/external/llvm-project/openmp/runtime/src/ |
D | kmp_lock.cpp | 72 static kmp_int32 __kmp_get_tas_lock_owner(kmp_tas_lock_t *lck) { in __kmp_get_tas_lock_owner() argument 73 return KMP_LOCK_STRIP(KMP_ATOMIC_LD_RLX(&lck->lk.poll)) - 1; in __kmp_get_tas_lock_owner() 76 static inline bool __kmp_is_tas_lock_nestable(kmp_tas_lock_t *lck) { in __kmp_is_tas_lock_nestable() argument 77 return lck->lk.depth_locked != -1; in __kmp_is_tas_lock_nestable() 81 __kmp_acquire_tas_lock_timed_template(kmp_tas_lock_t *lck, kmp_int32 gtid) { in __kmp_acquire_tas_lock_timed_template() argument 85 kmp_uint32 curr = KMP_LOCK_STRIP(lck->lk.poll); in __kmp_acquire_tas_lock_timed_template() 87 __kmp_printf("LOCK CONTENTION: %p\n", lck); in __kmp_acquire_tas_lock_timed_template() 94 if (KMP_ATOMIC_LD_RLX(&lck->lk.poll) == tas_free && in __kmp_acquire_tas_lock_timed_template() 95 __kmp_atomic_compare_store_acq(&lck->lk.poll, tas_free, tas_busy)) { in __kmp_acquire_tas_lock_timed_template() 96 KMP_FSYNC_ACQUIRED(lck); in __kmp_acquire_tas_lock_timed_template() [all …]
|
D | kmp_lock.h | 144 extern int __kmp_acquire_tas_lock(kmp_tas_lock_t *lck, kmp_int32 gtid); 145 extern int __kmp_test_tas_lock(kmp_tas_lock_t *lck, kmp_int32 gtid); 146 extern int __kmp_release_tas_lock(kmp_tas_lock_t *lck, kmp_int32 gtid); 147 extern void __kmp_init_tas_lock(kmp_tas_lock_t *lck); 148 extern void __kmp_destroy_tas_lock(kmp_tas_lock_t *lck); 150 extern int __kmp_acquire_nested_tas_lock(kmp_tas_lock_t *lck, kmp_int32 gtid); 151 extern int __kmp_test_nested_tas_lock(kmp_tas_lock_t *lck, kmp_int32 gtid); 152 extern int __kmp_release_nested_tas_lock(kmp_tas_lock_t *lck, kmp_int32 gtid); 153 extern void __kmp_init_nested_tas_lock(kmp_tas_lock_t *lck); 154 extern void __kmp_destroy_nested_tas_lock(kmp_tas_lock_t *lck); [all …]
|
D | tsan_annotations.h | 85 #define ANNOTATE_RWLOCK_CREATE(lck) \ argument 86 AnnotateRWLockCreate(__FILE__, __LINE__, (uptr)lck) 87 #define ANNOTATE_RWLOCK_RELEASED(lck) \ argument 88 AnnotateRWLockAcquired(__FILE__, __LINE__, (uptr)lck, 1) 89 #define ANNOTATE_RWLOCK_ACQUIRED(lck) \ argument 90 AnnotateRWLockReleased(__FILE__, __LINE__, (uptr)lck, 1) 104 #define ANNOTATE_RWLOCK_CREATE(lck) argument 105 #define ANNOTATE_RWLOCK_RELEASED(lck) argument 106 #define ANNOTATE_RWLOCK_ACQUIRED(lck) argument 120 #define ANNOTATE_QUEUING_CREATE(lck) argument [all …]
|
D | kmp_csupport.cpp | 852 ompt_wait_id_t lck; in __kmpc_ordered() local 857 lck = (ompt_wait_id_t)(uintptr_t)&team->t.t_ordered.dt.t_value; in __kmpc_ordered() 859 th->th.ompt_thread_info.wait_id = lck; in __kmpc_ordered() 866 ompt_mutex_ordered, omp_lock_hint_none, kmp_mutex_impl_spin, lck, in __kmpc_ordered() 886 ompt_mutex_ordered, (ompt_wait_id_t)(uintptr_t)lck, codeptr_ra); in __kmpc_ordered() 942 kmp_indirect_lock_t **lck; in __kmp_init_indirect_csptr() local 943 lck = (kmp_indirect_lock_t **)crit; in __kmp_init_indirect_csptr() 953 int status = KMP_COMPARE_AND_STORE_PTR(lck, nullptr, ilk); in __kmp_init_indirect_csptr() 962 KMP_DEBUG_ASSERT(*lck != NULL); in __kmp_init_indirect_csptr() 1086 kmp_user_lock_p lck = (kmp_user_lock_p)TCR_PTR(*lck_pp); in __kmp_get_critical_section_ptr() local [all …]
|
D | kmp_error.cpp | 244 __kmp_check_sync( int gtid, enum cons_type ct, ident_t const * ident, kmp_user_lock_p lck, kmp_uint… argument 246 __kmp_check_sync( int gtid, enum cons_type ct, ident_t const * ident, kmp_user_lock_p lck ) 292 if (lck != NULL && 293 __kmp_get_user_lock_owner(lck, seq) == 296 if (lck != NULL && 297 __kmp_get_user_lock_owner(lck) == 303 while (index != 0 && p->stack_data[index].name != lck) { 330 __kmp_push_sync( int gtid, enum cons_type ct, ident_t const * ident, kmp_user_lock_p lck, kmp_uint3… argument 332 __kmp_push_sync( int gtid, enum cons_type ct, ident_t const * ident, kmp_user_lock_p lck ) 341 __kmp_check_sync(gtid, ct, ident, lck, seq); [all …]
|
D | kmp_atomic.h | 361 static inline void __kmp_acquire_atomic_lock(kmp_atomic_lock_t *lck, in __kmp_acquire_atomic_lock() argument 366 ompt_mutex_atomic, 0, kmp_mutex_impl_queuing, (ompt_wait_id_t)(uintptr_t)lck, in __kmp_acquire_atomic_lock() 371 __kmp_acquire_queuing_lock(lck, gtid); in __kmp_acquire_atomic_lock() 376 ompt_mutex_atomic, (ompt_wait_id_t)(uintptr_t)lck, OMPT_GET_RETURN_ADDRESS(0)); in __kmp_acquire_atomic_lock() 381 static inline int __kmp_test_atomic_lock(kmp_atomic_lock_t *lck, in __kmp_test_atomic_lock() argument 383 return __kmp_test_queuing_lock(lck, gtid); in __kmp_test_atomic_lock() 386 static inline void __kmp_release_atomic_lock(kmp_atomic_lock_t *lck, in __kmp_release_atomic_lock() argument 388 __kmp_release_queuing_lock(lck, gtid); in __kmp_release_atomic_lock() 392 ompt_mutex_atomic, (ompt_wait_id_t)(uintptr_t)lck, OMPT_GET_RETURN_ADDRESS(0)); in __kmp_release_atomic_lock() 397 static inline void __kmp_init_atomic_lock(kmp_atomic_lock_t *lck) { in __kmp_init_atomic_lock() argument [all …]
|
D | kmp_dispatch.cpp | 1209 kmp_lock_t *lck = pr->u.p.th_steal_lock; in __kmp_dispatch_next_algorithm() local 1210 KMP_DEBUG_ASSERT(lck != NULL); in __kmp_dispatch_next_algorithm() 1212 __kmp_acquire_lock(lck, gtid); in __kmp_dispatch_next_algorithm() 1216 __kmp_release_lock(lck, gtid); in __kmp_dispatch_next_algorithm() 1255 lck = victim->u.p.th_steal_lock; in __kmp_dispatch_next_algorithm() 1256 KMP_ASSERT(lck != NULL); in __kmp_dispatch_next_algorithm() 1257 __kmp_acquire_lock(lck, gtid); in __kmp_dispatch_next_algorithm() 1261 __kmp_release_lock(lck, gtid); in __kmp_dispatch_next_algorithm() 1276 __kmp_release_lock(lck, gtid); in __kmp_dispatch_next_algorithm() 2093 kmp_lock_t *lck = buf->u.p.th_steal_lock; in __kmp_dispatch_next() local [all …]
|
D | kmp.h | 3828 kmp_critical_name *lck); 3830 kmp_critical_name *lck); 3834 kmp_critical_name *lck); 3836 kmp_critical_name *lck); 3843 kmp_critical_name *lck);
|
D | kmp_itt.inl | 714 KMP_ITT_DEBUG_PRINT("[lck ini] scre( %p, \"%s\", \"%s\", 0 )\n", lock, type, 731 KMP_ITT_DEBUG_PRINT("[lck ini] scre( %p, \"%s\", \"%s\", 0 )\n", lock, type, 744 KMP_ITT_DEBUG_PRINT("[lck dst] sdes( %p )\n", lock);
|
D | kmp_runtime.cpp | 546 static void __kmp_reset_lock(kmp_bootstrap_lock_t *lck) { in __kmp_reset_lock() argument 548 __kmp_init_bootstrap_lock(lck); // make the lock released in __kmp_reset_lock() 8235 kmp_critical_name *lck) { in __kmp_determine_reduction_method() argument 8251 KMP_DEBUG_ASSERT(lck); // it would be nice to test ( lck != 0 ) in __kmp_determine_reduction_method() 8345 KMP_ASSERT(lck); // lck should be != 0 in __kmp_determine_reduction_method()
|
/external/ltp/testcases/kernel/syscalls/fcntl/ |
D | fcntl36.c | 76 struct flock64 lck = { in fn_ofd_w() local 87 lck.l_type = F_WRLCK; in fn_ofd_w() 88 my_fcntl(fd, F_OFD_SETLKW, &lck); in fn_ofd_w() 93 lck.l_type = F_UNLCK; in fn_ofd_w() 94 my_fcntl(fd, F_OFD_SETLKW, &lck); in fn_ofd_w() 116 struct flock lck = { in fn_posix_w() local 126 lck.l_type = F_WRLCK; in fn_posix_w() 127 SAFE_FCNTL(fd, F_SETLKW, &lck); in fn_posix_w() 132 lck.l_type = F_UNLCK; in fn_posix_w() 133 SAFE_FCNTL(fd, F_SETLKW, &lck); in fn_posix_w() [all …]
|
D | fcntl_common.h | 21 static int my_fcntl(int fd, int cmd, void *lck) in my_fcntl() argument 23 return SAFE_FCNTL(fd, cmd, lck); in my_fcntl() 26 static int my_fcntl(int fd, int cmd, void *lck) in my_fcntl() argument 28 int ret = tst_syscall(__NR_fcntl64, fd, cmd, lck); in my_fcntl()
|
D | fcntl34.c | 58 struct flock64 lck = { in thread_fn_01() local 65 lck.l_type = F_WRLCK; in thread_fn_01() 66 my_fcntl(fd, F_OFD_SETLKW, &lck); in thread_fn_01() 71 lck.l_type = F_UNLCK; in thread_fn_01() 72 my_fcntl(fd, F_OFD_SETLKW, &lck); in thread_fn_01()
|
/external/llvm-project/openmp/runtime/test/lock/ |
D | omp_test_lock.c | 7 omp_lock_t lck; variable 16 omp_init_lock (&lck); in test_omp_test_lock() 17 #pragma omp parallel shared(lck) in test_omp_test_lock() 21 while (!omp_test_lock (&lck)) in test_omp_test_lock() 29 omp_unset_lock (&lck); in test_omp_test_lock() 32 omp_destroy_lock(&lck); in test_omp_test_lock()
|
D | omp_test_nest_lock.c | 5 static omp_nest_lock_t lck; variable 14 omp_init_nest_lock (&lck); in test_omp_test_nest_lock() 15 #pragma omp parallel shared(lck) in test_omp_test_nest_lock() 21 while(!omp_test_nest_lock (&lck)) in test_omp_test_nest_lock() 29 omp_unset_nest_lock (&lck); in test_omp_test_nest_lock() 32 omp_destroy_nest_lock (&lck); in test_omp_test_nest_lock()
|
D | omp_nest_lock.c | 5 omp_nest_lock_t lck; variable 14 omp_init_nest_lock(&lck); in test_omp_nest_lock() 15 #pragma omp parallel shared(lck) in test_omp_nest_lock() 19 omp_set_nest_lock(&lck); in test_omp_nest_lock() 26 omp_unset_nest_lock(&lck); in test_omp_nest_lock() 29 omp_destroy_nest_lock(&lck); in test_omp_nest_lock()
|
D | omp_lock.c | 7 omp_lock_t lck; variable 16 omp_init_lock(&lck); in test_omp_lock() 17 #pragma omp parallel shared(lck) in test_omp_lock() 21 omp_set_lock(&lck); in test_omp_lock() 28 omp_unset_lock(&lck); in test_omp_lock() 31 omp_destroy_lock(&lck); in test_omp_lock()
|
/external/llvm-project/clang/test/Analysis/Inputs/ |
D | system-header-simulator-for-pthread-lock.h | 37 extern void lck_mtx_destroy(lck_mtx_t *lck, lck_grp_t *grp); 39 extern void lck_rw_lock_exclusive(lck_rw_t *lck); 40 extern void lck_rw_unlock_exclusive(lck_rw_t *lck); 41 extern void lck_rw_lock_shared(lck_rw_t *lck); 42 extern void lck_rw_unlock_shared(lck_rw_t *lck);
|
/external/llvm-project/openmp/libomptarget/deviceRTLs/common/src/ |
D | critical.cu | 18 kmp_CriticalName *lck) { in __kmpc_critical() argument 20 omp_set_lock((omp_lock_t *)lck); in __kmpc_critical() 25 kmp_CriticalName *lck) { in __kmpc_end_critical() argument 27 omp_unset_lock((omp_lock_t *)lck); in __kmpc_end_critical()
|
/external/llvm-project/openmp/runtime/test/misc_bugs/ |
D | teams-reduction.c | 47 kmp_critical_name *lck); 48 void __kmpc_end_reduce(ident_t *, int32_t global_tid, kmp_critical_name *lck);
|
/external/clang/test/Analysis/Inputs/ |
D | system-header-simulator-for-pthread-lock.h | 28 extern void lck_mtx_destroy(lck_mtx_t *lck, lck_grp_t *grp);
|
/external/one-true-awk/testdir/ |
D | td.1 | 34 lck DRw4p0msMLxDk 172 1 m6532,m149 /usr/guest 108 lck DRw4p0msMLxDk 172 1 m6532,m149 /usr/guest 182 lck DRw4p0msMLxDk 172 1 m6532,m149 /usr/guest 256 lck DRw4p0msMLxDk 172 1 m6532,m149 /usr/guest 330 lck DRw4p0msMLxDk:172:1:m6532,m149:/usr/guest: 404 lck DRw4p0msMLxDk:172:1:m6532,m149:/usr/guest: 478 lck DRw4p0msMLxDk:172:1:m6532,m149:/usr/guest: 552 lck DRw4p0msMLxDk:172:1:m6532,m149:/usr/guest: 626 lck DRw4p0msMLxDk:172:1:m6532,m149:/usr/guest: 732 lck DRw4p0msMLxDk 172 1 m6532,m149 /usr/guest [all …]
|
D | test.data | 25 6462 lck
|
/external/e2fsprogs/lib/ext2fs/ |
D | tdb.c | 501 struct tdb_lock_type *lck = NULL; in tdb_unlock() local 527 lck = &tdb->lockrecs[i]; in tdb_unlock() 532 if ((lck == NULL) || (lck->count == 0)) { in tdb_unlock() 537 if (lck->count > 1) { in tdb_unlock() 538 lck->count--; in tdb_unlock() 563 *lck = tdb->lockrecs[tdb->num_lockrecs-1]; in tdb_unlock()
|