Home
last modified time | relevance | path

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

12

/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.h422 bool *__ptr = (ptr); \
426 __ptr, val, sysctl_handle_bool, "CU", __DESCR(descr), \
442 int8_t *__ptr = (ptr); \
447 __ptr, val, sysctl_handle_8, "C", __DESCR(descr), NULL); \
462 uint8_t *__ptr = (ptr); \
467 __ptr, val, sysctl_handle_8, "CU", __DESCR(descr), NULL); \
482 int16_t *__ptr = (ptr); \
487 __ptr, val, sysctl_handle_16, "S", __DESCR(descr), NULL); \
502 uint16_t *__ptr = (ptr); \
507 __ptr, val, sysctl_handle_16, "SU", __DESCR(descr), NULL); \
[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, NULL, NULL);
[all …]
/freebsd/contrib/llvm-project/clang/lib/Headers/
H A D__clang_cuda_intrinsics.h486 __device__ inline size_t __nv_cvta_generic_to_global_impl(const void *__ptr) { in __nv_cvta_generic_to_global_impl() argument
487 return (size_t)(void __attribute__((address_space(1))) *)__ptr; in __nv_cvta_generic_to_global_impl()
489 __device__ inline size_t __nv_cvta_generic_to_shared_impl(const void *__ptr) { in __nv_cvta_generic_to_shared_impl() argument
490 return (size_t)(void __attribute__((address_space(3))) *)__ptr; in __nv_cvta_generic_to_shared_impl()
492 __device__ inline size_t __nv_cvta_generic_to_constant_impl(const void *__ptr) { in __nv_cvta_generic_to_constant_impl() argument
493 return (size_t)(void __attribute__((address_space(4))) *)__ptr; in __nv_cvta_generic_to_constant_impl()
495 __device__ inline size_t __nv_cvta_generic_to_local_impl(const void *__ptr) { in __nv_cvta_generic_to_local_impl() argument
496 return (size_t)(void __attribute__((address_space(5))) *)__ptr; in __nv_cvta_generic_to_local_impl()
498 __device__ inline void *__nv_cvta_global_to_generic_impl(size_t __ptr) { in __nv_cvta_global_to_generic_impl() argument
499 return (void *)(void __attribute__((address_space(1))) *)__ptr; in __nv_cvta_global_to_generic_impl()
[all …]
H A Dvecintrin.h30 __lcbb(const void *__ptr, unsigned short __len)
314 vec_insert_and_zero(const signed char *__ptr) { in vec_insert_and_zero() argument
316 __vec[7] = *__ptr; in vec_insert_and_zero()
321 vec_insert_and_zero(const unsigned char *__ptr) { in vec_insert_and_zero() argument
323 __vec[7] = *__ptr; in vec_insert_and_zero()
328 vec_insert_and_zero(const signed short *__ptr) { in vec_insert_and_zero() argument
330 __vec[3] = *__ptr; in vec_insert_and_zero()
335 vec_insert_and_zero(const unsigned short *__ptr) { in vec_insert_and_zero() argument
337 __vec[3] = *__ptr; in vec_insert_and_zero()
342 vec_insert_and_zero(const signed int *__ptr) { in vec_insert_and_zero() argument
[all …]
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, \
662 __device__ static void __tex_fetch(__T *__ptr, cudaTextureObject_t __handle,
665 *__ptr = __convert<__T, __FetchT>::__run(
684 __device__ static void __tex_fetch(__T *__ptr, __HandleT __handle,
687 *__ptr = __convert<__T, __FetchT>::__run(
696 __tex_fetch(__DataT *, __RetT *__ptr,
700 *__ptr = __convert<__RetT, float4>::__run(
709 __tex_fetch(__DataT *, __RetT *__ptr,
713 *__ptr = __convert<__RetT, __FetchT>::__run(
/freebsd/contrib/llvm-project/libcxx/src/include/
H A Doverridable_function.h84 uintptr_t __ptr = reinterpret_cast<uintptr_t>(__fptr); 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()
116 uintptr_t __ptr = reinterpret_cast<uintptr_t>(__fptr);
118 return __ptr < __start || __ptr > __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/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/__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.h85 …_LIBCPP_HIDE_FROM_ABI void deallocate_bytes(void* __ptr, size_t __nbytes, size_t __alignment = ali…
86 __res_->deallocate(__ptr, __nbytes, __alignment);
97 _LIBCPP_HIDE_FROM_ABI void deallocate_object(_Type* __ptr, size_t __n = 1) {
98 deallocate_bytes(__ptr, __n * sizeof(_Type), alignof(_Type));
103 _Type* __ptr = allocate_object<_Type>(); in new_object() local
104 auto __guard = std::__make_exception_guard([&] { deallocate_object(__ptr); }); in new_object()
105 construct(__ptr, std::forward<_CtorArgs>(__ctor_args)...); in new_object()
107 return __ptr; in new_object()
111 _LIBCPP_HIDE_FROM_ABI void delete_object(_Type* __ptr) { in delete_object() argument
112 destroy(__ptr); in delete_object()
[all …]
/freebsd/contrib/llvm-project/libcxx/include/__format/
H A Dbuffer.h67 _LIBCPP_HIDE_FROM_ABI explicit __output_buffer(_CharT* __ptr, size_t __capacity, _Tp* __obj) in __output_buffer() argument
68 : __ptr_(__ptr), in __output_buffer()
73 _LIBCPP_HIDE_FROM_ABI void __reset(_CharT* __ptr, size_t __capacity) { in __reset() argument
74 __ptr_ = __ptr; in __reset()
289 _LIBCPP_HIDE_FROM_ABI void __flush(_CharT* __ptr, size_t __n) { in __flush() argument
290 __out_it_ = std::ranges::copy_n(__ptr, __n, std::move(__out_it_)).out; in __flush()
333 _LIBCPP_HIDE_FROM_ABI void __flush(_CharT* __ptr, size_t __n) {
334 __container_->insert(__container_->end(), __ptr, __ptr + __n);
373 _LIBCPP_HIDE_FROM_ABI void __flush(_CharT* __ptr, size_
[all...]
H A Dformatter_integral.h97 auto __ptr = __grouping.begin(); in __determine_grouping() local
100 __size -= *__ptr; in __determine_grouping()
102 __r.push_back(*__ptr); in __determine_grouping()
105 __r.push_back(*__ptr + __size); in __determine_grouping()
110 if (__ptr != __end) { in __determine_grouping()
112 ++__ptr; in __determine_grouping()
114 } while (*__ptr == 0 && __ptr != __end); in __determine_grouping()
H A Dformatter_pointer.h42 …_LIBCPP_HIDE_FROM_ABI typename _FormatContext::iterator format(const void* __ptr, _FormatContext& … in format()
50 return __formatter::__format_integer(reinterpret_cast<uintptr_t>(__ptr), __ctx, __specs); in format()
/freebsd/contrib/llvm-project/libcxx/include/__memory/
H A Dassume_aligned.h26 _LIBCPP_NODISCARD _LIBCPP_HIDE_FROM_ABI _LIBCPP_CONSTEXPR_SINCE_CXX14 _Tp* __assume_aligned(_Tp* __ptr) {
30 (void)__builtin_assume_aligned(__ptr, _Np); in assume_aligned() argument
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) {
43 return std::__assume_aligned<_Np>(__ptr);
H A Daligned_alloc.h52 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_aligned_free(void* __ptr) {
54 ::_aligned_free(__ptr); in __libcpp_aligned_free() argument
56 ::free(__ptr); in __libcpp_aligned_free()
H A Duses_allocator_construction.h212 __uninitialized_construct_using_allocator(_Type* __ptr, const _Alloc& __alloc, _Args&&... __args) { in __uninitialized_construct_using_allocator() argument
214 …[&__ptr](auto&&... __xs) { return std::__construct_at(__ptr, std::forward<decltype(__xs)>(__xs)...… in __uninitialized_construct_using_allocator()
236 uninitialized_construct_using_allocator(_Type* __ptr, const _Alloc& __alloc, _Args&&... __args)
237 …-> decltype(std::__uninitialized_construct_using_allocator(__ptr, __alloc, std::forward<_Args>(__a…
238 …return /*--*/ std::__uninitialized_construct_using_allocator(__ptr, __alloc, std::forward<_Args>(_…
/freebsd/contrib/ofed/libibverbs/
H A Dconfig.h6 void *__ptr; \
7 if (posix_memalign(&__ptr, (align), (size))) \
8 __ptr = NULL; \
9 __ptr; \
/freebsd/contrib/llvm-project/libcxx/include/
H A Dsyncstream166 _LIBCPP_HIDE_FROM_ABI void __inc_reference([[maybe_unused]] void* __ptr) {
167 _LIBCPP_ASSERT_INTERNAL(__ptr != nullptr, "non-wrapped streambufs are never written to");
169 ++__lut_[reinterpret_cast<uintptr_t>(__ptr)].__count;
172 // pre: __ptr is in __lut_
173 _LIBCPP_HIDE_FROM_ABI void __dec_reference([[maybe_unused]] void* __ptr) noexcept {
176 auto __it = __get_it(__ptr);
186 // _ __get_it(__ptr)->second.__mutex exclusive
188 // Instead store a pointer to __get_it(__ptr)->second.__mutex when
191 // pre: __ptr is in __lut_
192 …[[nodiscard]] _LIBCPP_HIDE_FROM_ABI lock_guard<mutex> __get_lock([[maybe_unused]] void* __ptr) noe…
[all …]
H A Dnew293 _LIBCPP_HIDE_FROM_ABI void __do_deallocate_handle_size(void* __ptr, size_t __size, _Args... __args)…
296 return std::__libcpp_operator_delete(__ptr, __args...);
298 return std::__libcpp_operator_delete(__ptr, __size, __args...);
302 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_deallocate(void* __ptr, size_t __size, size_t __align) {
305 return __do_deallocate_handle_size(__ptr, __size);
309 return __do_deallocate_handle_size(__ptr, __size, __align_val);
311 return __do_deallocate_handle_size(__ptr, __size);
316 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_deallocate_unsized(void* __ptr, size_t __align) {
319 return __libcpp_operator_delete(__ptr);
323 return __libcpp_operator_delete(__ptr, __align_val);
[all …]
H A Dsource_location58 // The defaulted __ptr argument is necessary so that the builtin is evaluated
60 static consteval source_location current(__bsl_ty __ptr = __builtin_source_location()) noexcept {
62 __sl.__ptr_ = static_cast<const __impl*>(__ptr);
/freebsd/contrib/llvm-project/libcxx/include/__pstl/backends/
H A Dlibdispatch.h136 auto __destroy = [=](__merge_range_t* __ptr) {
137 std::destroy_n(__ptr, __n_ranges);
138 std::allocator<__merge_range_t>().deallocate(__ptr, __n_ranges);
221 auto __destroy = [__count = __partitions.__chunk_count_](_Value* __ptr) {
222 std::destroy_n(__ptr, __count);
223 std::allocator<_Value>().deallocate(__ptr, __count);
271 auto __destroy = [__size](_Value* __ptr) {
272 std::destroy_n(__ptr, __size);
273 std::allocator<_Value>().deallocate(__ptr, __size);
/freebsd/contrib/llvm-project/libcxx/include/__atomic/
H A Datomic_ref.h62 _Tp* __ptr = std::addressof(__val); in __clear_padding() local
64 __builtin_clear_padding(__ptr); in __clear_padding()
66 return __ptr; in __clear_padding()
70 …_Tp* __ptr, _Tp* __expected, _Tp* __desired, bool __is_weak, int __success, int __failure) noexcep… in __compare_exchange()
78 … return __atomic_compare_exchange(__ptr, __expected, __desired, __is_weak, __success, __failure); in __compare_exchange()
90 …if (__atomic_compare_exchange(__ptr, std::addressof(__copy), __desired, __is_weak, __success, __fa… in __compare_exchange()
349 _LIBCPP_HIDE_FROM_ABI explicit atomic_ref(_Tp*& __ptr) : __base(__ptr) {}
/freebsd/contrib/llvm-project/libcxx/src/support/runtime/
H A Dexception_pointer_msvc.ipp51 exception_ptr __copy_exception_ptr(void* __except, const void* __ptr) {
53 if (__ptr)
54 __ExceptionPtrCopyException(&__ret, __except, __ptr);
/freebsd/contrib/llvm-project/clang/lib/Headers/cuda_wrappers/
H A Dnew94 __device__ inline void *operator new(__SIZE_TYPE__, void *__ptr) CUDA_NOEXCEPT {
95 return __ptr;
97 __device__ inline void *operator new[](__SIZE_TYPE__, void *__ptr) CUDA_NOEXCEPT {
98 return __ptr;

12