/freebsd/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; } 26 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR unsigned __convert_to_integral(unsigned __val) { return __val; } 28 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR long __convert_to_integral(long __val) { return __val; } in __convert_to_integral() argument 30 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR unsigned long __convert_to_integral(unsigned long __val) { 31 return __val; in __convert_to_integral() argument 34 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR long long __convert_to_integral(long long __val) { return __val; } in __convert_to_integral() argument 25 __convert_to_integral(int __val) __convert_to_integral() argument 37 __convert_to_integral(long long __val) __convert_to_integral() argument 40 __convert_to_integral(unsigned long long __val) __convert_to_integral() argument 45 __convert_to_integral(_Fp __val) __convert_to_integral() argument 49 __convert_to_integral(__int128_t __val) __convert_to_integral() argument 52 __convert_to_integral(__uint128_t __val) __convert_to_integral() argument [all...] |
H A D | to_underlying.h | 24 _LIBCPP_HIDE_FROM_ABI constexpr typename underlying_type<_Tp>::type __to_underlying(_Tp __val) noex… in __to_underlying() argument 25 return static_cast<typename underlying_type<_Tp>::type>(__val); in __to_underlying() 31 [[nodiscard]] _LIBCPP_HIDE_FROM_ABI constexpr underlying_type_t<_Tp> to_underlying(_Tp __val) noexc… in to_underlying() argument 32 return std::__to_underlying(__val); in to_underlying()
|
/freebsd/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/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) { 49 __atomic_store_n(__dest, __val, __order); 53 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_relaxed_store(_ValueType* __dest, _FromType __val) { 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) { 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) { 64 return __atomic_add_fetch(__val, __a, __order); in __libcpp_relaxed_store() argument 75 _ValueType* __val, 80 return __atomic_compare_exchange_n(__val, __expecte [all...] |
/freebsd/contrib/llvm-project/clang/lib/Headers/ |
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)); \ 55 inline __device__ long __FnName(long __val, __Type __offset, \ [all …]
|
H A D | pkuintrin.h | 27 _wrpkru(unsigned int __val) in _wrpkru() argument 29 __builtin_ia32_wrpkru(__val); in _wrpkru()
|
/freebsd/sys/i386/include/ |
H A D | pcpu.h | 139 __pcpu_type(name) __val; \ 141 u_char __b[MIN(sizeof(__val), 4)]; \ 144 __val = (val); \ 145 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \ 146 sizeof(__val) == 4) { \ 150 "r" (*(struct __s *)(void *)&__val) \ 153 *__PCPU_PTR(name) += __val; \ 160 __pcpu_type(name) __val; \ 162 u_char __b[MIN(sizeof(__val), [all...] |
/freebsd/contrib/llvm-project/libcxx/include/__bit/ |
H A D | byteswap.h | 26 [[nodiscard]] _LIBCPP_HIDE_FROM_ABI constexpr _Tp byteswap(_Tp __val) noexcept { in byteswap() argument 28 return __val; in byteswap() 30 return __builtin_bswap16(__val); in byteswap() 32 return __builtin_bswap32(__val); in byteswap() 34 return __builtin_bswap64(__val); in byteswap() 38 return __builtin_bswap128(__val); in byteswap() 40 return static_cast<_Tp>(byteswap(static_cast<uint64_t>(__val))) << 64 | in byteswap() 41 static_cast<_Tp>(byteswap(static_cast<uint64_t>(__val >> 64))); in byteswap()
|
/freebsd/contrib/llvm-project/libcxx/include/__numeric/ |
H A D | adjacent_difference.h | 33 typename iterator_traits<_InputIterator>::value_type __val(*__first); in adjacent_difference() 35 *__result = __val - std::move(__acc); in adjacent_difference() 37 *__result = __val - __acc; in adjacent_difference() 39 __acc = std::move(__val); in adjacent_difference() 52 typename iterator_traits<_InputIterator>::value_type __val(*__first); in adjacent_difference() 54 *__result = __binary_op(__val, std::move(__acc)); in adjacent_difference() 56 *__result = __binary_op(__val, __acc); in adjacent_difference() 58 __acc = std::move(__val); in adjacent_difference()
|
H A D | midpoint.h | 57 _LIBCPP_HIDE_FROM_ABI constexpr int __sign(_Tp __val) { in __sign() argument 58 return (_Tp(0) < __val) - (__val < _Tp(0)); in __sign()
|
/freebsd/contrib/llvm-project/libcxx/src/ |
H A D | atomic.cpp | 57 …atform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention_t __val) { in __libcpp_platform_wait_on_address() argument 59 _LIBCPP_FUTEX(__ptr, FUTEX_WAIT_PRIVATE, __val, &__timeout, 0, 0); in __libcpp_platform_wait_on_address() 77 …atform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention_t __val) { 79 __ulock_wait(UL_COMPARE_AND_WAIT64, const_cast<__cxx_atomic_contention_t*>(__ptr), __val, 0); 96 …atform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention_t __val) { 97 _umtx_op(const_cast<__cxx_atomic_contention_t*>(__ptr), UMTX_OP_WAIT, __val, NULL, NULL); 109 …atform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention_t __val) { 111 … { return !__cxx_nonatomic_compare_equal(__cxx_atomic_load(__ptr, memory_order_relaxed), __val); },
|
/freebsd/sys/sys/ |
H A D | stdatomic.h | 90 #define ATOMIC_VAR_INIT(value) { .__val = (value) } 91 #define atomic_init(obj, value) ((void)((obj)->__val = (value))) 183 ((void)(obj), sizeof((obj)->__val) <= sizeof(void *)) 288 (((__typeof__((object)->__val))0) + (operand)) 294 (_Bool)((*__ep = __sync_val_compare_and_swap(&(object)->__val, \ 304 ((void)(order), __sync_swap(&(object)->__val, desired)) 317 __sync_lock_test_and_set(&(__o)->__val, __d); \ 321 ((void)(order), __sync_fetch_and_add(&(object)->__val, \ 324 ((void)(order), __sync_fetch_and_and(&(object)->__val, operand)) 326 ((void)(order), __sync_fetch_and_or(&(object)->__val, operand)) [all …]
|
/freebsd/contrib/llvm-project/libcxx/include/__pstl/internal/ |
H A D | glue_memory_impl.h |
|
/freebsd/contrib/llvm-project/libcxx/include/__atomic/ |
H A D | cxx_atomic_impl.h | 33 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_assign_volatile(_Tp& __a_value, _Tv const& __val) { in __cxx_atomic_assign_volatile() argument 34 __a_value = __val; in __cxx_atomic_assign_volatile() 37 …DE_FROM_ABI void __cxx_atomic_assign_volatile(_Tp volatile& __a_value, _Tv volatile const& __val) { in __cxx_atomic_assign_volatile() argument 40 volatile const char* __from = reinterpret_cast<volatile const char*>(std::addressof(__val)); in __cxx_atomic_assign_volatile() 59 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(volatile __cxx_atomic_base_impl<_Tp>* __a, _Tp __val) { in __cxx_atomic_init() argument 60 __cxx_atomic_assign_volatile(__a->__a_value, __val); in __cxx_atomic_init() 64 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(__cxx_atomic_base_impl<_Tp>* __a, _Tp __val) { in __cxx_atomic_init() argument 65 __a->__a_value = __val; in __cxx_atomic_init() 78 __cxx_atomic_store(volatile __cxx_atomic_base_impl<_Tp>* __a, _Tp __val, memory_order __order) { in __cxx_atomic_store() argument 79 __atomic_store(std::addressof(__a->__a_value), std::addressof(__val), __to_gcc_order(__order)); in __cxx_atomic_store() [all …]
|
/freebsd/contrib/llvm-project/libcxx/include/__expected/ |
H A D | expected.h | 437 _LIBCPP_HIDE_FROM_ABI constexpr _Tp& __val() { return __repr_.__v.__union_.__v.__val_; } 438 …_LIBCPP_HIDE_FROM_ABI constexpr const _Tp& __val() const { return __repr_.__v.__union_.__v.__val_;… 636 this->__val() = __rhs.__val(); 638 __reinit_expected<unexpect_t, in_place_t, _Err, _Tp>(this->__val(), __rhs.__unex()); 640 __reinit_expected<in_place_t, unexpect_t, _Tp, _Err>(this->__unex(), __rhs.__val()); 655 this->__val() = std::move(__rhs.__val()); 657 … __reinit_expected<unexpect_t, in_place_t, _Err, _Tp>(this->__val(), std::move(__rhs.__unex())); 659 … __reinit_expected<in_place_t, unexpect_t, _Tp, _Err>(this->__unex(), std::move(__rhs.__val())); 674 this->__val() = std::forward<_Up>(__v); 696 __reinit_expected<unexpect_t, in_place_t, _Err, _Tp>(this->__val(), __un.error()); [all …]
|
/freebsd/contrib/llvm-project/libcxx/include/__charconv/ |
H A D | from_chars_integral.h | 80 int __val; member 135 … __first, __last, __value, [](const char* __f, const char* __l, _Tp& __val) -> from_chars_result { in __from_chars_atoi() 141 __val = __a + __b; in __from_chars_atoi() 184 [](const char* __p, const char* __lastp, _Tp& __val, int __b) -> from_chars_result { in __from_chars_integral() 188 _Tp __x = __in_pattern(*__p++, __b).__val, __y = 0; in __from_chars_integral() 193 __x = __x * __b + __c.__val; in __from_chars_integral() 197 __y = __c.__val; in __from_chars_integral() 206 __val = __x + __y; in __from_chars_integral()
|
/freebsd/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/sys/contrib/openzfs/include/os/linux/kernel/linux/ |
H A D | simd_aarch64.h | 77 unsigned long __val; \ 78 asm("mrs %0, "#id : "=r" (__val)); \ 79 __val; \
|
/freebsd/contrib/llvm-project/libcxx/include/__system_error/ |
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;
|
H A D | error_code.h | 50 _LIBCPP_HIDE_FROM_ABI error_code(int __val, const error_category& __cat) _NOEXCEPT : __val_(__val), __cat_(&__cat) {} in error_code() argument 58 _LIBCPP_HIDE_FROM_ABI void assign(int __val, const error_category& __cat) _NOEXCEPT { 59 __val_ = __val; in assign() argument
|
/freebsd/contrib/llvm-project/libcxx/include/__chrono/ |
H A D | weekday.h | 39 _LIBCPP_HIDE_FROM_ABI inline explicit constexpr weekday(unsigned __val) noexcept in weekday() argument 40 : __wd_(static_cast<unsigned char>(__val == 7 ? 0 : __val)) {} in weekday() 155 …E_FROM_ABI explicit constexpr weekday_last(const chrono::weekday& __val) noexcept : __wd_{__val} {} in weekday_last() argument
|
/freebsd/sys/contrib/dev/athk/ath12k/ |
H A D | hal_rx.h | 28 #define HAL_RX_MPDU_INFO_PN_GET_BYTE1(__val) \ argument 29 le32_get_bits((__val), GENMASK(7, 0)) 31 #define HAL_RX_MPDU_INFO_PN_GET_BYTE2(__val) \ argument 32 le32_get_bits((__val), GENMASK(15, 8)) 34 #define HAL_RX_MPDU_INFO_PN_GET_BYTE3(__val) \ argument 35 le32_get_bits((__val), GENMASK(23, 16)) 37 #define HAL_RX_MPDU_INFO_PN_GET_BYTE4(__val) \ argument 38 le32_get_bits((__val), GENMASK(31, 24))
|
/freebsd/contrib/llvm-project/libcxx/include/__functional/ |
H A D | hash.h | 131 _LIBCPP_HIDE_FROM_ABI static _Size __rotate(_Size __val, int __shift) { 132 return __shift == 0 ? __val : ((__val >> __shift) | (__val << (64 - __shift))); 135 _LIBCPP_HIDE_FROM_ABI static _Size __rotate_by_at_least_1(_Size __val, int __shift) { 136 return (__val >> __shift) | (__val << (64 - __shift)); 139 _LIBCPP_HIDE_FROM_ABI static _Size __shift_mix(_Size __val) { return __val ^ (__val >> 47); }
|
/freebsd/contrib/llvm-project/libcxx/include/__iterator/ |
H A D | aliasing_iterator.h | 104 _Alias __val; member 105 __builtin_memcpy(&__val, std::__to_address(__base_), sizeof(value_type)); 106 return __val;
|