Home
last modified time | relevance | path

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

123

/freebsd/contrib/llvm-project/libcxx/include/__cxx03/__utility/
H A Dconvert_to_integral.h24 inline _LIBCPP_HIDE_FROM_ABI int __convert_to_integral(int __val) { return __val; } in __convert_to_integral() argument
26 inline _LIBCPP_HIDE_FROM_ABI unsigned __convert_to_integral(unsigned __val) { return __val; } in __convert_to_integral() argument
28 inline _LIBCPP_HIDE_FROM_ABI long __convert_to_integral(long __val) { return __val; } in __convert_to_integral() argument
30 …ne _LIBCPP_HIDE_FROM_ABI unsigned long __convert_to_integral(unsigned long __val) { return __val; } in __convert_to_integral() argument
32 inline _LIBCPP_HIDE_FROM_ABI long long __convert_to_integral(long long __val) { return __val; } in __convert_to_integral() argument
34 …_HIDE_FROM_ABI unsigned long long __convert_to_integral(unsigned long long __val) { return __val; } in __convert_to_integral() argument
37 inline _LIBCPP_HIDE_FROM_ABI long long __convert_to_integral(_Fp __val) { in __convert_to_integral() argument
38 return __val; in __convert_to_integral()
42 inline _LIBCPP_HIDE_FROM_ABI __int128_t __convert_to_integral(__int128_t __val) { return __val; } in __convert_to_integral() argument
44 inline _LIBCPP_HIDE_FROM_ABI __uint128_t __convert_to_integral(__uint128_t __val) { return __val; } in __convert_to_integral() argument
[all …]
/freebsd/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
30 … _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR unsigned long __convert_to_integral(unsigned long __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
36 …IDE_FROM_ABI _LIBCPP_CONSTEXPR unsigned long long __convert_to_integral(unsigned long long __val) { in __convert_to_integral() argument
37 return __val; in __convert_to_integral()
41 inline _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR long long __convert_to_integral(_Fp __val) { in __convert_to_integral() argument
42 return __val; in __convert_to_integral()
[all …]
H A Dto_underlying.h24 …__]] _LIBCPP_HIDE_FROM_ABI constexpr __underlying_type_t<_Tp> __to_underlying(_Tp __val) noexcept { in __to_underlying() argument
25 return static_cast<__underlying_type_t<_Tp>>(__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 Dpcpu.h152 __pcpu_type(name) __val; \
154 __val = (val); \
155 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \
156 sizeof(__val) == 4 || sizeof(__val) == 8) { \
157 __pc->name += __val; \
159 *__PCPU_PTR(name) += __val; \
167 __pcpu_type(name) __val; \
169 __val
[all...]
/freebsd/contrib/llvm-project/libcxx/src/include/
H A Datomic_support.h48 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_atomic_store(_ValueType* __dest, _FromType __val, int __…
49 __atomic_store_n(__dest, __val, __order);
53 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_relaxed_store(_ValueType* __dest, _FromType __val) { in __libcpp_relaxed_store() argument
54 __atomic_store_n(__dest, __val, _AO_Relaxed); in __libcpp_relaxed_store()
58 inline _LIBCPP_HIDE_FROM_ABI _ValueType __libcpp_atomic_load(_ValueType const* __val, int __order =…
59 return __atomic_load_n(__val, __order);
63 inline _LIBCPP_HIDE_FROM_ABI _ValueType __libcpp_atomic_add(_ValueType* __val, _AddType __a, int __…
64 return __atomic_add_fetch(__val, __a, __order);
75 _ValueType* __val,
80 …return __atomic_compare_exchange_n(__val, __expected, __after, true, __success_order, __fail_order…
[all …]
/freebsd/sys/i386/include/
H A Dpcpu.h140 __pcpu_type(name) __val; \
142 u_char __b[MIN(sizeof(__val), 4)]; \
145 __val = (val); \
146 if (sizeof(__val) == 1 || sizeof(__val) == 2 || \
147 sizeof(__val) == 4) { \
151 "r" (*(struct __s *)(void *)&__val) \
154 *__PCPU_PTR(name) += __val; \
161 __pcpu_type(name) __val; \
163 u_char __b[MIN(sizeof(__val), 4)]; \
166 __val = (val); \
[all …]
/freebsd/contrib/llvm-project/clang/lib/Headers/
H A D__clang_cuda_intrinsics.h25 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 …]
/freebsd/contrib/llvm-project/libcxx/include/__bit/
H A Dbyteswap.h26 [[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 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()
/freebsd/contrib/llvm-project/libcxx/include/__cxx03/__numeric/
H A Dadjacent_difference.h33 typename iterator_traits<_InputIterator>::value_type __val(*__first); in adjacent_difference()
34 *__result = __val - __acc; in adjacent_difference()
35 __acc = std::move(__val); in adjacent_difference()
48 typename iterator_traits<_InputIterator>::value_type __val(*__first); in adjacent_difference()
49 *__result = __binary_op(__val, __acc); in adjacent_difference()
50 __acc = std::move(__val); in adjacent_difference()
/freebsd/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()
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, nullptr, nullptr);
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 Dstdatomic.h97 #define ATOMIC_VAR_INIT(value) { .__val = (value) }
107 #define atomic_init(obj, value) ((void)((obj)->__val = (value)))
195 ((void)(obj), sizeof((obj)->__val) <= sizeof(void *))
307 (((__typeof__((object)->__val))0) + (operand))
311 ((void)(order), __sync_fetch_and_add(&(object)->__val, 0))
315 ((void)(order), __sync_swap(&(object)->__val, desired))
328 __sync_lock_test_and_set(&(__o)->__val, __d); \
335 (_Bool)((*__ep = __sync_val_compare_and_swap(&(object)->__val, \
344 ((void)(order), __sync_fetch_and_add(&(object)->__val, \
347 ((void)(order), __sync_fetch_and_sub(&(object)->__val, \
[all …]
/freebsd/contrib/llvm-project/libcxx/include/__atomic/support/
H A Dgcc.h34 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_assign_volatile(_Tp& __a_value, _Tv const& __val) { in __cxx_atomic_assign_volatile() argument
35 __a_value = __val; in __cxx_atomic_assign_volatile()
38 …DE_FROM_ABI void __cxx_atomic_assign_volatile(_Tp volatile& __a_value, _Tv volatile const& __val) { in __cxx_atomic_assign_volatile() argument
41 volatile const char* __from = reinterpret_cast<volatile const char*>(std::addressof(__val)); in __cxx_atomic_assign_volatile()
60 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(volatile __cxx_atomic_base_impl<_Tp>* __a, _Tp __val) { in __cxx_atomic_init() argument
61 __cxx_atomic_assign_volatile(__a->__a_value, __val); in __cxx_atomic_init()
65 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(__cxx_atomic_base_impl<_Tp>* __a, _Tp __val) { in __cxx_atomic_init() argument
66 __a->__a_value = __val; in __cxx_atomic_init()
79 __cxx_atomic_store(volatile __cxx_atomic_base_impl<_Tp>* __a, _Tp __val, memory_order __order) { in __cxx_atomic_store() argument
80 __atomic_store(std::addressof(__a->__a_value), std::addressof(__val), __to_gcc_order(__order)); in __cxx_atomic_store()
[all …]
H A Dc11.h52 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(__cxx_atomic_base_impl<_Tp> volatile* __a, _Tp __val) … in __cxx_atomic_init() argument
53 __c11_atomic_init(std::addressof(__a->__a_value), __val); in __cxx_atomic_init()
56 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(__cxx_atomic_base_impl<_Tp>* __a, _Tp __val) _NOEXCEPT… in __cxx_atomic_init() argument
57 __c11_atomic_init(std::addressof(__a->__a_value), __val); in __cxx_atomic_init()
62 __cxx_atomic_store(__cxx_atomic_base_impl<_Tp> volatile* __a, _Tp __val, memory_order __order) _NOE… in __cxx_atomic_store() argument
63 …__c11_atomic_store(std::addressof(__a->__a_value), __val, static_cast<__memory_order_underlying_t>… in __cxx_atomic_store()
67 __cxx_atomic_store(__cxx_atomic_base_impl<_Tp>* __a, _Tp __val, memory_order __order) _NOEXCEPT { in __cxx_atomic_store() argument
68 …__c11_atomic_store(std::addressof(__a->__a_value), __val, static_cast<__memory_order_underlying_t>… in __cxx_atomic_store()
/freebsd/contrib/llvm-project/libcxx/include/__pstl/internal/
H A Dglue_memory_impl.h
/freebsd/contrib/llvm-project/libcxx/include/__cxx03/__atomic/
H A Dcxx_atomic_impl.h33 _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()
53 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(volatile __cxx_atomic_base_impl<_Tp>* __a, _Tp __val) { in __cxx_atomic_init() argument
54 __cxx_atomic_assign_volatile(__a->__a_value, __val); in __cxx_atomic_init()
58 _LIBCPP_HIDE_FROM_ABI void __cxx_atomic_init(__cxx_atomic_base_impl<_Tp>* __a, _Tp __val) { in __cxx_atomic_init() argument
59 __a->__a_value = __val; in __cxx_atomic_init()
72 __cxx_atomic_store(volatile __cxx_atomic_base_impl<_Tp>* __a, _Tp __val, memory_order __order) { in __cxx_atomic_store() argument
73 __atomic_store(std::addressof(__a->__a_value), std::addressof(__val), __to_gcc_order(__order)); in __cxx_atomic_store()
[all …]
/freebsd/sys/compat/linuxkpi/common/include/linux/
H A Doverflow.h75 type __val; \
76 __builtin_add_overflow(a, b, &__val); \
77 __val; \
121 type __val; \
122 __builtin_sub_overflow(a, b, &__val); \
123 __val; \
167 type __val; \
168 __builtin_mul_overflow(a, b, &__val); \
169 __val; \
H A Dminmax.h82 typeof(array[0]) __val = array[0]; \
84 __val = op(__val, array[__i]); \
85 __val; })
/freebsd/contrib/llvm-project/libcxx/include/__expected/
H A Dexpected.h441 _LIBCPP_HIDE_FROM_ABI constexpr _Tp& __val() { return __repr_.__v.__union_.__v.__val_; }
442 …_LIBCPP_HIDE_FROM_ABI constexpr const _Tp& __val() const { return __repr_.__v.__union_.__v.__val_;…
641 this->__val() = __rhs.__val();
643 __reinit_expected<unexpect_t, in_place_t, _Err, _Tp>(this->__val(), __rhs.__unex());
645 __reinit_expected<in_place_t, unexpect_t, _Tp, _Err>(this->__unex(), __rhs.__val());
660 this->__val() = std::move(__rhs.__val());
662 … __reinit_expected<unexpect_t, in_place_t, _Err, _Tp>(this->__val(), std::move(__rhs.__unex()));
664 … __reinit_expected<in_place_t, unexpect_t, _Tp, _Err>(this->__unex(), std::move(__rhs.__val()));
679 this->__val() = std::forward<_Up>(__v);
701 __reinit_expected<unexpect_t, in_place_t, _Err, _Tp>(this->__val(), __un.error());
[all …]
/freebsd/contrib/llvm-project/libcxx/include/__charconv/
H A Dfrom_chars_integral.h80 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 Dranges_replace.h41 auto __pred = [&](const auto& __val) -> bool { return __val == __old_value; };
50 auto __pred = [&](auto&& __val) -> bool { return __val == __old_value; };
H A Dranges_remove_copy.h51 auto __pred = [&](auto&& __val) -> bool { return __value == __val; };
60 auto __pred = [&](auto&& __val) -> bool { return __value == __val; };
/freebsd/sys/contrib/openzfs/include/os/linux/kernel/linux/
H A Dsimd_aarch64.h68 unsigned long __val; \
69 asm("mrs %0, "#id : "=r" (__val)); \
70 __val; \
/freebsd/contrib/llvm-project/libcxx/include/__cxx03/__system_error/
H A Derror_condition.h49 _LIBCPP_HIDE_FROM_ABI error_condition(int __val, const error_category& __cat) _NOEXCEPT
50 : __val_(__val),
59 _LIBCPP_HIDE_FROM_ABI void assign(int __val, const error_category& __cat) _NOEXCEPT {
60 __val_ = __val;
/freebsd/contrib/llvm-project/libcxx/include/__system_error/
H A Derror_condition.h56 _LIBCPP_HIDE_FROM_ABI error_condition(int __val, const error_category& __cat) _NOEXCEPT
57 : __val_(__val),
66 _LIBCPP_HIDE_FROM_ABI void assign(int __val, const error_category& __cat) _NOEXCEPT {
67 __val_ = __val;

123