/netbsd-current/sys/sys/ |
H A D | common_lock.h | 41 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 43 return *__ptr != __SIMPLELOCK_UNLOCKED; 47 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 49 return *__ptr == __SIMPLELOCK_UNLOCKED; 53 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 56 *__ptr = __SIMPLELOCK_UNLOCKED; 58 __atomic_store_n(__ptr, __SIMPLELOCK_UNLOCKED, __ATOMIC_RELAXED); 63 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 66 *__ptr = __SIMPLELOCK_LOCKED; 68 __atomic_store_n(__ptr, __SIMPLELOCK_LOCKE 73 __cpu_simple_lock_init(__cpu_simple_lock_t *__ptr) argument 83 __cpu_simple_lock(__cpu_simple_lock_t *__ptr) argument 91 __cpu_simple_lock_try(__cpu_simple_lock_t *__ptr) argument 97 __cpu_simple_unlock(__cpu_simple_lock_t *__ptr) argument [all...] |
/netbsd-current/sys/arch/or1k/include/ |
H A D | lock.h | 39 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 41 return *__ptr != __SIMPLELOCK_UNLOCKED; 45 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 47 return *__ptr == __SIMPLELOCK_UNLOCKED; 51 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 54 __atomic_clear(__ptr, __ATOMIC_RELAXED); 56 *__ptr = __SIMPLELOCK_UNLOCKED; 61 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 64 (void)__atomic_test_and_set(__ptr, __ATOMIC_RELAXED); 66 *__ptr 71 __cpu_simple_lock_init(__cpu_simple_lock_t *__ptr) argument 81 __cpu_simple_lock(__cpu_simple_lock_t *__ptr) argument 117 __cpu_simple_lock_try(__cpu_simple_lock_t *__ptr) argument 139 __cpu_simple_unlock(__cpu_simple_lock_t *__ptr) argument [all...] |
/netbsd-current/sys/arch/m68k/include/ |
H A D | lock.h | 40 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 42 return *__ptr == __SIMPLELOCK_LOCKED; 46 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 48 return *__ptr == __SIMPLELOCK_UNLOCKED; 60 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 62 *__ptr = __SIMPLELOCK_UNLOCKED; 66 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 68 *__ptr = __SIMPLELOCK_LOCKED;
|
/netbsd-current/external/gpl3/gcc.old/dist/gcc/config/i386/ |
H A D | pmm_malloc.h | 40 void *__ptr; local 45 if (posix_memalign (&__ptr, __alignment, __size) == 0) 46 return __ptr; 52 _mm_free (void *__ptr) argument 54 free (__ptr);
|
/netbsd-current/external/gpl3/gcc/dist/gcc/config/i386/ |
H A D | pmm_malloc.h | 40 void *__ptr; local 45 if (posix_memalign (&__ptr, __alignment, __size) == 0) 46 return __ptr; 52 _mm_free (void *__ptr) argument 54 free (__ptr);
|
/netbsd-current/external/gpl3/gcc.old/dist/libstdc++-v3/include/parallel/ |
H A D | compatibility.h | 56 __add_omp(volatile _Tp* __ptr, _Tp __addend) argument 61 __res = *__ptr; 62 *(__ptr) += __addend; 69 * @param __ptr Pointer to a signed integer. 74 __fetch_and_add(volatile _Tp* __ptr, _Tp __addend) argument 76 if (__atomic_always_lock_free(sizeof(_Tp), __ptr)) 77 return __atomic_fetch_add(__ptr, __addend, __ATOMIC_ACQ_REL); 78 return __add_omp(__ptr, __addend); 83 __cas_omp(volatile _Tp* __ptr, _Tp __comparand, _Tp __replacement) argument 88 if (*__ptr 108 __compare_and_swap(volatile _Tp* __ptr, _Tp __comparand, _Tp __replacement) argument [all...] |
/netbsd-current/external/gpl3/gcc/dist/libstdc++-v3/include/parallel/ |
H A D | compatibility.h | 56 __add_omp(volatile _Tp* __ptr, _Tp __addend) argument 61 __res = *__ptr; 62 *(__ptr) += __addend; 69 * @param __ptr Pointer to a signed integer. 74 __fetch_and_add(volatile _Tp* __ptr, _Tp __addend) argument 76 if (__atomic_always_lock_free(sizeof(_Tp), __ptr)) 77 return __atomic_fetch_add(__ptr, __addend, __ATOMIC_ACQ_REL); 78 return __add_omp(__ptr, __addend); 83 __cas_omp(volatile _Tp* __ptr, _Tp __comparand, _Tp __replacement) argument 88 if (*__ptr 108 __compare_and_swap(volatile _Tp* __ptr, _Tp __comparand, _Tp __replacement) argument [all...] |
/netbsd-current/sys/arch/powerpc/include/ |
H A D | lock.h | 40 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 42 return *__ptr == __SIMPLELOCK_LOCKED; 46 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 48 return *__ptr == __SIMPLELOCK_UNLOCKED; 52 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 54 *__ptr = __SIMPLELOCK_UNLOCKED; 58 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 60 *__ptr = __SIMPLELOCK_LOCKED;
|
/netbsd-current/sys/arch/sh3/include/ |
H A D | lock.h | 49 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 51 return *__ptr == __SIMPLELOCK_LOCKED; 55 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 57 return *__ptr == __SIMPLELOCK_UNLOCKED; 61 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 63 *__ptr = __SIMPLELOCK_UNLOCKED; 67 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 69 *__ptr = __SIMPLELOCK_LOCKED;
|
/netbsd-current/sys/arch/alpha/include/ |
H A D | lock.h | 45 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 47 return *__ptr == __SIMPLELOCK_LOCKED; 51 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 53 return *__ptr == __SIMPLELOCK_UNLOCKED; 57 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 59 *__ptr = __SIMPLELOCK_UNLOCKED; 63 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 65 *__ptr = __SIMPLELOCK_LOCKED;
|
/netbsd-current/external/gpl3/gcc.old/dist/gcc/config/rs6000/ |
H A D | mm_malloc.h | 44 void *__ptr; local 50 if (posix_memalign (&__ptr, __alignment, __size) == 0) 51 return __ptr; 57 _mm_free (void * __ptr) argument 59 free (__ptr);
|
/netbsd-current/external/gpl3/gcc/dist/gcc/config/rs6000/ |
H A D | mm_malloc.h | 44 void *__ptr; local 50 if (posix_memalign (&__ptr, __alignment, __size) == 0) 51 return __ptr; 57 _mm_free (void * __ptr) argument 59 free (__ptr);
|
/netbsd-current/external/bsd/wpa/dist/src/utils/ |
H A D | platform.h | 14 } __attribute__((packed)) *__ptr = (void *) (p); \ 16 __ptr->__val; \
|
/netbsd-current/sys/arch/x86/include/ |
H A D | lock.h | 42 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 44 return *__ptr == __SIMPLELOCK_LOCKED; 48 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 50 return *__ptr == __SIMPLELOCK_UNLOCKED; 54 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 57 *__ptr = __SIMPLELOCK_LOCKED; 61 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 64 *__ptr = __SIMPLELOCK_UNLOCKED;
|
/netbsd-current/sys/arch/sparc/include/ |
H A D | lock.h | 75 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 77 return *__ptr == __SIMPLELOCK_LOCKED; 81 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 83 return *__ptr == __SIMPLELOCK_UNLOCKED; 87 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 89 *__ptr = __SIMPLELOCK_UNLOCKED; 93 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 95 *__ptr = __SIMPLELOCK_LOCKED;
|
/netbsd-current/sys/arch/vax/include/ |
H A D | lock.h | 42 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 44 return *__ptr == __SIMPLELOCK_LOCKED; 48 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 50 return *__ptr == __SIMPLELOCK_UNLOCKED; 54 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 56 *__ptr = __SIMPLELOCK_UNLOCKED; 60 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 62 *__ptr = __SIMPLELOCK_LOCKED;
|
/netbsd-current/sys/arch/mips/include/ |
H A D | lock.h | 47 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 49 return *__ptr != __SIMPLELOCK_UNLOCKED; 53 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 55 return *__ptr == __SIMPLELOCK_UNLOCKED; 59 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 61 *__ptr = __SIMPLELOCK_UNLOCKED; 65 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 67 *__ptr = __SIMPLELOCK_LOCKED;
|
/netbsd-current/external/gpl3/gcc.old/dist/libstdc++-v3/libsupc++/ |
H A D | hash_bytes.h | 47 _Hash_bytes(const void* __ptr, size_t __len, size_t __seed); 54 _Fnv_hash_bytes(const void* __ptr, size_t __len, size_t __seed);
|
/netbsd-current/external/gpl3/gcc/dist/libstdc++-v3/libsupc++/ |
H A D | hash_bytes.h | 47 _Hash_bytes(const void* __ptr, size_t __len, size_t __seed); 54 _Fnv_hash_bytes(const void* __ptr, size_t __len, size_t __seed);
|
/netbsd-current/sys/arch/ia64/include/ |
H A D | lock.h | 40 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 42 return *__ptr == __SIMPLELOCK_LOCKED; 46 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 48 return *__ptr == __SIMPLELOCK_UNLOCKED; 52 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 55 *__ptr = __SIMPLELOCK_LOCKED; 59 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 62 *__ptr = __SIMPLELOCK_UNLOCKED;
|
/netbsd-current/sys/arch/arm/include/ |
H A D | lock.h | 45 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 47 return *__ptr == __SIMPLELOCK_LOCKED; 51 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 53 return *__ptr == __SIMPLELOCK_UNLOCKED; 57 __cpu_simple_lock_clear(__cpu_simple_lock_t *__ptr) argument 59 *__ptr = __SIMPLELOCK_UNLOCKED; 63 __cpu_simple_lock_set(__cpu_simple_lock_t *__ptr) argument 65 *__ptr = __SIMPLELOCK_LOCKED; 97 __swp(unsigned char __val, __cpu_simple_lock_t *__ptr) argument 101 : "=&r" (__val32) : "r" (__val), "r" (__ptr) 114 __swp(int __val, __cpu_simple_lock_t *__ptr) argument [all...] |
/netbsd-current/external/gpl3/gcc/dist/libstdc++-v3/include/bits/ |
H A D | align.h | 47 * @a __align into the buffer @a __ptr of size @a __space bytes. If such 48 * a buffer fits then @a __ptr is changed to point to the first byte of the 55 * @param __ptr Pointer to a buffer of @a __space bytes. 56 * @param __space Size of the buffer pointed to by @a __ptr. 62 align(size_t __align, size_t __size, void*& __ptr, size_t& __space) noexcept 66 const auto __intptr = reinterpret_cast<uintptr_t>(__ptr); 74 return __ptr = reinterpret_cast<void*>(__aligned); 84 * @param __ptr A pointer that is aligned to _Align 93 assume_aligned(_Tp* __ptr) noexcept 97 return __ptr; [all...] |
/netbsd-current/sys/arch/hppa/include/ |
H A D | lock.h | 52 __SIMPLELOCK_LOCKED_P(const __cpu_simple_lock_t *__ptr) argument 54 return *__SIMPLELOCK_ALIGN(__ptr) == __SIMPLELOCK_RAW_LOCKED; 58 __SIMPLELOCK_UNLOCKED_P(const __cpu_simple_lock_t *__ptr) argument 60 return *__SIMPLELOCK_ALIGN(__ptr) == __SIMPLELOCK_RAW_UNLOCKED; 64 __ldcw(volatile unsigned long *__ptr) argument 69 : "=r" (__val) : "r" (__ptr)
|
/netbsd-current/external/apache2/llvm/dist/clang/lib/Headers/ |
H A D | __clang_hip_runtime_wrapper.h | 56 extern "C" __device__ void *__hip_free(void *__ptr); 60 static inline __device__ void *free(void *__ptr) { return __hip_free(__ptr); } argument 66 static inline __device__ void *free(void *__ptr) { argument
|
/netbsd-current/external/gpl3/gcc.old/dist/libstdc++-v3/include/bits/ |
H A D | allocated_ptr.h | 51 /// Take ownership of __ptr 52 __allocated_ptr(_Alloc& __a, pointer __ptr) noexcept 53 : _M_alloc(std::__addressof(__a)), _M_ptr(__ptr) 56 /// Convert __ptr to allocator's pointer type and take ownership of it 59 __allocated_ptr(_Alloc& __a, _Ptr __ptr) argument 61 _M_ptr(pointer_traits<pointer>::pointer_to(*__ptr))
|