Home
last modified time | relevance | path

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

123

/freebsd-14.2/sys/sys/
H A Dsmr_types.h55 type __ptr; /* Do not access directly */ \
63 (__typeof((p)->__ptr))atomic_load_acq_ptr((uintptr_t *)&(p)->__ptr); \
73 (__typeof((p)->__ptr))atomic_load_ptr(&(p)->__ptr); \
86 __typeof((p)->__ptr) _v = (v); \
99 __typeof((p)->__ptr) _v = (v); \
102 (__typeof((p)->__ptr))atomic_swap_ptr( \
103 (uintptr_t *)&(p)->__ptr, (uintptr_t)_v); \
113 (__typeof((p)->__ptr))atomic_load_ptr(&(p)->__ptr); \
123 __typeof((p)->__ptr) _v = (v); \
124 atomic_store_ptr((uintptr_t *)&(p)->__ptr, (uintptr_t)_v); \
[all …]
H A Dsysctl.h424 bool *__ptr = (ptr); \
444 int8_t *__ptr = (ptr); \
464 uint8_t *__ptr = (ptr); \
484 int16_t *__ptr = (ptr); \
504 uint16_t *__ptr = (ptr); \
524 int32_t *__ptr = (ptr); \
544 uint32_t *__ptr = (ptr); \
564 int64_t *__ptr = (ptr); \
584 uint64_t *__ptr = (ptr); \
607 int *__ptr = (ptr); \
[all …]
/freebsd-14.2/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()
76 __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention…
77 __ulock_wait(UL_COMPARE_AND_WAIT, const_cast<__cxx_atomic_contention_t*>(__ptr), __val, 0);
82 …RE_AND_WAIT | (__notify_one ? 0 : ULF_WAKE_ALL), const_cast<__cxx_atomic_contention_t*>(__ptr), 0);
93 __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, __cxx_contention…
94 _umtx_op(const_cast<__cxx_atomic_contention_t*>(__ptr), UMTX_OP_WAIT, __val, NULL, NULL);
98 …_umtx_op(const_cast<__cxx_atomic_contention_t*>(__ptr), UMTX_OP_WAKE, __notify_one ? 1 : INT_MAX, …
[all …]
/freebsd-14.2/contrib/llvm-project/clang/lib/Headers/
H A D__clang_cuda_intrinsics.h489 return (size_t)(void __attribute__((address_space(1))) *)__ptr; in __nv_cvta_generic_to_global_impl()
513 return __nv_cvta_generic_to_shared_impl(__ptr); in __nvvm_get_smem_pointer()
576 return (void*)__ptr; in __nv_associate_access_property()
586 return __nvvm_isspacep_shared_cluster(__ptr); in __isClusterShared()
591 return __nvvm_mapa((void *)__ptr, __rank); in __cluster_map_shared_rank()
595 return __nvvm_getctarank((void *)__ptr); in __cluster_query_shared_rank()
599 __cluster_map_shared_multicast(const void *__ptr, in __cluster_map_shared_multicast() argument
601 return make_uint2((unsigned)__cvta_generic_to_shared(__ptr), in __cluster_map_shared_multicast()
659 : "l"(__ptr), "f"(__val.x), "f"(__val.y)); in atomicAdd()
667 : "l"(__ptr), "f"(__val.x), "f"(__val.y)); in atomicAdd_block()
[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 Dvecintrin.h316 __vec[7] = *__ptr; in vec_insert_and_zero()
323 __vec[7] = *__ptr; in vec_insert_and_zero()
330 __vec[3] = *__ptr; in vec_insert_and_zero()
337 __vec[3] = *__ptr; in vec_insert_and_zero()
344 __vec[1] = *__ptr; in vec_insert_and_zero()
351 __vec[1] = *__ptr; in vec_insert_and_zero()
358 __vec[0] = *__ptr; in vec_insert_and_zero()
365 __vec[0] = *__ptr; in vec_insert_and_zero()
373 __vec[1] = *__ptr; in vec_insert_and_zero()
381 __vec[0] = *__ptr; in vec_insert_and_zero()
[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-14.2/contrib/llvm-project/libcxx/include/__memory/
H A Dassume_aligned.h26 …P_NODISCARD _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.h52 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_aligned_free(void* __ptr) { in __libcpp_aligned_free() argument
54 ::_aligned_free(__ptr); in __libcpp_aligned_free()
56 ::free(__ptr); in __libcpp_aligned_free()
H A Duses_allocator_construction.h220 __uninitialized_construct_using_allocator(_Type* __ptr, const _Alloc& __alloc, _Args&&... __args) { in __uninitialized_construct_using_allocator() argument
222 …[&__ptr](auto&&... __xs) { return std::__construct_at(__ptr, std::forward<decltype(__xs)>(__xs)...… in __uninitialized_construct_using_allocator()
244 uninitialized_construct_using_allocator(_Type* __ptr, const _Alloc& __alloc, _Args&&... __args)
245 …-> decltype(std::__uninitialized_construct_using_allocator(__ptr, __alloc, std::forward<_Args>(__a…
246 …return /*--*/ std::__uninitialized_construct_using_allocator(__ptr, __alloc, std::forward<_Args>(_…
/freebsd-14.2/contrib/llvm-project/libcxx/include/__utility/
H A Dis_pointer_in_range.h36 const _Tp* __begin, const _Tp* __end, const _Up* __ptr) {
42 if (!__builtin_constant_p(__begin <= __ptr && __ptr < __end))
47 return !__less<>()(__ptr, __begin) && __less<>()(__ptr, __end);
52 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-14.2/contrib/llvm-project/libcxx/src/include/
H A Doverridable_function.h82 uintptr_t __ptr = reinterpret_cast<uintptr_t>(__fptr); in __is_function_overridden() local
85 return __ptr < __start || __ptr > __end; in __is_function_overridden()
106 uintptr_t __ptr = reinterpret_cast<uintptr_t>(__fptr);
108 return __ptr < __start || __ptr > __end;
/freebsd-14.2/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-14.2/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-14.2/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-14.2/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-14.2/contrib/llvm-project/libcxx/include/__format/
H A Dbuffer.h68 : __ptr_(__ptr), in __output_buffer()
74 __ptr_ = __ptr; in __reset()
289 _LIBCPP_HIDE_FROM_ABI void __flush(_CharT* __ptr, size_t __n) { in __flush() argument
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_t __n) { __writer_.__flush(__ptr, __n); }
418 _LIBCPP_HIDE_FROM_ABI void __flush(_CharT* __ptr, size_t __n) {
465 if (__size_ == 0 && __ptr != __storage_.__begin()) {
466 __writer_.__flush(__ptr, __n);
472 std::copy_n(__ptr, __s, __writer_.__out_it());
[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()
/freebsd-14.2/contrib/ofed/libibverbs/
H A Dconfig.h6 void *__ptr; \
7 if (posix_memalign(&__ptr, (align), (size))) \
8 __ptr = NULL; \
9 __ptr; \
/freebsd-14.2/contrib/llvm-project/libcxx/include/__algorithm/pstl_backends/cpu_backends/
H A Dlibdispatch.h126 auto __destroy = [=](__merge_range_t* __ptr) { in __parallel_merge()
127 std::destroy_n(__ptr, __n_ranges); in __parallel_merge()
128 std::allocator<__merge_range_t>().deallocate(__ptr, __n_ranges); in __parallel_merge()
211 auto __destroy = [__count = __partitions.__chunk_count_](_Value* __ptr) { in __parallel_transform_reduce()
212 std::destroy_n(__ptr, __count); in __parallel_transform_reduce()
213 std::allocator<_Value>().deallocate(__ptr, __count); in __parallel_transform_reduce()
262 auto __destroy = [__size](_Value* __ptr) { in __parallel_stable_sort()
263 std::destroy_n(__ptr, __size); in __parallel_stable_sort()
264 std::allocator<_Value>().deallocate(__ptr, __size); in __parallel_stable_sort()
/freebsd-14.2/contrib/llvm-project/libcxx/include/
H A Dsyncstream164 _LIBCPP_HIDE_FROM_ABI void __inc_reference([[maybe_unused]] void* __ptr) {
167 ++__lut_[reinterpret_cast<uintptr_t>(__ptr)].__count;
170 // pre: __ptr is in __lut_
171 _LIBCPP_HIDE_FROM_ABI void __dec_reference([[maybe_unused]] void* __ptr) noexcept {
174 auto __it = __get_it(__ptr);
184 // _ __get_it(__ptr)->second.__mutex exclusive
186 // Instead store a pointer to __get_it(__ptr)->second.__mutex when
189 // pre: __ptr is in __lut_
192 return lock_guard{__get_it(__ptr)->second.__mutex};
202 auto __it = __lut_.find(reinterpret_cast<uintptr_t>(__ptr));
[all …]
H A Dnew299 _LIBCPP_HIDE_FROM_ABI void __do_deallocate_handle_size(void* __ptr, size_t __size, _Args... __args)…
302 return std::__libcpp_operator_delete(__ptr, __args...);
304 return std::__libcpp_operator_delete(__ptr, __size, __args...);
308 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_deallocate(void* __ptr, size_t __size, size_t __align) {
311 return __do_deallocate_handle_size(__ptr, __size);
315 return __do_deallocate_handle_size(__ptr, __size, __align_val);
317 return __do_deallocate_handle_size(__ptr, __size);
322 inline _LIBCPP_HIDE_FROM_ABI void __libcpp_deallocate_unsized(void* __ptr, size_t __align) {
325 return __libcpp_operator_delete(__ptr);
329 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-14.2/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-14.2/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;

123