Home
last modified time | relevance | path

Searched refs:__ptr (Results 1 – 25 of 78) sorted by relevance

1234

/freebsd/contrib/llvm-project/libcxx/src/include/
H A Dfrom_chars_floating_point.h41 __from_chars_floating_point_inf(const char* const __first, const char* __last, const char* __ptr, b… in __from_chars_floating_point_inf() argument
42 if (__last - __ptr < 2) [[unlikely]] in __from_chars_floating_point_inf()
45 if (std::tolower(__ptr[0]) != 'n' || std::tolower(__ptr[1]) != 'f') [[unlikely]] in __from_chars_floating_point_inf()
48 __ptr += 2; in __from_chars_floating_point_inf()
55 if (__last - __ptr >= 5 // in __from_chars_floating_point_inf()
56 && std::tolower(__ptr[0]) == 'i' // in __from_chars_floating_point_inf()
57 && std::tolower(__ptr[1]) == 'n' // in __from_chars_floating_point_inf()
58 && std::tolower(__ptr[2]) == 'i' // in __from_chars_floating_point_inf()
59 && std::tolower(__ptr[3]) == 't' // in __from_chars_floating_point_inf()
60 && std::tolower(__ptr[4]) == 'y') in __from_chars_floating_point_inf()
[all …]
H A Doverridable_function.h84 uintptr_t __ptr = reinterpret_cast<uintptr_t>(_Func); in __is_function_overridden() local
91 …__ptr = reinterpret_cast<uintptr_t>(ptrauth_strip(reinterpret_cast<void*>(__ptr), ptrauth_key_func… in __is_function_overridden()
95 return __ptr < __start || __ptr > __end; in __is_function_overridden()
118 uintptr_t __ptr = reinterpret_cast<uintptr_t>(_Func);
122 …__ptr = reinterpret_cast<uintptr_t>(ptrauth_strip(reinterpret_cast<void*>(__ptr), ptrauth_key_func…
125 return __ptr < __start || __ptr > __end;
/freebsd/sys/sys/
H A Dsmr_types.h55 type __ptr; /* Do not access directly */ \
63 (__typeof((p)->__ptr))atomic_load_acq_ptr( \
64 (const uintptr_t *)&(p)->__ptr); \
74 (__typeof((p)->__ptr))atomic_load_ptr( \
75 (const uintptr_t *)&(p)->__ptr); \
88 __typeof((p)->__ptr) _v = (v); \
89 atomic_store_rel_ptr((uintptr_t *)&(p)->__ptr, (uintptr_t)_v); \
101 __typeof((p)->__ptr) _v = (v); \
104 (__typeof((p)->__ptr))atomic_swap_ptr( \
105 (uintptr_t *)&(p)->__ptr, (uintptr_t)_v); \
[all …]
H A Dsysctl.h425 bool *__ptr = (ptr); \
429 __ptr, val, sysctl_handle_bool, "CU", __DESCR(descr), \
445 int8_t *__ptr = (ptr); \
450 __ptr, val, sysctl_handle_8, "C", __DESCR(descr), NULL); \
465 uint8_t *__ptr = (ptr); \
470 __ptr, val, sysctl_handle_8, "CU", __DESCR(descr), NULL); \
485 int16_t *__ptr = (ptr); \
490 __ptr, val, sysctl_handle_16, "S", __DESCR(descr), NULL); \
505 uint16_t *__ptr = (ptr); \
510 __ptr, val, sysctl_handle_16, "SU", __DESCR(descr), NULL); \
[all …]
/freebsd/contrib/llvm-project/clang/lib/Headers/
H A D__clang_cuda_intrinsics.h487 inline __device__ __DeclType __FnName(const __DeclType *__ptr) { \
489 asm(__AsmOp " %0, [%1];" : __AsmType(__ret) : "l"(__ptr)__Clobber); \
496 inline __device__ __DeclType __FnName(const __DeclType *__ptr) { \
501 : "l"(__ptr)__Clobber); \
511 inline __device__ __DeclType __FnName(const __DeclType *__ptr) { \
517 : "l"(__ptr)__Clobber); \
565 inline __device__ long __ldcg(const long *__ptr) { in __ldcg() argument
568 asm("ld.global.cg.s64 %0, [%1];" : "=l"(__ret) : "l"(__ptr)); in __ldcg()
570 asm("ld.global.cg.s32 %0, [%1];" : "=r"(__ret) : "l"(__ptr)); in __ldcg()
631 inline __device__ long __ldcv(const long *__ptr) { in __ldcv() argument
[all …]
H A D__clang_hip_runtime_wrapper.h73 __attribute__((noinline, weak)) __device__ void free(void *__ptr) { in free() argument
75 __asan_free_impl((unsigned long long)__ptr, __pc); in free()
81 __attribute__((weak)) inline __device__ void free(void *__ptr) { in free() argument
82 __ockl_dm_dealloc((unsigned long long)__ptr); in free()
88 __device__ void *__hip_free(void *__ptr);
92 __attribute__((weak)) inline __device__ void free(void *__ptr) {
93 __hip_free(__ptr);
100 __attribute__((weak)) inline __device__ void free(void *__ptr) {
H A D__clang_cuda_texture_intrinsics.h21 #define __nv_tex_surf_handler(__op, __ptr, ...) \ argument
23 ::__cuda_tex::__Tag<::__cuda_tex::__tex_op_hash(__op)>>(__ptr, \
759 static __device__ void __run(__type *__ptr, cudaSurfaceObject_t obj, \
788 static __device__ void __run(__type *__ptr, cudaSurfaceObject_t obj, \
814 #define __SW_ASM_ARGS(__type) (__type(*__ptr))
815 #define __SW_ASM_ARGS1(__type) (__type(__ptr->x))
816 #define __SW_ASM_ARGS2(__type) (__type(__ptr->x), __type(__ptr->y))
818 (__type(__ptr->x), __type(__ptr->y), __type(__ptr->z), __type(__ptr->w))
1015 __device__ static void __tex_fetch_impl(__surface_op_tag, __DataT *__ptr,
1018 __surf_read_write_v2<__op, __DataT>::__run(__ptr, __handle, __args...);
[all …]
H A Dvecintrin.h33 __lcbb(const void *__ptr, unsigned short __len)
317 vec_insert_and_zero(const signed char *__ptr) { in vec_insert_and_zero() argument
319 __vec[7] = *__ptr; in vec_insert_and_zero()
324 vec_insert_and_zero(const unsigned char *__ptr) { in vec_insert_and_zero() argument
326 __vec[7] = *__ptr; in vec_insert_and_zero()
331 vec_insert_and_zero(const signed short *__ptr) { in vec_insert_and_zero() argument
333 __vec[3] = *__ptr; in vec_insert_and_zero()
338 vec_insert_and_zero(const unsigned short *__ptr) { in vec_insert_and_zero() argument
340 __vec[3] = *__ptr; in vec_insert_and_zero()
345 vec_insert_and_zero(const signed int *__ptr) { in vec_insert_and_zero() argument
[all …]
/freebsd/contrib/llvm-project/libcxx/src/
H A Datomic.cpp57 __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention… in __libcpp_platform_wait_on_address() argument
59 _LIBCPP_FUTEX(__ptr, FUTEX_WAIT_PRIVATE, __val, &__timeout, 0, 0); in __libcpp_platform_wait_on_address()
62 static void __libcpp_platform_wake_by_address(__cxx_atomic_contention_t const volatile* __ptr, bool… in __libcpp_platform_wake_by_address() argument
63 _LIBCPP_FUTEX(__ptr, FUTEX_WAKE_PRIVATE, __notify_one ? 1 : INT_MAX, 0, 0, 0); in __libcpp_platform_wake_by_address()
77 __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention…
79 __ulock_wait(UL_COMPARE_AND_WAIT64, const_cast<__cxx_atomic_contention_t*>(__ptr), __val, 0);
82 static void __libcpp_platform_wake_by_address(__cxx_atomic_contention_t const volatile* __ptr, bool…
85 …_AND_WAIT64 | (__notify_one ? 0 : ULF_WAKE_ALL), const_cast<__cxx_atomic_contention_t*>(__ptr), 0);
96 __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention…
97 _umtx_op(const_cast<__cxx_atomic_contention_t*>(__ptr), UMTX_OP_WAIT, __val, nullptr, nullptr);
[all …]
/freebsd/contrib/llvm-project/libcxx/include/__memory/
H A Dunique_temporary_buffer.h37 _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR_SINCE_CXX23 void operator()(_Tp* __ptr) _NOEXCEPT { in operator()
39 allocator<_Tp>().deallocate(__ptr, __count_); in operator()
43 std::__libcpp_deallocate_unsized<_Tp>(__ptr); in operator()
60 _Tp* __ptr = nullptr; in __allocate_unique_temporary_buffer() local
69 __ptr = static_cast<_Tp*>(::operator new(__count * sizeof(_Tp), __al, nothrow)); in __allocate_unique_temporary_buffer()
71 __ptr = static_cast<_Tp*>(::operator new(__count * sizeof(_Tp), nothrow)); in __allocate_unique_temporary_buffer()
79 __ptr = static_cast<_Tp*>(::operator new(__count * sizeof(_Tp), nothrow)); in __allocate_unique_temporary_buffer()
82 if (__ptr) { in __allocate_unique_temporary_buffer()
88 return __unique_buffer_type(__ptr, __deleter_type(__count)); in __allocate_unique_temporary_buffer()
H A Dassume_aligned.h26 …discard__]] _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR_SINCE_CXX14 _Tp* __assume_aligned(_Tp* __ptr) { in __assume_aligned() argument
30 (void)__builtin_assume_aligned(__ptr, _Np); in __assume_aligned()
31 return __ptr; in __assume_aligned()
34 reinterpret_cast<uintptr_t>(__ptr) % _Np == 0, "Alignment assumption is violated"); in __assume_aligned()
35 return static_cast<_Tp*>(__builtin_assume_aligned(__ptr, _Np)); in __assume_aligned()
42 [[nodiscard]] _LIBCPP_HIDE_FROM_ABI constexpr _Tp* assume_aligned(_Tp* __ptr) { in assume_aligned() argument
43 return std::__assume_aligned<_Np>(__ptr); in assume_aligned()
H A Daligned_alloc.h51 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_aligned_free(void* __ptr) { in __libcpp_aligned_free() argument
53 ::_aligned_free(__ptr); in __libcpp_aligned_free()
55 ::free(__ptr); in __libcpp_aligned_free()
H A Dunique_ptr.h74 _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR_SINCE_CXX23 void operator()(_Tp* __ptr) const _NOEXCEPT { in operator()
77 delete __ptr; in operator() local
89 _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR_SINCE_CXX23 void operator()(_Up* __ptr) const _NOEXCEPT {
91 delete[] __ptr;
349 _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR bool __in_bounds(_Tp* __ptr, size_t __index) const {
354 size_t __cookie = std::__get_array_cookie(__ptr);
379 _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR bool __in_bounds(_Tp* __ptr, size_t __index) const {
382 size_t __cookie = std::__get_array_cookie(__ptr);
487 _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR_SINCE_CXX23 explicit unique_ptr(_Pp __ptr) _NOEXCEPT
488 : __ptr_(__ptr),
[all …]
/freebsd/contrib/llvm-project/libcxx/include/__cxx03/__utility/
H A Dis_pointer_in_range.h37 __is_pointer_in_range(const _Tp* __begin, const _Tp* __end, const _Up* __ptr) {
43 if (!__builtin_constant_p(__begin <= __ptr && __ptr < __end))
47 return !__less<>()(__ptr, __begin) && __less<>()(__ptr, __end);
52 __is_pointer_in_range(const _Tp* __begin, const _Tp* __end, const _Up* __ptr) {
56 return reinterpret_cast<const char*>(__begin) <= reinterpret_cast<const char*>(__ptr) &&
57 reinterpret_cast<const char*>(__ptr) < reinterpret_cast<const char*>(__end);
/freebsd/contrib/llvm-project/libcxx/include/__utility/
H A Dis_pointer_in_range.h37 __is_pointer_in_range(const _Tp* __begin, const _Tp* __end, const _Up* __ptr) {
43 if (!__builtin_constant_p(__begin <= __ptr && __ptr < __end))
47 return !__less<>()(__ptr, __begin) && __less<>()(__ptr, __end);
52 __is_pointer_in_range(const _Tp* __begin, const _Tp* __end, const _Up* __ptr) {
56 return reinterpret_cast<const char*>(__begin) <= reinterpret_cast<const char*>(__ptr) &&
57 reinterpret_cast<const char*>(__ptr) < reinterpret_cast<const char*>(__end);
/freebsd/contrib/llvm-project/libcxx/include/__new/
H A Dallocate.h75 …__type_identity_t<_Tp>* __ptr, __element_count __n, size_t __align = _LIBCPP_ALIGNOF(_Tp)) _NOEXCE…
80 return std::__libcpp_operator_delete(__ptr _LIBCPP_ONLY_IF_SIZED_DEALLOCATION(, __size));
84 …return std::__libcpp_operator_delete(__ptr _LIBCPP_ONLY_IF_SIZED_DEALLOCATION(, __size), __align_v…
86 return std::__libcpp_operator_delete(__ptr _LIBCPP_ONLY_IF_SIZED_DEALLOCATION(, __size));
95 __libcpp_deallocate_unsized(__type_identity_t<_Tp>* __ptr, size_t __align = _LIBCPP_ALIGNOF(_Tp)) _…
98 return std::__libcpp_operator_delete(__ptr);
102 return std::__libcpp_operator_delete(__ptr, __align_val);
104 return std::__libcpp_operator_delete(__ptr);
/freebsd/contrib/llvm-project/libcxx/include/__cxx03/__memory/
H A Dassume_aligned.h26 _LIBCPP_NODISCARD _LIBCPP_HIDE_FROM_ABI _Tp* __assume_aligned(_Tp* __ptr) { in __assume_aligned() argument
30 (void)__builtin_assume_aligned(__ptr, _Np); in __assume_aligned()
31 return __ptr; in __assume_aligned()
34 reinterpret_cast<uintptr_t>(__ptr) % _Np == 0, "Alignment assumption is violated"); in __assume_aligned()
35 return static_cast<_Tp*>(__builtin_assume_aligned(__ptr, _Np)); in __assume_aligned()
H A Daligned_alloc.h41 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_aligned_free(void* __ptr) { in __libcpp_aligned_free() argument
43 ::_aligned_free(__ptr); in __libcpp_aligned_free()
45 ::free(__ptr); in __libcpp_aligned_free()
/freebsd/contrib/llvm-project/clang/lib/Headers/ppc_wrappers/
H A Dmm_malloc.h29 void *__ptr; in _mm_malloc() local
33 if (posix_memalign(&__ptr, __alignment, __size) == 0) in _mm_malloc()
34 return __ptr; in _mm_malloc()
39 static __inline void _mm_free(void *__ptr) { free(__ptr); } in _mm_free() argument
/freebsd/contrib/llvm-project/libcxx/include/experimental/__simd/
H A Daligned_tag.h29 static _LIBCPP_HIDE_FROM_ABI constexpr _Up* __apply(_Up* __ptr) { in __apply()
30 return __ptr; in __apply()
42 static _LIBCPP_HIDE_FROM_ABI constexpr _Up* __apply(_Up* __ptr) { in __apply()
43 return std::__assume_aligned<__alignment<_Tp, _Up>, _Up>(__ptr); in __apply()
56 static _LIBCPP_HIDE_FROM_ABI constexpr _Up* __apply(_Up* __ptr) { in __apply()
57 return std::__assume_aligned<__alignment<_Tp, _Up>, _Up>(__ptr); in __apply()
/freebsd/contrib/llvm-project/libcxx/include/__algorithm/
H A Dpush_heap.h40 _RandomAccessIterator __ptr = __first + __len; in __sift_up() local
42 if (__comp(*__ptr, *--__last)) { in __sift_up()
45 *__last = _IterOps<_AlgPolicy>::__iter_move(__ptr); in __sift_up()
46 __last = __ptr; in __sift_up()
50 __ptr = __first + __len; in __sift_up()
51 } while (__comp(*__ptr, __t)); in __sift_up()
/freebsd/contrib/llvm-project/libcxx/include/__cxx03/__algorithm/
H A Dpush_heap.h40 _RandomAccessIterator __ptr = __first + __len; in __sift_up() local
42 if (__comp(*__ptr, *--__last)) { in __sift_up()
45 *__last = _IterOps<_AlgPolicy>::__iter_move(__ptr); in __sift_up()
46 __last = __ptr; in __sift_up()
50 __ptr = __first + __len; in __sift_up()
51 } while (__comp(*__ptr, __t)); in __sift_up()
/freebsd/contrib/llvm-project/libcxx/include/__memory_resource/
H A Dpolymorphic_allocator.h87 …_LIBCPP_HIDE_FROM_ABI void deallocate_bytes(void* __ptr, size_t __nbytes, size_t __alignment = ali…
88 __res_->deallocate(__ptr, __nbytes, __alignment);
99 _LIBCPP_HIDE_FROM_ABI void deallocate_object(_Type* __ptr, size_t __n = 1) {
100 deallocate_bytes(__ptr, __n * sizeof(_Type), alignof(_Type));
105 _Type* __ptr = allocate_object<_Type>(); in new_object() local
106 auto __guard = std::__make_exception_guard([&] { deallocate_object(__ptr); }); in new_object()
107 construct(__ptr, std::forward<_CtorArgs>(__ctor_args)...); in new_object()
109 return __ptr; in new_object()
113 _LIBCPP_HIDE_FROM_ABI void delete_object(_Type* __ptr) { in delete_object() argument
114 destroy(__ptr); in delete_object()
[all …]
/freebsd/contrib/ofed/libibverbs/
H A Dconfig.h5 void *__ptr; \
6 if (posix_memalign(&__ptr, (align), (size))) \
7 __ptr = NULL; \
8 __ptr; \
/freebsd/contrib/llvm-project/libcxx/include/
H A Dsyncstream173 _LIBCPP_HIDE_FROM_ABI void __inc_reference([[maybe_unused]] void* __ptr) {
174 _LIBCPP_ASSERT_INTERNAL(__ptr != nullptr, "non-wrapped streambufs are never written to");
176 ++__lut_[reinterpret_cast<uintptr_t>(__ptr)].__count;
179 // pre: __ptr is in __lut_
180 _LIBCPP_HIDE_FROM_ABI void __dec_reference([[maybe_unused]] void* __ptr) noexcept {
183 auto __it = __get_it(__ptr);
193 // _ __get_it(__ptr)->second.__mutex exclusive
195 // Instead store a pointer to __get_it(__ptr)->second.__mutex when
198 // pre: __ptr is in __lut_
199 …[[nodiscard]] _LIBCPP_HIDE_FROM_ABI lock_guard<mutex> __get_lock([[maybe_unused]] void* __ptr) noe…
[all …]

1234