Home
last modified time | relevance | path

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

/llvm-project-15.0.7/openmp/runtime/src/
H A Dkmp_lock.cpp657 if (lck->lk.self != lck) { in __kmp_acquire_ticket_lock_with_checks()
698 if (lck->lk.self != lck) { in __kmp_test_ticket_lock_with_checks()
736 if (lck->lk.self != lck) { in __kmp_release_ticket_lock_with_checks()
755 lck->lk.self = lck; in __kmp_init_ticket_lock()
791 if (lck->lk.self != lck) { in __kmp_destroy_ticket_lock_with_checks()
830 if (lck->lk.self != lck) { in __kmp_acquire_nested_ticket_lock_with_checks()
868 if (lck->lk.self != lck) { in __kmp_test_nested_ticket_lock_with_checks()
898 if (lck->lk.self != lck) { in __kmp_release_nested_ticket_lock_with_checks()
1817 lck->stats.next = lck; in __kmp_init_speculative_stats()
1818 lck->stats.prev = lck; in __kmp_init_speculative_stats()
[all …]
H A Dkmp_lock.h536 __kmp_init_ticket_lock(lck); in __kmp_init_bootstrap_lock()
540 __kmp_destroy_ticket_lock(lck); in __kmp_destroy_bootstrap_lock()
568 __kmp_init_ticket_lock(lck); in __kmp_init_lock()
572 __kmp_destroy_ticket_lock(lck); in __kmp_destroy_lock()
733 (*__kmp_destroy_user_lock_)(lck); in __kmp_destroy_user_lock()
808 if (lck->tas.lk.poll - 1 == in __kmp_test_nested_user_lock_with_checks()
816 lck->tas.lk.depth_locked = 1; in __kmp_test_nested_user_lock_with_checks()
1197 __kmp_indirect_set_location[(lck)->type]((lck)->lock, loc); \
1206 __kmp_indirect_set_flags[(lck)->type]((lck)->lock, flag); \
1214 ? __kmp_indirect_get_location[(lck)->type]((lck)->lock) \
[all …]
H A Dkmp_csupport.cpp1208 if (lck == NULL) { in __kmp_get_critical_section_ptr()
1243 return lck; in __kmp_get_critical_section_ptr()
1556 lck = ilk->lock; in __kmpc_critical_with_hint()
1644 KMP_D_LOCK_FUNC(lck, unset)((kmp_dyna_lock_t *)lck, global_tid); in __kmpc_end_critical()
1650 lck = ilk->lock; in __kmpc_end_critical()
2473 INIT_LOCK(lck); in __kmpc_init_lock()
2533 (sizeof(lck->tas.lk.poll) + sizeof(lck->tas.lk.depth_locked) <= in __kmpc_init_nest_lock()
2667 (sizeof(lck->tas.lk.poll) + sizeof(lck->tas.lk.depth_locked) <= in __kmpc_destroy_nest_lock()
2700 (sizeof(lck->tas.lk.poll) + sizeof(lck->tas.lk.depth_locked) <= in __kmpc_destroy_nest_lock()
2860 (sizeof(lck->tas.lk.poll) + sizeof(lck->tas.lk.depth_locked) <= in __kmpc_set_nest_lock()
[all …]
H A Dkmp_error.cpp252 __kmp_check_sync( int gtid, enum cons_type ct, ident_t const * ident, kmp_user_lock_p lck )
298 if (lck != NULL &&
299 __kmp_get_user_lock_owner(lck, seq) ==
302 if (lck != NULL &&
303 __kmp_get_user_lock_owner(lck) ==
309 while (index != 0 && p->stack_data[index].name != lck) {
336 __kmp_push_sync( int gtid, enum cons_type ct, ident_t const * ident, kmp_user_lock_p lck, kmp_uint3… argument
338 __kmp_push_sync( int gtid, enum cons_type ct, ident_t const * ident, kmp_user_lock_p lck )
347 __kmp_check_sync(gtid, ct, ident, lck, seq);
349 __kmp_check_sync(gtid, ct, ident, lck);
[all …]
H A Dkmp_atomic.h367 static inline void __kmp_acquire_atomic_lock(kmp_atomic_lock_t *lck, in __kmp_acquire_atomic_lock() argument
373 (ompt_wait_id_t)(uintptr_t)lck, OMPT_GET_RETURN_ADDRESS(0)); in __kmp_acquire_atomic_lock()
377 __kmp_acquire_queuing_lock(lck, gtid); in __kmp_acquire_atomic_lock()
382 ompt_mutex_atomic, (ompt_wait_id_t)(uintptr_t)lck, in __kmp_acquire_atomic_lock()
388 static inline int __kmp_test_atomic_lock(kmp_atomic_lock_t *lck, in __kmp_test_atomic_lock() argument
390 return __kmp_test_queuing_lock(lck, gtid); in __kmp_test_atomic_lock()
395 __kmp_release_queuing_lock(lck, gtid); in __kmp_release_atomic_lock()
399 ompt_mutex_atomic, (ompt_wait_id_t)(uintptr_t)lck, in __kmp_release_atomic_lock()
405 static inline void __kmp_init_atomic_lock(kmp_atomic_lock_t *lck) { in __kmp_init_atomic_lock() argument
406 __kmp_init_queuing_lock(lck); in __kmp_init_atomic_lock()
[all …]
H A Dkmp_dispatch.cpp1219 kmp_lock_t *lck = pr->u.p.steal_lock; in __kmp_dispatch_next_algorithm() local
1220 KMP_DEBUG_ASSERT(lck != NULL); in __kmp_dispatch_next_algorithm()
1223 __kmp_acquire_lock(lck, gtid); in __kmp_dispatch_next_algorithm()
1227 __kmp_release_lock(lck, gtid); in __kmp_dispatch_next_algorithm()
1268 __kmp_acquire_lock(lck, gtid); in __kmp_dispatch_next_algorithm()
1271 __kmp_release_lock(lck, gtid); in __kmp_dispatch_next_algorithm()
1336 __kmp_acquire_lock(lck, gtid); in __kmp_dispatch_next_algorithm()
1339 __kmp_release_lock(lck, gtid); in __kmp_dispatch_next_algorithm()
2219 KMP_ASSERT(lck != NULL); in __kmp_dispatch_next()
2220 __kmp_destroy_lock(lck); in __kmp_dispatch_next()
[all …]
H A Dkmp_itt.inl658 KMP_ITT_DEBUG_PRINT("[lck ini] scre( %p, \"%s\", \"%s\", 0 )\n", lock, type,
675 KMP_ITT_DEBUG_PRINT("[lck ini] scre( %p, \"%s\", \"%s\", 0 )\n", lock, type,
688 KMP_ITT_DEBUG_PRINT("[lck dst] sdes( %p )\n", lock);
H A Dkmp.h4045 kmp_critical_name *lck);
4047 kmp_critical_name *lck);
4051 kmp_critical_name *lck);
4053 kmp_critical_name *lck);
4060 kmp_critical_name *lck);
H A Dkmp_runtime.cpp8718 kmp_critical_name *lck) { in __kmp_determine_reduction_method() argument
8734 KMP_DEBUG_ASSERT(lck); // it would be nice to test ( lck != 0 ) in __kmp_determine_reduction_method()
8829 KMP_ASSERT(lck); // lck should be != 0 in __kmp_determine_reduction_method()
/llvm-project-15.0.7/openmp/runtime/test/lock/
H A 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()
H A 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()
H A 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()
H A 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()
/llvm-project-15.0.7/clang/test/Analysis/Inputs/
H A 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);
/llvm-project-15.0.7/openmp/runtime/test/misc_bugs/
H A Dteams-reduction.c47 kmp_critical_name *lck);
48 void __kmpc_end_reduce(ident_t *, int32_t global_tid, kmp_critical_name *lck);