| /external/opencv3/modules/core/include/opencv2/core/cuda/ |
| warp_reduce.hpp | 55 __device__ __forceinline__ T warp_reduce(volatile T *ptr , const unsigned int tid = threadIdx.x)
57 const unsigned int lane = tid & 31; // index of thread in warp (0..31)
61 T partial = ptr[tid];
63 ptr[tid] = partial = partial + ptr[tid + 16];
64 ptr[tid] = partial = partial + ptr[tid + 8];
65 ptr[tid] = partial = partial + ptr[tid + 4];
66 ptr[tid] = partial = partial + ptr[tid + 2]
[all...] |
| block.hpp | 90 int tid = flattenedThreadId(); local
91 value += tid;
93 for(OutIt t = beg + tid; t < end; t += STRIDE, value += STRIDE)
134 int tid = flattenedThreadId(); local
135 T val = buffer[tid];
137 if (CTA_SIZE >= 1024) { if (tid < 512) buffer[tid] = val = op(val, buffer[tid + 512]); __syncthreads(); }
138 if (CTA_SIZE >= 512) { if (tid < 256) buffer[tid] = val = op(val, buffer[tid + 256]); __syncthreads();
156 int tid = flattenedThreadId(); local
[all...] |
| /hardware/qcom/gps/msmcobalt/utils/platform_lib_abstractions/loc_stub/src/ |
| loc_stub_sched_policy.cpp | 47 int set_sched_policy(int tid, SchedPolicy policy)
|
| /external/valgrind/coregrind/ |
| m_threadstate.c | 56 ThreadId tid; local
62 for (tid = 1; tid < VG_N_THREADS; tid++) {
64 ANNOTATE_BENIGN_RACE_SIZED(&VG_(threads)[tid].status,
65 sizeof(VG_(threads)[tid].status), ""));
67 ANNOTATE_BENIGN_RACE_SIZED(&VG_(threads)[tid].os_state.exitcode,
68 sizeof(VG_(threads)[tid].os_state.exitcode),
97 ThreadState *VG_(get_ThreadState)(ThreadId tid)
99 vg_assert(tid >= 0 && tid < VG_N_THREADS)
140 ThreadId tid; local
154 ThreadId tid; local
167 ThreadId tid; local
[all...] |
| pub_core_replacemalloc.h | 44 void* (*tl_malloc) (ThreadId tid, SizeT n);
45 void* (*tl___builtin_new) (ThreadId tid, SizeT n);
46 void* (*tl___builtin_vec_new) (ThreadId tid, SizeT n);
47 void* (*tl_memalign) (ThreadId tid, SizeT align, SizeT n);
48 void* (*tl_calloc) (ThreadId tid, SizeT nmemb, SizeT n);
49 void (*tl_free) (ThreadId tid, void* p);
50 void (*tl___builtin_delete) (ThreadId tid, void* p);
51 void (*tl___builtin_vec_delete)(ThreadId tid, void* p);
52 void* (*tl_realloc) (ThreadId tid, void* p, SizeT size);
53 SizeT (*tl_malloc_usable_size) (ThreadId tid, void* payload)
[all...] |
| pub_core_coredump.h | 41 extern void VG_(make_coredump) ( ThreadId tid, const vki_siginfo_t *si,
|
| pub_core_signals.h | 58 extern SysRes VG_(do_sys_sigaltstack) ( ThreadId tid, vki_stack_t* ss,
63 extern SysRes VG_(do_sys_sigprocmask) ( ThreadId tid, Int how,
68 ( ThreadId tid, /* OUT */ vki_sigset_t* saved_mask );
75 extern void VG_(synth_fault) (ThreadId tid);
76 extern void VG_(synth_fault_mapping)(ThreadId tid, Addr addr);
77 extern void VG_(synth_fault_perms) (ThreadId tid, Addr addr);
78 extern void VG_(synth_sigill) (ThreadId tid, Addr addr);
79 extern void VG_(synth_sigtrap) (ThreadId tid);
80 extern void VG_(synth_sigbus) (ThreadId tid);
81 extern void VG_(synth_sigfpe) (ThreadId tid, UInt code)
[all...] |
| m_machine.c | 48 Addr VG_(get_IP) ( ThreadId tid ) {
49 return INSTR_PTR( VG_(threads)[tid].arch );
51 Addr VG_(get_SP) ( ThreadId tid ) {
52 return STACK_PTR( VG_(threads)[tid].arch );
54 Addr VG_(get_FP) ( ThreadId tid ) {
55 return FRAME_PTR( VG_(threads)[tid].arch );
58 void VG_(set_IP) ( ThreadId tid, Addr ip ) {
59 INSTR_PTR( VG_(threads)[tid].arch ) = ip;
61 void VG_(set_SP) ( ThreadId tid, Addr sp ) {
62 STACK_PTR( VG_(threads)[tid].arch ) = sp
418 ThreadId tid; local
[all...] |
| pub_core_syswrap.h | 45 extern void VG_(main_thread_wrapper_NORETURN)(ThreadId tid);
47 extern void VG_(client_syscall) ( ThreadId tid, UInt trc );
49 extern void VG_(post_syscall) ( ThreadId tid );
51 /* Clear this module's private state for thread 'tid' */
52 extern void VG_(clear_syscallInfo) ( Int tid );
55 extern Bool VG_(is_in_syscall) ( Int tid );
59 ThreadId tid,
68 extern Bool VG_(is_ip_in_blocking_syscall)(ThreadId tid, Addr ip);
91 extern void VG_(save_context)(ThreadId tid, vki_ucontext_t *uc,
93 extern void VG_(restore_context)(ThreadId tid, vki_ucontext_t *uc
[all...] |
| /external/opencv3/modules/cudev/include/opencv2/cudev/block/ |
| scan.hpp | 58 __device__ T blockScanInclusive(T data, volatile T* smem, uint tid)
63 T warpResult = warpScanInclusive(data, smem, tid);
69 if ((tid & (WARP_SIZE - 1)) == (WARP_SIZE - 1))
71 smem[tid >> LOG_WARP_SIZE] = warpResult;
76 if (tid < (THREADS_NUM / WARP_SIZE))
79 T val = smem[tid];
82 smem[tid] = warpScanExclusive(val, smem, tid);
88 return warpResult + smem[tid >> LOG_WARP_SIZE];
92 return warpScanInclusive(data, smem, tid);
[all...] |
| /frameworks/base/core/java/android/os/ |
| ISchedulingPolicyService.aidl | 28 * Move thread tid into appropriate cgroup and assign it priority prio.
29 * The thread group leader of tid must be pid.
32 int requestPriority(int pid, int tid, int prio);
|
| /hardware/qcom/gps/msmcobalt/utils/platform_lib_abstractions/loc_pla/src/ |
| platform_lib_sched_policy.cpp | 37 int platform_lib_abstraction_set_sched_policy(int tid, PLASchedPolicy policy)
39 return set_sched_policy(tid, (SchedPolicy)policy);
|
| /external/opencv3/modules/imgproc/src/opencl/ |
| clahe.cl | 50 inline int calc_lut(__local int* smem, int val, int tid)
52 smem[tid] = val;
55 if (tid == 0)
60 return smem[tid];
64 inline void reduce(volatile __local int* smem, int val, int tid)
66 smem[tid] = val;
69 if (tid < 128)
70 smem[tid] = val += smem[tid + 128];
73 if (tid < 64
[all...] |
| /bionic/libc/bionic/ |
| gettid.cpp | 34 return __get_thread()->tid;
|
| pthread_gettid_np.cpp | 32 return reinterpret_cast<pthread_internal_t*>(t)->tid;
|
| /ndk/tests/device/test-openmp/jni/ |
| openmp2.c | 8 int nthreads, tid; local
11 #pragma omp parallel default(shared) private(nthreads, tid)
15 tid = omp_get_thread_num();
16 printf("Hello World from thread = %d\n", tid);
18 if (tid == 0)
|
| /external/opencv3/modules/objdetect/src/opencl/ |
| objdetect_hog.cl | 147 int tid = (cell_y * CELLS_PER_BLOCK_Y + cell_x) * 12 + cell_thread_x;
148 if ((tid < cblock_hist_size) && (gid < blocks_total))
152 block_hist[tid] = final_hist[tid];
162 const int tid = get_local_id(0);
164 const int bid = tid / 36; /* block-hist id, (0 - 6) */
166 const int hid = tid - boffset; /* histogram bin id, (0 - 35) */
169 squares[tid] = elem * elem;
189 squares[tid] = elem * elem;
212 unsigned int tid = get_local_id(0)
[all...] |
| /system/core/libbacktrace/ |
| thread_utils.c | 25 int tgkill(int tgid, int tid, int sig) {
26 return syscall(__NR_tgkill, tgid, tid, sig);
|
| /external/valgrind/coregrind/m_coredump/ |
| coredump-macho.c | 38 void VG_(make_coredump)(ThreadId tid, const vki_siginfo_t *si, ULong max_size)
|
| /system/core/include/cutils/ |
| sched_policy.h | 38 extern int set_cpuset_policy(int tid, SchedPolicy policy);
40 /* Assign thread tid to the cgroup associated with the specified policy.
43 * On platforms which support gettid(), zero tid means current thread.
46 extern int set_sched_policy(int tid, SchedPolicy policy);
48 /* Return the policy associated with the cgroup of thread tid via policy pointer.
49 * On platforms which support gettid(), zero tid means current thread.
52 extern int get_sched_policy(int tid, SchedPolicy *policy);
|
| debugger.h | 44 pid_t tid; member in struct:__anon74239
53 int dump_tombstone(pid_t tid, char* pathbuf, size_t pathlen);
61 int dump_tombstone_timeout(pid_t tid, char* pathbuf, size_t pathlen, int timeout_secs);
66 int dump_backtrace_to_file(pid_t tid, int fd);
73 int dump_backtrace_to_file_timeout(pid_t tid, int fd, int timeout_secs);
|
| /external/valgrind/drd/tests/ |
| annotate_hb_race.c | 31 pthread_t tid[2]; local
35 pthread_create(&tid[0], 0, thread_func, &result[0]);
36 pthread_create(&tid[1], 0, thread_func, &result[1]);
42 pthread_join(tid[0], NULL);
43 pthread_join(tid[1], NULL);
|
| pth_cancel_locked.c | 27 pthread_t tid; local
36 pthread_create(&tid, 0, &thread, 0);
43 pthread_cancel(tid);
46 pthread_join(tid, 0);
49 pthread_cancel(tid);
|
| /external/valgrind/drd/ |
| drd_thread.h | 146 DrdThreadId DRD_(VgThreadIdToDrdThreadId)(const ThreadId tid);
147 DrdThreadId DRD_(NewVgThreadIdToDrdThreadId)(const ThreadId tid);
148 DrdThreadId DRD_(PtThreadIdToDrdThreadId)(const PThreadId tid);
149 ThreadId DRD_(DrdThreadIdToVgThreadId)(const DrdThreadId tid);
154 void DRD_(thread_delete)(const DrdThreadId tid, Bool detached);
155 void DRD_(thread_finished)(const DrdThreadId tid);
156 void DRD_(drd_thread_atfork_child)(const DrdThreadId tid);
157 void DRD_(thread_pre_cancel)(const DrdThreadId tid);
158 void DRD_(thread_set_stack_startup)(const DrdThreadId tid,
160 Addr DRD_(thread_get_stack_min)(const DrdThreadId tid);
[all...] |
| drd_thread.c | 48 static void thread_append_segment(const DrdThreadId tid, Segment* const sg);
49 static void thread_discard_segment(const DrdThreadId tid, Segment* const sg);
51 const DrdThreadId tid);
52 static Bool thread_conflict_set_up_to_date(const DrdThreadId tid);
164 DrdThreadId DRD_(VgThreadIdToDrdThreadId)(const ThreadId tid)
168 if (tid == VG_INVALID_THREADID)
174 && DRD_(g_threadinfo)[i].vg_threadid == tid)
184 static DrdThreadId DRD_(VgThreadIdToNewDrdThreadId)(const ThreadId tid)
188 tl_assert(DRD_(VgThreadIdToDrdThreadId)(tid) == DRD_INVALID_THREADID);
198 DRD_(g_threadinfo)[i].vg_threadid = tid;
[all...] |
