Home
last modified time | relevance | path

Searched refs:lck (Results 1 – 24 of 24) sorted by relevance

/external/llvm-project/openmp/runtime/src/
Dkmp_lock.cpp72 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 …]
Dkmp_lock.h144 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 …]
Dtsan_annotations.h85 #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 …]
Dkmp_csupport.cpp852 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 …]
Dkmp_error.cpp244 __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 …]
Dkmp_atomic.h361 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 …]
Dkmp_dispatch.cpp1209 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 …]
Dkmp.h3828 kmp_critical_name *lck);
3830 kmp_critical_name *lck);
3834 kmp_critical_name *lck);
3836 kmp_critical_name *lck);
3843 kmp_critical_name *lck);
Dkmp_itt.inl714 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);
Dkmp_runtime.cpp546 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/
Dfcntl36.c76 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 …]
Dfcntl_common.h21 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()
Dfcntl34.c58 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/
Domp_test_lock.c7 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()
Domp_test_nest_lock.c5 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()
Domp_nest_lock.c5 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()
Domp_lock.c7 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/
Dsystem-header-simulator-for-pthread-lock.h37 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/
Dcritical.cu18 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/
Dteams-reduction.c47 kmp_critical_name *lck);
48 void __kmpc_end_reduce(ident_t *, int32_t global_tid, kmp_critical_name *lck);
/external/clang/test/Analysis/Inputs/
Dsystem-header-simulator-for-pthread-lock.h28 extern void lck_mtx_destroy(lck_mtx_t *lck, lck_grp_t *grp);
/external/one-true-awk/testdir/
Dtd.134 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 …]
Dtest.data25 6462 lck
/external/e2fsprogs/lib/ext2fs/
Dtdb.c501 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()