| /freebsd-13-stable/contrib/llvm-project/libcxx/src/include/ |
| H A D | atomic_support.h | 56 void __libcpp_atomic_store(_ValueType* __dest, _FromType __val, argument
59 __atomic_store_n(__dest, __val, __order);
64 void __libcpp_relaxed_store(_ValueType* __dest, _FromType __val) argument
66 __atomic_store_n(__dest, __val, _AO_Relaxed);
71 _ValueType __libcpp_atomic_load(_ValueType const* __val, argument
74 return __atomic_load_n(__val, __order);
79 _ValueType __libcpp_atomic_add(_ValueType* __val, _AddType __a, argument
82 return __atomic_add_fetch(__val, __a, __order);
95 bool __libcpp_atomic_compare_exchange(_ValueType* __val, argument
100 return __atomic_compare_exchange_n(__val, __expecte
[all...] |
| /freebsd-13-stable/contrib/wpa/src/utils/ |
| H A D | platform.h | 13 typeof(*(p)) __val; \
16 __ptr->__val; \
|
| /freebsd-13-stable/contrib/llvm-project/clang/lib/Headers/ |
| H A D | pkuintrin.h | 27 _wrpkru(unsigned int __val) argument
29 __builtin_ia32_wrpkru(__val);
|
| H A D | __clang_cuda_intrinsics.h | 25 inline __device__ int __FnName(int __val, __Type __offset, \
27 return __IntIntrinsic(__val, __offset, \
30 inline __device__ float __FnName(float __val, __Type __offset, \
32 return __FloatIntrinsic(__val, __offset, \
35 inline __device__ unsigned int __FnName(unsigned int __val, __Type __offset, \
38 ::__FnName(static_cast<int>(__val), __offset, __width)); \
40 inline __device__ long long __FnName(long long __val, __Type __offset, \
45 _Static_assert(sizeof(__val) == sizeof(__Bits)); \
48 memcpy(&__tmp, &__val, sizeof(__val)); \
[all...] |
| /freebsd-13-stable/sys/i386/include/ |
| H A D | pcpu.h | 156 __pcpu_type(name) __val; \
158 u_char __b[MIN(sizeof(__val), 4)]; \
161 __val = (val); \
162 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \
163 sizeof(__val) == 4) { \
164 __s = *(struct __s *)(void *)&__val; \
169 *__PCPU_PTR(name) += __val; \
199 __pcpu_type(name) __val; \
201 u_char __b[MIN(sizeof(__val),
[all...] |
| /freebsd-13-stable/sys/amd64/include/ |
| H A D | pcpu.h | 167 __pcpu_type(name) __val; \
172 __val = (val); \
173 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \
174 sizeof(__val) == 4 || sizeof(__val) == 8) { \
175 __s = *(struct __s *)(void *)&__val; \
180 *__PCPU_PTR(name) += __val; \
215 __pcpu_type(name) __val; \
220 __val
[all...] |
| /freebsd-13-stable/sys/sys/ |
| H A D | stdatomic.h | 91 #define ATOMIC_VAR_INIT(value) { .__val = (value) }
92 #define atomic_init(obj, value) ((void)((obj)->__val = (value)))
179 ((void)(obj), sizeof((obj)->__val) <= sizeof(void *))
284 (((__typeof__((object)->__val))0) + (operand))
290 (_Bool)((*__ep = __sync_val_compare_and_swap(&(object)->__val, \
300 ((void)(order), __sync_swap(&(object)->__val, desired))
313 __sync_lock_test_and_set(&(__o)->__val, __d); \
317 ((void)(order), __sync_fetch_and_add(&(object)->__val, \
320 ((void)(order), __sync_fetch_and_and(&(object)->__val, operand))
322 ((void)(order), __sync_fetch_and_or(&(object)->__val, operan
[all...] |
| H A D | cdefs.h | 272 #define _Atomic(T) struct { T volatile __val; }
|
| /freebsd-13-stable/contrib/llvm-project/libcxx/src/ |
| H A D | atomic.cpp | 35 __cxx_contention_t __val)
38 syscall(SYS_futex, __ptr, FUTEX_WAIT_PRIVATE, __val, &__timeout, 0, 0);
57 __cxx_contention_t __val)
60 const_cast<__cxx_atomic_contention_t*>(__ptr), __val, 0);
75 __cxx_contention_t __val)
78 return !__cxx_nonatomic_compare_equal(__cxx_atomic_load(__ptr, memory_order_relaxed), __val);
34 __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention_t __val) argument
|
| /freebsd-13-stable/sys/contrib/octeon-sdk/cvmx-malloc/ |
| H A D | malloc.h | 165 extern int mallopt __MALLOC_P ((int __param, int __val));
|
| /freebsd-13-stable/sys/ofed/drivers/infiniband/ulp/sdp/ |
| H A D | sdp_proc.c | 238 u32 __val = 0; \
241 __val += per_cpu(sdpstats, __i).var; \
242 __val; \
|
| /freebsd-13-stable/crypto/openssh/ |
| H A D | defines.h | 677 ((((u_int64_t)(f).__val[0] & 0xffffffffUL) << 32) | \
678 ((f).__val[1] & 0xffffffffUL))
|