Searched refs:__ptr (Results 1 - 25 of 124) sorted by relevance

12345

/netbsd-current/sys/sys/
H A Dcommon_lock.h41 __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 Dlock.h39 __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 Dlock.h40 __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 Dpmm_malloc.h40 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 Dpmm_malloc.h40 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 Dcompatibility.h56 __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 Dcompatibility.h56 __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 Dlock.h40 __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 Dlock.h49 __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 Dlock.h45 __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 Dmm_malloc.h44 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 Dmm_malloc.h44 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 Dplatform.h14 } __attribute__((packed)) *__ptr = (void *) (p); \
16 __ptr->__val; \
/netbsd-current/sys/arch/x86/include/
H A Dlock.h42 __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 Dlock.h75 __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 Dlock.h42 __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 Dlock.h47 __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 Dhash_bytes.h47 _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 Dhash_bytes.h47 _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 Dlock.h40 __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 Dlock.h45 __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 Dalign.h47 * @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 Dlock.h52 __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.h56 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 Dallocated_ptr.h51 /// 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))

Completed in 267 milliseconds

12345