/freebsd-current/contrib/llvm-project/libcxx/include/__utility/ |
H A D | convert_to_integral.h | 24 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR int __convert_to_integral(int __val) { return __val; } argument 26 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR unsigned __convert_to_integral(unsigned __val) { return __val; } argument 28 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR long __convert_to_integral(long __val) { return __val; } argument 30 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR unsigned long __convert_to_integral(unsigned long __val) { argument 31 return __val; 34 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR long long __convert_to_integral(long long __val) { return __val; } argument 36 __convert_to_integral(unsigned long long __val) argument 41 __convert_to_integral(_Fp __val) argument 46 __convert_to_integral(__int128_t __val) argument 48 __convert_to_integral(__uint128_t __val) argument 62 __convert_to_integral(_Tp __val) argument [all...] |
H A D | to_underlying.h | 24 _LIBCPP_HIDE_FROM_ABI constexpr typename underlying_type<_Tp>::type __to_underlying(_Tp __val) noexcept { 25 return static_cast<typename underlying_type<_Tp>::type>(__val); 31 _LIBCPP_NODISCARD_EXT _LIBCPP_HIDE_FROM_ABI constexpr underlying_type_t<_Tp> to_underlying(_Tp __val) noexcept { 32 return std::__to_underlying(__val);
|
/freebsd-current/contrib/llvm-project/libcxx/include/__bit/ |
H A D | byteswap.h | 26 _LIBCPP_NODISCARD_EXT _LIBCPP_HIDE_FROM_ABI constexpr _Tp byteswap(_Tp __val) noexcept { 28 return __val; 30 return __builtin_bswap16(__val); 32 return __builtin_bswap32(__val); 34 return __builtin_bswap64(__val); 38 return __builtin_bswap128(__val); 40 return static_cast<_Tp>(byteswap(static_cast<uint64_t>(__val))) << 64 | 41 static_cast<_Tp>(byteswap(static_cast<uint64_t>(__val >> 64)));
|
/freebsd-current/contrib/llvm-project/libcxx/src/include/ |
H A D | atomic_support.h | 48 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_atomic_store(_ValueType* __dest, _FromType __val, int __order = _AO_Seq) { argument 49 __atomic_store_n(__dest, __val, __order); 53 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_relaxed_store(_ValueType* __dest, _FromType __val) { argument 54 __atomic_store_n(__dest, __val, _AO_Relaxed); 58 inline _LIBCPP_HIDE_FROM_ABI _ValueType __libcpp_atomic_load(_ValueType const* __val, int __order = _AO_Seq) { argument 59 return __atomic_load_n(__val, __order); 63 inline _LIBCPP_HIDE_FROM_ABI _ValueType __libcpp_atomic_add(_ValueType* __val, _AddType __a, int __order = _AO_Seq) { argument 64 return __atomic_add_fetch(__val, __a, __order); 75 _ValueType* __val, 80 return __atomic_compare_exchange_n(__val, __expecte 74 __libcpp_atomic_compare_exchange( _ValueType* __val, _ValueType* __expected, _ValueType __after, int __success_order = _AO_Seq, int __fail_order = _AO_Seq) argument [all...] |
/freebsd-current/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)); \ 655 atomicAdd(float2 *__ptr, float2 __val) argument 663 atomicAdd_block(float2 *__ptr, float2 __val) argument 671 atomicAdd_system(float2 *__ptr, float2 __val) argument 679 atomicAdd(float4 *__ptr, float4 __val) argument 687 atomicAdd_block(float4 *__ptr, float4 __val) argument 696 atomicAdd_system(float4 *__ptr, float4 __val) argument [all...] |
/freebsd-current/sys/amd64/include/ |
H A D | pcpu.h | 151 __pcpu_type(name) __val; \ 153 __val = (val); \ 154 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \ 155 sizeof(__val) == 4 || sizeof(__val) == 8) { \ 156 __pc->name += __val; \ 158 *__PCPU_PTR(name) += __val; \ 166 __pcpu_type(name) __val; \ 168 __val [all...] |
/freebsd-current/contrib/llvm-project/libcxx/include/__numeric/ |
H A D | adjacent_difference.h | 33 typename iterator_traits<_InputIterator>::value_type __val(*__first); 35 *__result = __val - std::move(__acc); 37 *__result = __val - __acc; 39 __acc = std::move(__val); 52 typename iterator_traits<_InputIterator>::value_type __val(*__first); 54 *__result = __binary_op(__val, std::move(__acc)); 56 *__result = __binary_op(__val, __acc); 58 __acc = std::move(__val);
|
H A D | midpoint.h | 57 _LIBCPP_HIDE_FROM_ABI constexpr int __sign(_Tp __val) { 58 return (_Tp(0) < __val) - (__val < _Tp(0));
|
/freebsd-current/sys/i386/include/ |
H A D | pcpu.h | 148 __pcpu_type(name) __val; \ 150 u_char __b[MIN(sizeof(__val), 4)]; \ 153 __val = (val); \ 154 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \ 155 sizeof(__val) == 4) { \ 156 __s = *(struct __s *)(void *)&__val; \ 161 *__PCPU_PTR(name) += __val; \ 168 __pcpu_type(name) __val; \ 170 u_char __b[MIN(sizeof(__val), [all...] |
/freebsd-current/sys/contrib/openzfs/include/os/linux/kernel/linux/ |
H A D | simd_aarch64.h | 87 unsigned long __val; \ 88 asm("mrs %0, "#id : "=r" (__val)); \ 89 __val; \
|
/freebsd-current/contrib/llvm-project/libcxx/src/ |
H A D | atomic.cpp | 57 __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention_t __val) { argument 59 _LIBCPP_FUTEX(__ptr, FUTEX_WAIT_PRIVATE, __val, &__timeout, 0, 0); 76 __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention_t __val) { 77 __ulock_wait(UL_COMPARE_AND_WAIT, const_cast<__cxx_atomic_contention_t*>(__ptr), __val, 0); 93 __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention_t __val) { 94 _umtx_op(const_cast<__cxx_atomic_contention_t*>(__ptr), UMTX_OP_WAIT, __val, NULL, NULL); 106 __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention_t __val) { 108 [=]() -> bool { return !__cxx_nonatomic_compare_equal(__cxx_atomic_load(__ptr, memory_order_relaxed), __val); },
|
/freebsd-current/contrib/llvm-project/libcxx/include/__algorithm/ |
H A D | ranges_replace.h | 42 auto __pred = [&](const auto& __val) -> bool { return __val == __old_value; }; 51 auto __pred = [&](auto&& __val) -> bool { return __val == __old_value; };
|
H A D | ranges_remove_copy.h | 53 auto __pred = [&](auto&& __val) -> bool { return __value == __val; }; 62 auto __pred = [&](auto&& __val) -> bool { return __value == __val; };
|
/freebsd-current/contrib/llvm-project/libcxx/include/__atomic/ |
H A D | atomic_sync.h | 92 _Tp __val; member in struct:__cxx_atomic_wait_test_fn_impl 95 return !std::__cxx_nonatomic_compare_equal(std::__cxx_atomic_load(__a, __order), __val); 101 __cxx_atomic_wait(_Atp* __a, _Tp const __val, memory_order __order) { argument 102 __cxx_atomic_wait_test_fn_impl<_Atp, _Tp> __test_fn = {__a, __val, __order};
|
H A D | cxx_atomic_impl.h | 35 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_assign_volatile(_Tp& __a_value, _Tv const& __val) { argument 36 __a_value = __val; 39 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_assign_volatile(_Tp volatile& __a_value, _Tv volatile const& __val) { argument 42 volatile const char* __from = reinterpret_cast<volatile const char*>(std::addressof(__val)); 91 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(volatile __cxx_atomic_base_impl<_Tp>* __a, _Tp __val) { argument 92 __cxx_atomic_assign_volatile(__a->__a_value, __val); 96 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(__cxx_atomic_base_impl<_Tp>* __a, _Tp __val) { argument 97 __a->__a_value = __val; 110 __cxx_atomic_store(volatile __cxx_atomic_base_impl<_Tp>* __a, _Tp __val, memory_order __order) { argument 111 __atomic_store(std::addressof(__a->__a_value), std::addressof(__val), __to_gcc_orde 115 __cxx_atomic_store(__cxx_atomic_base_impl<_Tp>* __a, _Tp __val, memory_order __order) argument 584 __cxx_atomic_init(volatile __cxx_atomic_lock_impl<_Tp>* __a, _Tp __val) argument 588 __cxx_atomic_init(__cxx_atomic_lock_impl<_Tp>* __a, _Tp __val) argument 593 __cxx_atomic_store(volatile __cxx_atomic_lock_impl<_Tp>* __a, _Tp __val, memory_order) argument 599 __cxx_atomic_store(__cxx_atomic_lock_impl<_Tp>* __a, _Tp __val, memory_order) argument [all...] |
/freebsd-current/sys/sys/ |
H A D | stdatomic.h | 89 #define ATOMIC_VAR_INIT(value) { .__val = (value) } 90 #define atomic_init(obj, value) ((void)((obj)->__val = (value))) 182 ((void)(obj), sizeof((obj)->__val) <= sizeof(void *)) 287 (((__typeof__((object)->__val))0) + (operand)) 293 (_Bool)((*__ep = __sync_val_compare_and_swap(&(object)->__val, \ 303 ((void)(order), __sync_swap(&(object)->__val, desired)) 316 __sync_lock_test_and_set(&(__o)->__val, __d); \ 320 ((void)(order), __sync_fetch_and_add(&(object)->__val, \ 323 ((void)(order), __sync_fetch_and_and(&(object)->__val, operand)) 325 ((void)(order), __sync_fetch_and_or(&(object)->__val, operan [all...] |
/freebsd-current/contrib/llvm-project/libcxx/include/__system_error/ |
H A D | error_code.h | 50 _LIBCPP_HIDE_FROM_ABI error_code(int __val, const error_category& __cat) _NOEXCEPT : __val_(__val), __cat_(&__cat) {} 58 _LIBCPP_HIDE_FROM_ABI void assign(int __val, const error_category& __cat) _NOEXCEPT { 59 __val_ = __val;
|
H A D | error_condition.h | 57 _LIBCPP_HIDE_FROM_ABI error_condition(int __val, const error_category& __cat) _NOEXCEPT 58 : __val_(__val), 67 _LIBCPP_HIDE_FROM_ABI void assign(int __val, const error_category& __cat) _NOEXCEPT { 68 __val_ = __val;
|
/freebsd-current/contrib/llvm-project/libcxx/include/__charconv/ |
H A D | from_chars_integral.h | 79 int __val; member in struct:__in_pattern_result 134 __first, __last, __value, [](const char* __f, const char* __l, _Tp& __val) -> from_chars_result { 140 __val = __a + __b; 183 [](const char* __p, const char* __lastp, _Tp& __val, int __b) -> from_chars_result { 187 _Tp __x = __in_pattern(*__p++, __b).__val, __y = 0; 192 __x = __x * __b + __c.__val; 196 __y = __c.__val; 205 __val = __x + __y;
|
/freebsd-current/contrib/llvm-project/libcxx/include/__expected/ |
H A D | expected.h | 446 _LIBCPP_HIDE_FROM_ABI constexpr _Tp& __val() { return __repr_.__v.__union_.__v.__val_; } function in class:__expected_base 447 _LIBCPP_HIDE_FROM_ABI constexpr const _Tp& __val() const { return __repr_.__v.__union_.__v.__val_; } function in class:__expected_base 638 this->__val() = __rhs.__val(); 640 __reinit_expected<unexpect_t, in_place_t, _Err, _Tp>(this->__val(), __rhs.__unex()); 642 __reinit_expected<in_place_t, unexpect_t, _Tp, _Err>(this->__unex(), __rhs.__val()); 657 this->__val() = std::move(__rhs.__val()); 659 __reinit_expected<unexpect_t, in_place_t, _Err, _Tp>(this->__val(), std::move(__rhs.__unex())); 661 __reinit_expected<in_place_t, unexpect_t, _Tp, _Err>(this->__unex(), std::move(__rhs.__val())); [all...] |
/freebsd-current/contrib/llvm-project/libcxx/include/__chrono/ |
H A D | weekday.h | 39 _LIBCPP_HIDE_FROM_ABI inline explicit constexpr weekday(unsigned __val) noexcept 40 : __wd_(static_cast<unsigned char>(__val == 7 ? 0 : __val)) {} argument 152 _LIBCPP_HIDE_FROM_ABI explicit constexpr weekday_last(const chrono::weekday& __val) noexcept : __wd_{__val} {}
|
H A D | day.h | 33 _LIBCPP_HIDE_FROM_ABI explicit inline constexpr day(unsigned __val) noexcept 34 : __d_(static_cast<unsigned char>(__val)) {}
|
H A D | year.h | 37 _LIBCPP_HIDE_FROM_ABI explicit inline constexpr year(int __val) noexcept : __y_(static_cast<short>(__val)) {}
|
/freebsd-current/sys/contrib/dev/athk/ath12k/ |
H A D | hal_rx.h | 28 #define HAL_RX_MPDU_INFO_PN_GET_BYTE1(__val) \ 29 le32_get_bits((__val), GENMASK(7, 0)) 31 #define HAL_RX_MPDU_INFO_PN_GET_BYTE2(__val) \ 32 le32_get_bits((__val), GENMASK(15, 8)) 34 #define HAL_RX_MPDU_INFO_PN_GET_BYTE3(__val) \ 35 le32_get_bits((__val), GENMASK(23, 16)) 37 #define HAL_RX_MPDU_INFO_PN_GET_BYTE4(__val) \ 38 le32_get_bits((__val), GENMASK(31, 24))
|