Searched refs:thr (Results 1 - 25 of 96) sorted by relevance

1234

/openbsd-current/gnu/gcc/libgomp/testsuite/libgomp.c/
H A Dcopyin-1.c8 int thr = 32; variable
9 #pragma omp threadprivate (thr)
19 #pragma omp parallel copyin (thr) reduction (||:l)
21 l = thr != 32;
22 thr = omp_get_thread_num () + 11;
25 if (l || thr != 11)
29 l = thr != omp_get_thread_num () + 11;
H A Dcopyin-2.c8 struct { int t; char buf[64]; } thr = { 32, "" }; variable in typeref:struct:__anon412
9 #pragma omp threadprivate (thr)
19 #pragma omp parallel copyin (thr) reduction (||:l)
21 l = thr.t != 32;
22 thr.t = omp_get_thread_num () + 11;
25 if (l || thr.t != 11)
29 l = thr.t != omp_get_thread_num () + 11;
H A Dcopyin-3.c8 int thr; variable
9 #pragma omp threadprivate (thr)
14 return l || (thr != omp_get_thread_num () * 2);
25 thr = 8;
27 #pragma omp parallel copyin (thr)
33 l = thr != 8;
34 thr = omp_get_thread_num () * 2;
/openbsd-current/gnu/gcc/libgomp/testsuite/libgomp.c++/
H A Dcopyin-1.C8 int thr = 32; variable
9 #pragma omp threadprivate (thr)
19 #pragma omp parallel copyin (thr) reduction (||:l)
21 l = thr != 32;
22 thr = omp_get_thread_num () + 11;
25 if (l || thr != 11)
29 l = thr != omp_get_thread_num () + 11;
H A Dcopyin-2.C8 struct S { int t; char buf[64]; } thr = { 32, "" }; variable in typeref:struct:S
9 #pragma omp threadprivate (thr)
19 #pragma omp parallel copyin (thr) reduction (||:l)
21 l = thr.t != 32;
22 thr.t = omp_get_thread_num () + 11;
25 if (l || thr.t != 11)
29 l = thr.t != omp_get_thread_num () + 11;
/openbsd-current/gnu/gcc/libgomp/
H A Dbarrier.c36 struct gomp_thread *thr = gomp_thread (); local
37 struct gomp_team *team = thr->ts.team;
H A Dsingle.c54 struct gomp_thread *thr = gomp_thread (); local
60 gomp_mutex_unlock (&thr->ts.work_share->lock);
66 gomp_barrier_wait (&thr->ts.team->barrier);
68 ret = thr->ts.work_share->copyprivate;
81 struct gomp_thread *thr = gomp_thread (); local
82 struct gomp_team *team = thr->ts.team;
86 thr->ts.work_share->copyprivate = data;
H A Dordered.c40 struct gomp_thread *thr = gomp_thread (); local
41 struct gomp_team *team = thr->ts.team;
42 struct gomp_work_share *ws = thr->ts.work_share;
52 ws->ordered_team_ids[index] = thr->ts.team_id;
58 gomp_sem_post (team->ordered_release[thr->ts.team_id]);
71 struct gomp_thread *thr = gomp_thread (); local
72 struct gomp_team *team = thr->ts.team;
73 struct gomp_work_share *ws = thr->ts.work_share;
106 struct gomp_thread *thr = gomp_thread (); local
107 struct gomp_team *team = thr
154 struct gomp_thread *thr = gomp_thread (); local
172 struct gomp_thread *thr = gomp_thread (); local
196 struct gomp_thread *thr = gomp_thread (); local
[all...]
H A Dteam.c73 struct gomp_thread *thr; local
78 thr = &gomp_tls_data;
81 thr = &local_thr;
82 pthread_setspecific (gomp_tls_key, thr);
84 gomp_sem_init (&thr->release, 0);
89 thr->ts = data->ts;
91 thr->ts.team->ordered_release[thr->ts.team_id] = &thr->release;
95 gomp_barrier_wait (&thr
182 struct gomp_thread *thr, *nthr; local
310 struct gomp_thread *thr = gomp_thread (); local
326 struct gomp_thread *thr; local
[all...]
/openbsd-current/gnu/llvm/compiler-rt/lib/tsan/rtl/
H A Dtsan_fd.h41 void FdAcquire(ThreadState *thr, uptr pc, int fd);
42 void FdRelease(ThreadState *thr, uptr pc, int fd);
43 void FdAccess(ThreadState *thr, uptr pc, int fd);
44 void FdClose(ThreadState *thr, uptr pc, int fd, bool write = true);
45 void FdFileCreate(ThreadState *thr, uptr pc, int fd);
46 void FdDup(ThreadState *thr, uptr pc, int oldfd, int newfd, bool write);
47 void FdPipeCreate(ThreadState *thr, uptr pc, int rfd, int wfd);
48 void FdEventCreate(ThreadState *thr, uptr pc, int fd);
49 void FdSignalCreate(ThreadState *thr, uptr pc, int fd);
50 void FdInotifyCreate(ThreadState *thr, upt
[all...]
H A Dtsan_rtl_thread.cpp24 ThreadContext::ThreadContext(Tid tid) : ThreadContextBase(tid), thr(), sync() {}
74 static void ThreadCheckIgnore(ThreadState *thr) { argument
77 if (thr->ignore_reads_and_writes)
78 ReportIgnoresEnabled(thr->tctx, &thr->mop_ignore_set);
79 if (thr->ignore_sync)
80 ReportIgnoresEnabled(thr->tctx, &thr->sync_ignore_set);
83 static void ThreadCheckIgnore(ThreadState *thr) {} argument
86 void ThreadFinalize(ThreadState *thr) { argument
104 ThreadCount(ThreadState *thr) argument
116 ThreadCreate(ThreadState *thr, uptr pc, uptr uid, bool detached) argument
145 ThreadState *thr; member in struct:__tsan::OnStartedArgs
152 ThreadStart(ThreadState *thr, Tid tid, tid_t os_id, ThreadType thread_type) argument
214 ThreadFinish(ThreadState *thr) argument
284 ThreadConsumeTid(ThreadState *thr, uptr pc, uptr uid) argument
293 ThreadJoin(ThreadState *thr, uptr pc, Tid tid) argument
316 ThreadDetach(ThreadState *thr, uptr pc, Tid tid) argument
323 ThreadNotJoined(ThreadState *thr, uptr pc, Tid tid, uptr uid) argument
328 ThreadSetName(ThreadState *thr, const char *name) argument
340 FiberCreate(ThreadState *thr, uptr pc, unsigned flags) argument
351 FiberDestroy(ThreadState *thr, uptr pc, ThreadState *fiber) argument
358 FiberSwitch(ThreadState *thr, uptr pc, ThreadState *fiber, unsigned flags) argument
[all...]
H A Dtsan_rtl_proc.cpp24 proc->thr = nullptr;
34 CHECK_EQ(proc->thr, nullptr);
45 void ProcWire(Processor *proc, ThreadState *thr) { argument
46 CHECK_EQ(thr->proc1, nullptr);
47 CHECK_EQ(proc->thr, nullptr);
48 thr->proc1 = proc;
49 proc->thr = thr;
52 void ProcUnwire(Processor *proc, ThreadState *thr) { argument
53 CHECK_EQ(thr
[all...]
H A Dtsan_fd.cpp56 static FdSync *allocsync(ThreadState *thr, uptr pc) { argument
57 FdSync *s = (FdSync*)user_alloc_internal(thr, pc, sizeof(FdSync),
69 static void unref(ThreadState *thr, uptr pc, FdSync *s) { argument
75 user_free(thr, pc, s, false);
80 static FdDesc *fddesc(ThreadState *thr, uptr pc, int fd) { argument
88 void *p = user_alloc_internal(thr, pc, size, kDefaultAlignment, false);
90 MemoryResetRange(thr, (uptr)&fddesc, (uptr)p, size);
94 user_free(thr, pc, p, false);
101 static void init(ThreadState *thr, uptr pc, int fd, FdSync *s, argument
103 FdDesc *d = fddesc(thr, p
145 FdOnFork(ThreadState *thr, uptr pc) argument
178 FdAcquire(ThreadState *thr, uptr pc, int fd) argument
189 FdRelease(ThreadState *thr, uptr pc, int fd) argument
202 FdAccess(ThreadState *thr, uptr pc, int fd) argument
210 FdClose(ThreadState *thr, uptr pc, int fd, bool write) argument
253 FdFileCreate(ThreadState *thr, uptr pc, int fd) argument
260 FdDup(ThreadState *thr, uptr pc, int oldfd, int newfd, bool write) argument
271 FdPipeCreate(ThreadState *thr, uptr pc, int rfd, int wfd) argument
279 FdEventCreate(ThreadState *thr, uptr pc, int fd) argument
286 FdSignalCreate(ThreadState *thr, uptr pc, int fd) argument
293 FdInotifyCreate(ThreadState *thr, uptr pc, int fd) argument
300 FdPollCreate(ThreadState *thr, uptr pc, int fd) argument
307 FdPollAdd(ThreadState *thr, uptr pc, int epfd, int fd) argument
331 FdSocketCreate(ThreadState *thr, uptr pc, int fd) argument
339 FdSocketAccept(ThreadState *thr, uptr pc, int fd, int newfd) argument
348 FdSocketConnecting(ThreadState *thr, uptr pc, int fd) argument
356 FdSocketConnect(ThreadState *thr, uptr pc, int fd) argument
[all...]
H A Dtsan_rtl.cpp79 static TracePart* TracePartAlloc(ThreadState* thr) { argument
84 Trace* trace = &thr->tctx->trace;
88 DPrintf("#%d: TracePartAlloc: part=%p\n", thr->tid, part);
151 bool attached = tctx->thr && tctx->thr->slot;
171 &tctx->thr->trace_pos,
180 if (tctx->thr && !tctx->thr->slot) {
181 atomic_store_relaxed(&tctx->thr->trace_pos, 0);
182 tctx->thr
295 SlotAttachAndLock(ThreadState* thr) argument
319 SlotDetachImpl(ThreadState* thr, bool exiting) argument
351 SlotDetach(ThreadState* thr) argument
373 SlotAttachAndLock(thr); variable
376 SlotUnlock(ThreadState* thr) argument
568 UnmapShadow(ThreadState *thr, uptr addr, uptr size) argument
669 ThreadState* thr = cur_thread(); local
680 Initialize(ThreadState *thr) argument
767 Finalize(ThreadState *thr) argument
811 SlotDetach(thr); variable
843 SlotAttachAndLock(thr); variable
844 SlotUnlock(thr); variable
848 ForkParentAfter(ThreadState* thr, uptr pc) argument
850 ForkChildAfter(ThreadState* thr, uptr pc, bool start_thread) argument
875 GrowShadowStack(ThreadState *thr) argument
887 CurrentStackId(ThreadState *thr, uptr pc) argument
909 TraceSkipGap(ThreadState* thr) argument
940 TraceSwitchPart(ThreadState* thr) argument
957 TraceSwitchPartImpl(ThreadState* thr) argument
1033 ThreadIgnoreBegin(ThreadState* thr, uptr pc) argument
1044 ThreadIgnoreEnd(ThreadState *thr) argument
1059 ThreadState *thr = cur_thread(); local
1064 ThreadIgnoreSyncBegin(ThreadState *thr, uptr pc) argument
1074 ThreadIgnoreSyncEnd(ThreadState *thr) argument
[all...]
H A Dtsan_rtl_mutex.cpp25 void ReportDeadlock(ThreadState *thr, uptr pc, DDReport *r);
26 void ReportDestroyLocked(ThreadState *thr, uptr pc, uptr addr,
30 ThreadState *thr; member in struct:__tsan::final
33 Callback(ThreadState *thr, uptr pc) argument
34 : thr(thr)
36 DDCallback::pt = thr->proc()->dd_pt;
37 DDCallback::lt = thr->dd_lt;
40 StackID Unwind() override { return CurrentStackId(thr, pc); }
41 int UniqueTid() override { return thr
44 DDMutexInit(ThreadState *thr, uptr pc, SyncVar *s) argument
50 ReportMutexMisuse(ThreadState *thr, uptr pc, ReportType typ, uptr addr, StackID creation_stack_id) argument
68 RecordMutexLock(ThreadState *thr, uptr pc, uptr addr, StackID stack_id, bool write) argument
80 RecordMutexUnlock(ThreadState *thr, uptr addr) argument
86 MutexCreate(ThreadState *thr, uptr pc, uptr addr, u32 flagz) argument
98 MutexDestroy(ThreadState *thr, uptr pc, uptr addr, u32 flagz) argument
140 MutexPreLock(ThreadState *thr, uptr pc, uptr addr, u32 flagz) argument
158 MutexPostLock(ThreadState *thr, uptr pc, uptr addr, u32 flagz, int rec) argument
216 MutexUnlock(ThreadState *thr, uptr pc, uptr addr, u32 flagz) argument
266 MutexPreReadLock(ThreadState *thr, uptr pc, uptr addr, u32 flagz) argument
281 MutexPostReadLock(ThreadState *thr, uptr pc, uptr addr, u32 flagz) argument
324 MutexReadUnlock(ThreadState *thr, uptr pc, uptr addr) argument
365 MutexReadOrWriteUnlock(ThreadState *thr, uptr pc, uptr addr) argument
419 MutexRepair(ThreadState *thr, uptr pc, uptr addr) argument
428 MutexInvalidAccess(ThreadState *thr, uptr pc, uptr addr) argument
441 Acquire(ThreadState *thr, uptr pc, uptr addr) argument
455 AcquireGlobal(ThreadState *thr) argument
463 Release(ThreadState *thr, uptr pc, uptr addr) argument
476 ReleaseStore(ThreadState *thr, uptr pc, uptr addr) argument
489 ReleaseStoreAcquire(ThreadState *thr, uptr pc, uptr addr) argument
502 IncrementEpoch(ThreadState *thr) argument
516 AfterSleep(ThreadState *thr, uptr pc) argument
528 ReportDeadlock(ThreadState *thr, uptr pc, DDReport *r) argument
554 ReportDestroyLocked(ThreadState *thr, uptr pc, uptr addr, FastState last_lock, StackID creation_stack_id) argument
[all...]
H A Dtsan_mman.cpp85 ThreadState *thr = cur_thread(); local
86 if (thr->proc())
103 ProcWire(gp->proc, thr);
108 ThreadState *thr = cur_thread(); local
109 if (thr->proc() != gp->proc)
111 ProcUnwire(gp->proc, thr);
163 static void SignalUnsafeCall(ThreadState *thr, uptr pc) { argument
164 if (atomic_load_relaxed(&thr->in_signal_handler) == 0 ||
165 !ShouldReport(thr, ReportTypeSignalUnsafe))
168 ObtainCurrentStack(thr, p
178 user_alloc_internal(ThreadState *thr, uptr pc, uptr sz, uptr align, bool signal) argument
210 user_free(ThreadState *thr, uptr pc, void *p, bool signal) argument
219 user_alloc(ThreadState *thr, uptr pc, uptr sz) argument
223 user_calloc(ThreadState *thr, uptr pc, uptr size, uptr n) argument
236 user_reallocarray(ThreadState *thr, uptr pc, void *p, uptr size, uptr n) argument
246 OnUserAlloc(ThreadState *thr, uptr pc, uptr p, uptr sz, bool write) argument
264 OnUserFree(ThreadState *thr, uptr pc, uptr p, bool write) argument
279 user_realloc(ThreadState *thr, uptr pc, void *p, uptr sz) argument
297 user_memalign(ThreadState *thr, uptr pc, uptr align, uptr sz) argument
308 user_posix_memalign(ThreadState *thr, uptr pc, void **memptr, uptr align, uptr sz) argument
325 user_aligned_alloc(ThreadState *thr, uptr pc, uptr align, uptr sz) argument
336 user_valloc(ThreadState *thr, uptr pc, uptr sz) argument
340 user_pvalloc(ThreadState *thr, uptr pc, uptr sz) argument
366 ThreadState *thr = cur_thread(); local
373 ThreadState *thr = cur_thread(); local
380 ThreadState *thr = cur_thread(); local
390 ThreadState *thr = cur_thread(); local
437 ThreadState *thr = cur_thread(); local
[all...]
H A Dtsan_rtl.h114 ThreadState *thr; // currently wired thread, or nullptr member in struct:__tsan::Processor
143 ThreadState *thr; member in struct:__tsan::TidSlot
242 void set_cur_thread(ThreadState *thr);
252 ThreadState *thr = reinterpret_cast<ThreadState *>(cur_thread_placeholder); local
253 if (UNLIKELY(!thr->current))
254 thr->current = thr;
255 return thr->current;
257 inline void set_cur_thread(ThreadState *thr) { argument
258 reinterpret_cast<ThreadState *>(cur_thread_placeholder)->current = thr;
268 ThreadState *thr; member in class:__tsan::final
465 ObtainCurrentStack(ThreadState *thr, uptr toppc, StackTraceTy *stack, uptr *tag = nullptr) argument
536 MemoryAccessRange(ThreadState *thr, uptr pc, uptr addr, uptr size, bool is_write) argument
631 SlotLocker(ThreadState *thr, bool recursive = false) argument
657 SlotUnlocker(ThreadState *thr) argument
672 ProcessPendingSignals(ThreadState *thr) argument
680 LazyInitialize(ThreadState *thr) argument
699 TraceAcquire(ThreadState *thr, EventT **ev) argument
729 TraceRelease(ThreadState *thr, EventT *evp) argument
735 TraceEvent(ThreadState *thr, EventT ev) argument
746 TryTraceFunc(ThreadState *thr, uptr pc = 0) argument
780 FuncEntry(ThreadState *thr, uptr pc) argument
796 FuncExit(ThreadState *thr) argument
[all...]
H A Dtsan_interface.cpp31 ThreadState *thr = cur_thread(); local
32 MemoryAccess(thr, pc_no_pac, (uptr)addr, 8, kAccessRead);
33 MemoryAccess(thr, pc_no_pac, (uptr)addr + 8, 8, kAccessRead);
38 ThreadState *thr = cur_thread(); local
39 MemoryAccess(thr, pc_no_pac, (uptr)addr, 8, kAccessWrite);
40 MemoryAccess(thr, pc_no_pac, (uptr)addr + 8, 8, kAccessWrite);
47 ThreadState *thr = cur_thread(); local
48 UnalignedMemoryAccess(thr, pc, (uptr)addr, 8, kAccessRead);
49 UnalignedMemoryAccess(thr, pc, (uptr)addr + 8, 8, kAccessRead);
54 ThreadState *thr local
[all...]
/openbsd-current/gnu/llvm/compiler-rt/lib/tsan/dd/
H A Ddd_rtl.cpp21 static u32 CurrentStackTrace(Thread *thr, uptr skip) { argument
23 thr->ignore_interceptors = true;
25 thr->ignore_interceptors = false;
31 static void PrintStackTrace(Thread *thr, u32 stk) { argument
33 thr->ignore_interceptors = true;
35 thr->ignore_interceptors = false;
38 static void ReportDeadlock(Thread *thr, DDReport *rep) { argument
47 PrintStackTrace(thr, rep->loop[i].stk[1]);
51 PrintStackTrace(thr, rep->loop[i].stk[0]);
57 Callback::Callback(Thread *thr) argument
99 ThreadInit(Thread *thr) argument
106 ThreadDestroy(Thread *thr) argument
111 MutexBeforeLock(Thread *thr, uptr m, bool writelock) argument
124 MutexAfterLock(Thread *thr, uptr m, bool writelock, bool trylock) argument
137 MutexBeforeUnlock(Thread *thr, uptr m, bool writelock) argument
148 MutexDestroy(Thread *thr, uptr m) argument
[all...]
H A Ddd_rtl.h34 Thread *thr; member in struct:__dsan::final
36 Callback(Thread *thr);
57 void ThreadInit(Thread *thr);
58 void ThreadDestroy(Thread *thr);
60 void MutexBeforeLock(Thread *thr, uptr m, bool writelock);
61 void MutexAfterLock(Thread *thr, uptr m, bool writelock, bool trylock);
62 void MutexBeforeUnlock(Thread *thr, uptr m, bool writelock);
63 void MutexDestroy(Thread *thr, uptr m);
/openbsd-current/gnu/llvm/compiler-rt/lib/tsan/go/
H A Dtsan_go.cpp143 auto *thr = (ThreadState *)Alloc(sizeof(ThreadState)); local
144 internal_memset(thr, 0, sizeof(*thr));
145 return thr;
151 ThreadState *thr = AllocGoroutine(); local
152 main_thr = *thrp = thr;
153 Initialize(thr);
154 *procp = thr->proc1;
160 ThreadState *thr = main_thr; local
161 int res = Finalize(thr);
169 __tsan_read(ThreadState *thr, void *addr, void *pc) argument
173 __tsan_read_pc(ThreadState *thr, void *addr, uptr callpc, uptr pc) argument
181 __tsan_write(ThreadState *thr, void *addr, void *pc) argument
185 __tsan_write_pc(ThreadState *thr, void *addr, uptr callpc, uptr pc) argument
193 __tsan_read_range(ThreadState *thr, void *addr, uptr size, uptr pc) argument
197 __tsan_write_range(ThreadState *thr, void *addr, uptr size, uptr pc) argument
201 __tsan_func_enter(ThreadState *thr, void *pc) argument
205 __tsan_func_exit(ThreadState *thr) argument
209 __tsan_malloc(ThreadState *thr, uptr pc, uptr p, uptr sz) argument
221 ThreadState *thr = AllocGoroutine(); local
227 __tsan_go_end(ThreadState *thr) argument
240 __tsan_acquire(ThreadState *thr, void *addr) argument
244 __tsan_release_acquire(ThreadState *thr, void *addr) argument
248 __tsan_release(ThreadState *thr, void *addr) argument
252 __tsan_release_merge(ThreadState *thr, void *addr) argument
256 __tsan_finalizer_goroutine(ThreadState *thr) argument
258 __tsan_mutex_before_lock(ThreadState *thr, uptr addr, uptr write) argument
265 __tsan_mutex_after_lock(ThreadState *thr, uptr addr, uptr write) argument
272 __tsan_mutex_before_unlock(ThreadState *thr, uptr addr, uptr write) argument
279 __tsan_go_ignore_sync_begin(ThreadState *thr) argument
283 __tsan_go_ignore_sync_end(ThreadState *thr) argument
[all...]
/openbsd-current/gnu/usr.bin/binutils/gdb/testsuite/gdb.threads/
H A Dswitch-threads.c39 pthread_t thr; local
43 pthread_create (&thr, NULL, thread_func, NULL);
44 pthread_join (thr, &ret);
/openbsd-current/gnu/llvm/compiler-rt/lib/tsan/tests/unit/
H A Dtsan_mman_test.cpp37 ThreadState *thr = cur_thread(); local
39 char *p = (char*)user_alloc(thr, pc, 10);
41 char *p2 = (char*)user_alloc(thr, pc, 20);
46 user_free(thr, pc, p);
47 user_free(thr, pc, p2);
51 ThreadState *thr = cur_thread(); local
54 void *p = user_realloc(thr, pc, 0, 0);
58 user_free(thr, pc, p);
61 void *p = user_realloc(thr, pc, 0, 100);
64 user_free(thr, p
98 ThreadState *thr = cur_thread(); local
111 ThreadState *thr = cur_thread(); local
140 ThreadState *thr = cur_thread(); local
162 ThreadState *thr = cur_thread(); local
179 ThreadState *thr = cur_thread(); local
189 ThreadState *thr = cur_thread(); local
[all...]
H A Dtsan_trace_test.cpp37 for (auto *&thr : threads) {
38 thr = static_cast<ThreadState *>(
42 ProcWire(proc, thr);
43 ThreadStart(thr, tid, 0, ThreadType::Fiber);
55 auto *thr = threads[i]; local
57 Processor *proc = thr->proc();
58 ThreadFinish(thr);
59 ProcUnwire(proc, thr);
61 UnmapOrDie(thr, sizeof(ThreadState));
74 ThreadArray<1> thr; local
129 ThreadArray<1> thr; local
172 ThreadArray<1> thr; local
202 ThreadArray<1> thr; local
247 ThreadArray<1> thr; local
[all...]
/openbsd-current/gnu/usr.bin/gcc/gcc/testsuite/gcc.dg/tls/
H A Dopt-2.c9 __thread int thr; variable
31 int e = thr;
35 thr = e;
41 thr = 22;

Completed in 128 milliseconds

1234