Home
last modified time | relevance | path

Searched refs:__val (Results 1 – 25 of 46) sorted by relevance

12

/freebsd-14.2/contrib/llvm-project/libcxx/include/__utility/
H A Dconvert_to_integral.h24 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR int __convert_to_integral(int __val) { return __val;… in __convert_to_integral() argument
26 …PP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR unsigned __convert_to_integral(unsigned __val) { return __val; } in __convert_to_integral() argument
28 …ne _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR long __convert_to_integral(long __val) { return __val; } in __convert_to_integral() argument
31 return __val; in __convert_to_integral()
34 …_HIDE_FROM_ABI _LIBCPP_CONSTEXPR long long __convert_to_integral(long long __val) { return __val; } in __convert_to_integral() argument
37 return __val; in __convert_to_integral()
42 return __val; in __convert_to_integral()
46 …IDE_FROM_ABI _LIBCPP_CONSTEXPR __int128_t __convert_to_integral(__int128_t __val) { return __val; } in __convert_to_integral() argument
48 …E_FROM_ABI _LIBCPP_CONSTEXPR __uint128_t __convert_to_integral(__uint128_t __val) { return __val; } in __convert_to_integral() argument
62 __convert_to_integral(_Tp __val) {
[all …]
H A Dto_underlying.h24 _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 …CARD_EXT _LIBCPP_HIDE_FROM_ABI constexpr underlying_type_t<_Tp> to_underlying(_Tp __val) noexcept { in to_underlying() argument
32 return std::__to_underlying(__val); in to_underlying()
/freebsd-14.2/sys/amd64/include/
H A Dpcpu.h153 __val = (val); \
154 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \
155 sizeof(__val) == 4 || sizeof(__val) == 8) { \
168 __val = (val); \
169 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \
170 sizeof(__val) == 4 || sizeof(__val) == 8) { \
227 __val = (val); \
228 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \
229 sizeof(__val) == 4 || sizeof(__val) == 8) { \
248 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \
[all …]
/freebsd-14.2/contrib/llvm-project/libcxx/src/include/
H A Datomic_support.h49 __atomic_store_n(__dest, __val, __order);
54 __atomic_store_n(__dest, __val, _AO_Relaxed); in __libcpp_relaxed_store()
59 return __atomic_load_n(__val, __order);
75 _ValueType* __val,
89 *__dest = __val;
94 *__dest = __val;
99 return *__val;
104 return *__val += __a;
118 if (*__val == *__expected) {
119 *__val = __after;
[all …]
/freebsd-14.2/contrib/llvm-project/clang/lib/Headers/
H A D__clang_cuda_intrinsics.h48 memcpy(&__tmp, &__val, sizeof(__val)); \
81 memcpy(&__tmp, &__val, sizeof(__val)); \
132 memcpy(&__tmp, &__val, sizeof(__val)); \
167 memcpy(&__tmp, &__val, sizeof(__val)); \
655 __device__ inline float2 atomicAdd(float2 *__ptr, float2 __val) { in atomicAdd() argument
659 : "l"(__ptr), "f"(__val.x), "f"(__val.y)); in atomicAdd()
667 : "l"(__ptr), "f"(__val.x), "f"(__val.y)); in atomicAdd_block()
675 : "l"(__ptr), "f"(__val.x), "f"(__val.y)); in atomicAdd_system()
683 : "l"(__ptr), "f"(__val.x), "f"(__val.y), "f"(__val.z), "f"(__val.w)); in atomicAdd()
692 : "l"(__ptr), "f"(__val.x), "f"(__val.y), "f"(__val.z), "f"(__val.w)); in atomicAdd_block()
[all …]
H A Dpkuintrin.h27 _wrpkru(unsigned int __val) in _wrpkru() argument
29 __builtin_ia32_wrpkru(__val); in _wrpkru()
/freebsd-14.2/sys/i386/include/
H A Dpcpu.h148 __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) { \
161 *__PCPU_PTR(name) += __val; \
168 __pcpu_type(name) __val; \
173 __val = (val); \
174 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \
175 sizeof(__val) == 4) { \
[all …]
/freebsd-14.2/contrib/llvm-project/libcxx/include/__bit/
H A Dbyteswap.h26 _LIBCPP_NODISCARD_EXT _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-14.2/contrib/llvm-project/libcxx/include/__numeric/
H A Dadjacent_difference.h33 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 Dmidpoint.h57 _LIBCPP_HIDE_FROM_ABI constexpr int __sign(_Tp __val) { in __sign() argument
58 return (_Tp(0) < __val) - (__val < _Tp(0)); in __sign()
/freebsd-14.2/contrib/llvm-project/libcxx/src/
H A Datomic.cpp57 …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()
76 …atform_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 …atform_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 …atform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention_t __val) {
108 … { return !__cxx_nonatomic_compare_equal(__cxx_atomic_load(__ptr, memory_order_relaxed), __val); },
/freebsd-14.2/sys/sys/
H A Dstdatomic.h89 #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, \
325 ((void)(order), __sync_fetch_and_or(&(object)->__val, operand))
327 ((void)(order), __sync_fetch_and_sub(&(object)->__val, \
[all …]
/freebsd-14.2/contrib/llvm-project/libcxx/include/__atomic/
H A Dcxx_atomic_impl.h35 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_assign_volatile(_Tp& __a_value, _Tv const& __val) { in __cxx_atomic_assign_volatile() argument
36 __a_value = __val; in __cxx_atomic_assign_volatile()
92 __cxx_atomic_assign_volatile(__a->__a_value, __val); in __cxx_atomic_init()
96 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(__cxx_atomic_base_impl<_Tp>* __a, _Tp __val) { in __cxx_atomic_init() argument
97 __a->__a_value = __val; in __cxx_atomic_init()
321 __c11_atomic_init(std::addressof(__a->__a_value), __val);
325 __c11_atomic_init(std::addressof(__a->__a_value), __val);
585 __cxx_atomic_assign_volatile(__a->__a_value, __val);
589 __a->__a_value = __val;
595 __cxx_atomic_assign_volatile(__a->__a_value, __val);
[all …]
H A Datomic_sync.h92 _Tp __val; member
95 return !std::__cxx_nonatomic_compare_equal(std::__cxx_atomic_load(__a, __order), __val); in operator()
101 __cxx_atomic_wait(_Atp* __a, _Tp const __val, memory_order __order) { in __cxx_atomic_wait() argument
102 __cxx_atomic_wait_test_fn_impl<_Atp, _Tp> __test_fn = {__a, __val, __order}; in __cxx_atomic_wait()
/freebsd-14.2/contrib/llvm-project/libcxx/include/__charconv/
H A Dfrom_chars_integral.h79 int __val; member
134 … __first, __last, __value, [](const char* __f, const char* __l, _Tp& __val) -> from_chars_result { in __from_chars_atoi()
140 __val = __a + __b; in __from_chars_atoi()
183 [](const char* __p, const char* __lastp, _Tp& __val, int __b) -> from_chars_result { in __from_chars_integral()
187 _Tp __x = __in_pattern(*__p++, __b).__val, __y = 0; in __from_chars_integral()
192 __x = __x * __b + __c.__val; in __from_chars_integral()
196 __y = __c.__val; in __from_chars_integral()
205 __val = __x + __y; in __from_chars_integral()
/freebsd-14.2/contrib/llvm-project/libcxx/include/__algorithm/
H A Dranges_replace.h42 auto __pred = [&](const auto& __val) -> bool { return __val == __old_value; };
51 auto __pred = [&](auto&& __val) -> bool { return __val == __old_value; };
H A Dranges_remove_copy.h53 auto __pred = [&](auto&& __val) -> bool { return __value == __val; };
62 auto __pred = [&](auto&& __val) -> bool { return __value == __val; };
/freebsd-14.2/contrib/llvm-project/libcxx/include/__expected/
H A Dexpected.h638 this->__val() = __rhs.__val();
657 this->__val() = std::move(__rhs.__val());
721 return this->__val();
729 return this->__val();
767 swap(this->__val(), __rhs.__val());
803 return this->__val();
809 return this->__val();
815 return std::move(this->__val());
833 return this->__val();
841 return this->__val();
[all …]
/freebsd-14.2/sys/contrib/openzfs/include/os/linux/kernel/linux/
H A Dsimd_aarch64.h87 unsigned long __val; \
88 asm("mrs %0, "#id : "=r" (__val)); \
89 __val; \
/freebsd-14.2/contrib/llvm-project/libcxx/include/__system_error/
H A Derror_condition.h57 _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 Derror_code.h50 …_LIBCPP_HIDE_FROM_ABI error_code(int __val, const error_category& __cat) _NOEXCEPT : __val_(__val)… in error_code() argument
58 _LIBCPP_HIDE_FROM_ABI void assign(int __val, const error_category& __cat) _NOEXCEPT { in assign() argument
59 __val_ = __val; in assign()
/freebsd-14.2/contrib/llvm-project/libcxx/include/__chrono/
H A Dweekday.h39 _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()
152 …E_FROM_ABI explicit constexpr weekday_last(const chrono::weekday& __val) noexcept : __wd_{__val} {} in weekday_last() argument
H A Dday.h33 _LIBCPP_HIDE_FROM_ABI explicit inline constexpr day(unsigned __val) noexcept in day() argument
34 : __d_(static_cast<unsigned char>(__val)) {} in day()
/freebsd-14.2/sys/contrib/dev/athk/ath12k/
H A Dhal_rx.h28 #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-14.2/contrib/llvm-project/libcxx/include/__functional/
H A Dhash.h136 _LIBCPP_HIDE_FROM_ABI static _Size __rotate(_Size __val, int __shift) {
137 return __shift == 0 ? __val : ((__val >> __shift) | (__val << (64 - __shift)));
140 _LIBCPP_HIDE_FROM_ABI static _Size __rotate_by_at_least_1(_Size __val, int __shift) {
141 return (__val >> __shift) | (__val << (64 - __shift));
144 _LIBCPP_HIDE_FROM_ABI static _Size __shift_mix(_Size __val) { return __val ^ (__val >> 47); }

12