| /external/compiler-rt/lib/tsan/go/ |
| D | tsan_go.cc | 135 ThreadState *thr = (ThreadState*)internal_alloc(MBlockThreadContex, in AllocGoroutine() local
144 ThreadState *thr = AllocGoroutine(); in __tsan_init() local
153 ThreadState *thr = main_thr; in __tsan_fini() local
162 void __tsan_read(ThreadState *thr, void *addr, void *pc) { in __tsan_read()
166 void __tsan_read_pc(ThreadState *thr, void *addr, uptr callpc, uptr pc) { in __tsan_read_pc()
174 void __tsan_write(ThreadState *thr, void *addr, void *pc) { in __tsan_write()
178 void __tsan_write_pc(ThreadState *thr, void *addr, uptr callpc, uptr pc) { in __tsan_write_pc()
186 void __tsan_read_range(ThreadState *thr, void *addr, uptr size, uptr pc) { in __tsan_read_range()
190 void __tsan_write_range(ThreadState *thr, void *addr, uptr size, uptr pc) { in __tsan_write_range()
194 void __tsan_func_enter(ThreadState *thr, void *pc) { in __tsan_func_enter()
[all …]
|
| /external/compiler-rt/lib/tsan/dd/ |
| D | dd_rtl.cc | 22 static u32 CurrentStackTrace(Thread *thr, uptr skip) { in CurrentStackTrace()
32 static void PrintStackTrace(Thread *thr, u32 stk) { in PrintStackTrace()
39 static void ReportDeadlock(Thread *thr, DDReport *rep) { in ReportDeadlock()
58 Callback::Callback(Thread *thr) in Callback()
100 void ThreadInit(Thread *thr) { in ThreadInit()
107 void ThreadDestroy(Thread *thr) { in ThreadDestroy()
112 void MutexBeforeLock(Thread *thr, uptr m, bool writelock) { in MutexBeforeLock()
125 void MutexAfterLock(Thread *thr, uptr m, bool writelock, bool trylock) { in MutexAfterLock()
138 void MutexBeforeUnlock(Thread *thr, uptr m, bool writelock) { in MutexBeforeUnlock()
149 void MutexDestroy(Thread *thr, uptr m) { in MutexDestroy()
|
| /external/compiler-rt/lib/tsan/rtl/ |
| D | tsan_rtl_mutex.cc | 29 ThreadState *thr; member
43 void DDMutexInit(ThreadState *thr, uptr pc, SyncVar *s) { in DDMutexInit()
49 static void ReportMutexMisuse(ThreadState *thr, uptr pc, ReportType typ, in ReportMutexMisuse()
65 void MutexCreate(ThreadState *thr, uptr pc, uptr addr, in MutexCreate()
84 void MutexDestroy(ThreadState *thr, uptr pc, uptr addr) { in MutexDestroy()
144 void MutexLock(ThreadState *thr, uptr pc, uptr addr, int rec, bool try_lock) { in MutexLock()
189 int MutexUnlock(ThreadState *thr, uptr pc, uptr addr, bool all) { in MutexUnlock()
232 void MutexReadLock(ThreadState *thr, uptr pc, uptr addr, bool trylock) { in MutexReadLock()
267 void MutexReadUnlock(ThreadState *thr, uptr pc, uptr addr) { in MutexReadUnlock()
299 void MutexReadOrWriteUnlock(ThreadState *thr, uptr pc, uptr addr) { in MutexReadOrWriteUnlock()
[all …]
|
| D | tsan_fd.cc | 50 static FdSync *allocsync(ThreadState *thr, uptr pc) { in allocsync()
63 static void unref(ThreadState *thr, uptr pc, FdSync *s) { in unref()
74 static FdDesc *fddesc(ThreadState *thr, uptr pc, int fd) { in fddesc()
94 static void init(ThreadState *thr, uptr pc, int fd, FdSync *s, in init()
128 void FdOnFork(ThreadState *thr, uptr pc) { in FdOnFork()
160 void FdAcquire(ThreadState *thr, uptr pc, int fd) { in FdAcquire()
171 void FdRelease(ThreadState *thr, uptr pc, int fd) { in FdRelease()
182 void FdAccess(ThreadState *thr, uptr pc, int fd) { in FdAccess()
190 void FdClose(ThreadState *thr, uptr pc, int fd, bool write) { in FdClose()
218 void FdFileCreate(ThreadState *thr, uptr pc, int fd) { in FdFileCreate()
[all …]
|
| D | tsan_mman.cc | 83 ThreadState *thr = cur_thread(); in ScopedGlobalProcessor() local
106 ThreadState *thr = cur_thread(); in ~ScopedGlobalProcessor() local
135 static void SignalUnsafeCall(ThreadState *thr, uptr pc) { in SignalUnsafeCall()
149 void *user_alloc(ThreadState *thr, uptr pc, uptr sz, uptr align, bool signal) { in user_alloc()
162 void *user_calloc(ThreadState *thr, uptr pc, uptr size, uptr n) { in user_calloc()
171 void user_free(ThreadState *thr, uptr pc, void *p, bool signal) { in user_free()
180 void OnUserAlloc(ThreadState *thr, uptr pc, uptr p, uptr sz, bool write) { in OnUserAlloc()
189 void OnUserFree(ThreadState *thr, uptr pc, uptr p, bool write) { in OnUserFree()
197 void *user_realloc(ThreadState *thr, uptr pc, void *p, uptr sz) { in user_realloc()
227 ThreadState *thr = cur_thread(); in invoke_malloc_hook() local
[all …]
|
| D | tsan_rtl_thread.cc | 49 ThreadState *thr; member
81 ThreadState *thr; member
185 static void ThreadCheckIgnore(ThreadState *thr) { in ThreadCheckIgnore()
194 static void ThreadCheckIgnore(ThreadState *thr) {} in ThreadCheckIgnore()
197 void ThreadFinalize(ThreadState *thr) { in ThreadFinalize()
215 int ThreadCount(ThreadState *thr) { in ThreadCount()
221 int ThreadCreate(ThreadState *thr, uptr pc, uptr uid, bool detached) { in ThreadCreate()
232 void ThreadStart(ThreadState *thr, int tid, uptr os_id) { in ThreadStart()
277 void ThreadFinish(ThreadState *thr) { in ThreadFinish()
297 int ThreadTid(ThreadState *thr, uptr pc, uptr uid) { in ThreadTid()
[all …]
|
| D | tsan_rtl.cc | 308 void Initialize(ThreadState *thr) { in Initialize()
387 int Finalize(ThreadState *thr) { in Finalize()
438 void ForkBefore(ThreadState *thr, uptr pc) { in ForkBefore()
443 void ForkParentAfter(ThreadState *thr, uptr pc) { in ForkParentAfter()
448 void ForkChildAfter(ThreadState *thr, uptr pc) { in ForkChildAfter()
472 void GrowShadowStack(ThreadState *thr) { in GrowShadowStack()
485 u32 CurrentStackId(ThreadState *thr, uptr pc) { in CurrentStackId()
505 void TraceSwitch(ThreadState *thr) { in TraceSwitch()
521 uptr TraceTopPC(ThreadState *thr) { in TraceTopPC()
563 void HandleRace(ThreadState *thr, u64 *shadow_mem, in HandleRace()
[all …]
|
| D | tsan_rtl_proc.cc | 47 void ProcWire(Processor *proc, ThreadState *thr) { in ProcWire()
54 void ProcUnwire(Processor *proc, ThreadState *thr) { in ProcUnwire()
|
| D | tsan_interface_atomic.cc | 223 static T AtomicLoad(ThreadState *thr, uptr pc, const volatile T *a, in AtomicLoad()
253 static void AtomicStore(ThreadState *thr, uptr pc, volatile T *a, T v, in AtomicStore()
276 static T AtomicRMW(ThreadState *thr, uptr pc, volatile T *a, T v, morder mo) { in AtomicRMW()
333 static T AtomicExchange(ThreadState *thr, uptr pc, volatile T *a, T v, in AtomicExchange()
339 static T AtomicFetchAdd(ThreadState *thr, uptr pc, volatile T *a, T v, in AtomicFetchAdd()
345 static T AtomicFetchSub(ThreadState *thr, uptr pc, volatile T *a, T v, in AtomicFetchSub()
351 static T AtomicFetchAnd(ThreadState *thr, uptr pc, volatile T *a, T v, in AtomicFetchAnd()
357 static T AtomicFetchOr(ThreadState *thr, uptr pc, volatile T *a, T v, in AtomicFetchOr()
363 static T AtomicFetchXor(ThreadState *thr, uptr pc, volatile T *a, T v, in AtomicFetchXor()
369 static T AtomicFetchNand(ThreadState *thr, uptr pc, volatile T *a, T v, in AtomicFetchNand()
[all …]
|
| D | tsan_platform_mac.cc | 82 ThreadState *thr = (ThreadState *)SignalSafeGetOrAllocate( in cur_thread() local
136 ThreadState *thr = cur_thread(); in my_pthread_introspection_hook() local
146 ThreadState *thr = cur_thread(); in my_pthread_introspection_hook() local
|
| D | tsan_symbolize.cc | 26 ThreadState *thr = cur_thread(); in EnterSymbolizer() local
33 ThreadState *thr = cur_thread(); in ExitSymbolizer() local
|
| D | tsan_sync.cc | 27 void SyncVar::Init(ThreadState *thr, uptr pc, uptr addr, u64 uid) { in Init()
63 void MetaMap::AllocBlock(ThreadState *thr, uptr pc, uptr p, uptr sz) { in AllocBlock()
196 SyncVar* MetaMap::GetOrCreateAndLock(ThreadState *thr, uptr pc, in GetOrCreateAndLock()
205 SyncVar* MetaMap::GetAndLock(ThreadState *thr, uptr pc, in GetAndLock()
|
| /external/compiler-rt/lib/tsan/tests/unit/ |
| D | tsan_sync_test.cc | 20 ThreadState *thr = cur_thread(); in TEST() local
35 ThreadState *thr = cur_thread(); in TEST() local
52 ThreadState *thr = cur_thread(); in TEST() local
75 ThreadState *thr = cur_thread(); in TEST() local
112 ThreadState *thr = cur_thread(); in TEST() local
|
| D | tsan_mman_test.cc | 38 ThreadState *thr = cur_thread(); in TEST() local
52 ThreadState *thr = cur_thread(); in TEST() local
97 ThreadState *thr = cur_thread(); in TEST() local
110 ThreadState *thr = cur_thread(); in TEST() local
144 ThreadState *thr = cur_thread(); in TEST() local
|
| D | tsan_stack_test.cc | 22 ThreadState thr(0, 0, 0, 0, 0, 0, 0, 0, 0); in TestStackTrace() local
51 ThreadState thr(0, 0, 0, 0, 0, 0, 0, 0, 0); in TestTrim() local
|
| /external/libaom/libaom/av1/encoder/x86/ |
| D | av1_quantize_avx2.c | 47 __m256i *thr, __m256i *qp) { in init_qp()
69 static INLINE void update_qp(int log_scale, __m256i *thr, __m256i *qp) { in update_qp()
107 static INLINE void quantize(const __m256i *thr, const __m256i *qp, __m256i *c, in quantize()
263 __m256i coeff, thr; in av1_quantize_fp_avx2() local
293 static INLINE void quantize_32x32(const __m256i *thr, const __m256i *qp, in quantize_32x32()
338 __m256i coeff, thr; in av1_quantize_fp_32x32_avx2() local
368 static INLINE void quantize_64x64(const __m256i *thr, const __m256i *qp, in quantize_64x64()
417 __m256i coeff, thr; in av1_quantize_fp_64x64_avx2() local
|
| /external/compiler-rt/test/tsan/ |
| D | malloc_stack.cc | 6 void *thr(void *a) { in thr() function
|
| /external/compiler-rt/test/asan/TestCases/Windows/ |
| D | thread_stack_array_left_oob.cc | 19 HANDLE thr = CreateThread(NULL, 0, thread_proc, NULL, 0, NULL); in main() local
|
| D | beginthreadex.cc | 15 HANDLE thr = (HANDLE)_beginthreadex(NULL, 0, thread_proc, NULL, 0, NULL); in main() local
|
| D | dll_thread_stack_array_left_oob.cc | 26 HANDLE thr = CreateThread(NULL, 0, thread_proc, NULL, 0, NULL); in test_function() local
|
| D | thread_suspended.cc | 15 HANDLE thr = CreateThread(NULL, 0, thread_proc, NULL, CREATE_SUSPENDED, NULL); in main() local
|
| D | thread_stack_array_right_oob.cc | 19 HANDLE thr = CreateThread(NULL, 0, thread_proc, NULL, 0, NULL); in main() local
|
| D | thread_simple.cc | 15 HANDLE thr = CreateThread(NULL, 0, thread_proc, NULL, 0, NULL); in main() local
|
| /external/compiler-rt/test/tsan/Linux/ |
| D | mutex_robust.cc | 10 void *thr(void *p) { in thr() function
|
| D | mutex_robust2.cc | 11 void *thr(void *p) { in thr() function
|