Home
last modified time | relevance | path

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

123

/openbsd-src/gnu/llvm/libcxx/src/
H A Datomic.cpp44 static void __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr, in __libcpp_platform_wait_on_address() argument
48 syscall(SYS_futex, __ptr, FUTEX_WAIT_PRIVATE, __val, &__timeout, 0, 0); in __libcpp_platform_wait_on_address()
51 static void __libcpp_platform_wake_by_address(__cxx_atomic_contention_t const volatile* __ptr, in __libcpp_platform_wake_by_address() argument
54 syscall(SYS_futex, __ptr, FUTEX_WAKE_PRIVATE, __notify_one ? 1 : INT_MAX, 0, 0, 0); in __libcpp_platform_wake_by_address()
66 static void __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr,
70 const_cast<__cxx_atomic_contention_t*>(__ptr), __val, 0);
73 static void __libcpp_platform_wake_by_address(__cxx_atomic_contention_t const volatile* __ptr,
77 const_cast<__cxx_atomic_contention_t*>(__ptr), 0);
82 static void __libcpp_platform_wait_on_address(__cxx_atomic_contention_t const volatile* __ptr,
85 _umtx_op(const_cast<__cxx_atomic_contention_t*>(__ptr),
[all …]
/openbsd-src/gnu/llvm/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
/openbsd-src/gnu/llvm/clang/lib/Headers/
H A D__clang_hip_runtime_wrapper.h86 __attribute__((weak)) inline __device__ void free(void *__ptr) { in free() argument
87 __ockl_dm_dealloc((unsigned long long)__ptr); in free()
92 __device__ void *__hip_free(void *__ptr);
96 __attribute__((weak)) inline __device__ void free(void *__ptr) {
97 __hip_free(__ptr);
104 __attribute__((weak)) inline __device__ void free(void *__ptr) {
H A D__clang_cuda_intrinsics.h488 __device__ inline size_t __nv_cvta_generic_to_global_impl(const void *__ptr) { in __nv_cvta_generic_to_global_impl() argument
489 return (size_t)(void __attribute__((address_space(1))) *)__ptr; in __nv_cvta_generic_to_global_impl()
491 __device__ inline size_t __nv_cvta_generic_to_shared_impl(const void *__ptr) { in __nv_cvta_generic_to_shared_impl() argument
492 return (size_t)(void __attribute__((address_space(3))) *)__ptr; in __nv_cvta_generic_to_shared_impl()
494 __device__ inline size_t __nv_cvta_generic_to_constant_impl(const void *__ptr) { in __nv_cvta_generic_to_constant_impl() argument
495 return (size_t)(void __attribute__((address_space(4))) *)__ptr; in __nv_cvta_generic_to_constant_impl()
497 __device__ inline size_t __nv_cvta_generic_to_local_impl(const void *__ptr) { in __nv_cvta_generic_to_local_impl() argument
498 return (size_t)(void __attribute__((address_space(5))) *)__ptr; in __nv_cvta_generic_to_local_impl()
500 __device__ inline void *__nv_cvta_global_to_generic_impl(size_t __ptr) { in __nv_cvta_global_to_generic_impl() argument
501 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(
H A Darm_acle.h728 #define __arm_mte_create_random_tag(__ptr, __mask) __builtin_arm_irg(__ptr, __mask) argument
729 #define __arm_mte_increment_tag(__ptr, __tag_offset) __builtin_arm_addg(__ptr, __tag_offset) argument
730 #define __arm_mte_exclude_tag(__ptr, __excluded) __builtin_arm_gmi(__ptr, __excluded) argument
731 #define __arm_mte_get_tag(__ptr) __builtin_arm_ldg(__ptr) argument
732 #define __arm_mte_set_tag(__ptr) __builtin_arm_stg(__ptr) argument
/openbsd-src/gnu/llvm/libcxx/include/__algorithm/
H A Dpush_heap.h34 _RandomAccessIterator __ptr = __first + __len; in __sift_up() local
36 if (__comp(*__ptr, *--__last)) { in __sift_up()
39 *__last = _IterOps<_AlgPolicy>::__iter_move(__ptr); in __sift_up()
40 __last = __ptr; in __sift_up()
44 __ptr = __first + __len; in __sift_up()
45 } while (__comp(*__ptr, __t)); in __sift_up()
/openbsd-src/gnu/llvm/libcxx/include/__format/
H A Dbuffer.h60 _LIBCPP_HIDE_FROM_ABI explicit __output_buffer(_CharT* __ptr, size_t __capacity, _Tp* __obj) in __output_buffer() argument
61 : __ptr_(__ptr), in __output_buffer()
66 _LIBCPP_HIDE_FROM_ABI void __reset(_CharT* __ptr, size_t __capacity) { in __reset() argument
67 __ptr_ = __ptr; in __reset()
282 _LIBCPP_HIDE_FROM_ABI void __flush(_CharT* __ptr, size_t __n) { in __flush() argument
283 __out_it_ = std::ranges::copy_n(__ptr, __n, std::move(__out_it_)).out; in __flush()
325 _LIBCPP_HIDE_FROM_ABI void __flush(_CharT* __ptr, size_t __n) {
326 __container_->insert(__container_->end(), __ptr, __ptr + __n);
364 _LIBCPP_HIDE_FROM_ABI void __flush(_CharT* __ptr, size_t __n) { __writer_.__flush(__ptr, __n); }
409 _LIBCPP_HIDE_FROM_ABI void __flush(_CharT* __ptr, size_t __n) {
[all …]
H A Dformatter_integral.h88 auto __ptr = __grouping.begin(); in __determine_grouping() local
91 __size -= *__ptr; in __determine_grouping()
93 __r.push_back(*__ptr); in __determine_grouping()
96 __r.push_back(*__ptr + __size); in __determine_grouping()
101 if (__ptr != __end) { in __determine_grouping()
103 ++__ptr; in __determine_grouping()
105 } while (*__ptr == 0 && __ptr != __end); in __determine_grouping()
H A Dformatter_pointer.h44 _LIBCPP_HIDE_FROM_ABI auto format(const void* __ptr, auto& __ctx) const -> decltype(__ctx.out()) {
48 return __formatter::__format_integer(reinterpret_cast<uintptr_t>(__ptr), __ctx, __specs);
H A Dparser_std_format_spec.h60 if (__r.__ptr == __end || *__r.__ptr != _CharT('}')) in __parse_arg_id()
63 ++__r.__ptr; in __parse_arg_id()
463 __begin = __r.__ptr; in __parse_width()
474 __begin = __r.__ptr; in __parse_width()
491 __begin = __arg_id.__ptr; in __parse_precision()
501 __begin = __r.__ptr; in __parse_precision()
H A Dformat_arg.h69 __ptr, enumerator
136 case __format::__arg_t::__ptr: in decltype()
160 …__format_([](basic_format_parse_context<_CharT>& __parse_ctx, _Context& __ctx, const void* __ptr) { in __handle()
171 __ctx.advance_to(__f.format(*const_cast<_Qp*>(static_cast<const _Dp*>(__ptr)), __ctx)); in __handle()
/openbsd-src/gnu/llvm/libcxx/include/__memory/
H A Dassume_aligned.h30 constexpr _Tp* assume_aligned(_Tp* __ptr) { in assume_aligned() argument
35 return __ptr; in assume_aligned()
37 … _LIBCPP_ASSERT(reinterpret_cast<uintptr_t>(__ptr) % _Np == 0, "Alignment assumption is violated"); in assume_aligned()
38 return static_cast<_Tp*>(__builtin_assume_aligned(__ptr, _Np)); in assume_aligned()
H A Duses_allocator_construction.h188 __uninitialized_construct_using_allocator(_Type* __ptr, const _Alloc& __alloc, _Args&&... __args) { in __uninitialized_construct_using_allocator() argument
190 …[&__ptr](auto&&... __xs) { return std::__construct_at(__ptr, std::forward<decltype(__xs)>(__xs)...… in __uninitialized_construct_using_allocator()
212 uninitialized_construct_using_allocator(_Type* __ptr, const _Alloc& __alloc, _Args&&... __args)
213 …-> decltype(std::__uninitialized_construct_using_allocator(__ptr, __alloc, std::forward<_Args>(__a…
214 …return /*--*/ std::__uninitialized_construct_using_allocator(__ptr, __alloc, std::forward<_Args>(_…
H A Dalign.h21 _LIBCPP_FUNC_VIS void* align(size_t __align, size_t __sz, void*& __ptr, size_t& __space);
/openbsd-src/gnu/llvm/libcxx/include/__memory_resource/
H A Dpolymorphic_allocator.h82 void deallocate_bytes(void* __ptr, size_t __nbytes, size_t __alignment = alignof(max_align_t)) {
83 __res_->deallocate(__ptr, __nbytes, __alignment);
94 void deallocate_object(_Type* __ptr, size_t __n = 1) {
95 deallocate_bytes(__ptr, __n * sizeof(_Type), alignof(_Type));
100 _Type* __ptr = allocate_object<_Type>(); in new_object() local
101 auto __guard = std::__make_exception_guard([&] { deallocate_object(__ptr); }); in new_object()
102 construct(__ptr, std::forward<_CtorArgs>(__ctor_args)...); in new_object()
104 return __ptr; in new_object()
108 void delete_object(_Type* __ptr) { in delete_object() argument
109 destroy(__ptr); in delete_object()
[all …]
/openbsd-src/gnu/gcc/libstdc++-v3/include/tr1/
H A Dfunctional_iterate.h195 _M_call(_Tp& __ptr, const volatile void * _GLIBCXX_COMMA_SHIFTED
197 { return ((*__ptr).*__pmf)(_GLIBCXX_ARGS_SHIFTED); }
249 _M_call(_Tp& __ptr, const volatile void * _GLIBCXX_COMMA_SHIFTED
251 { return ((*__ptr).*__pmf)(_GLIBCXX_ARGS_SHIFTED); }
303 _M_call(_Tp& __ptr, const volatile void * _GLIBCXX_COMMA_SHIFTED
305 { return ((*__ptr).*__pmf)(_GLIBCXX_ARGS_SHIFTED); }
357 _M_call(_Tp& __ptr, const volatile void * _GLIBCXX_COMMA_SHIFTED
359 { return ((*__ptr).*__pmf)(_GLIBCXX_ARGS_SHIFTED); }
891 _Any_data __ptr;
892 if (_M_manager(__ptr, _M_functor, __get_functor_ptr)
[all …]
/openbsd-src/gnu/llvm/libcxx/include/
H A Dnew297 void __do_deallocate_handle_size(void *__ptr, size_t __size, _Args ...__args) {
300 return std::__libcpp_operator_delete(__ptr, __args...);
302 return std::__libcpp_operator_delete(__ptr, __size, __args...);
307 void __libcpp_deallocate(void* __ptr, size_t __size, size_t __align) {
310 return __do_deallocate_handle_size(__ptr, __size);
314 return __do_deallocate_handle_size(__ptr, __size, __align_val);
316 return __do_deallocate_handle_size(__ptr, __size);
321 inline _LIBCPP_INLINE_VISIBILITY void __libcpp_deallocate_unsized(void* __ptr, size_t __align) {
324 return __libcpp_operator_delete(__ptr);
328 return __libcpp_operator_delete(__ptr, __align_val);
[all …]
H A Dsource_location59 // The defaulted __ptr argument is necessary so that the builtin is evaluated
61 static consteval source_location current(__bsl_ty __ptr = __builtin_source_location()) noexcept {
63 __sl.__ptr_ = static_cast<const __impl*>(__ptr);
H A Dany314 constexpr _Storage() : __ptr(nullptr) {}
315 void * __ptr;
474 __dest.__s_.__ptr = __hold.release();
486 _Tp * __p = static_cast<_Tp *>(__this.__s_.__ptr);
494 _LargeHandler::__create(__dest, *static_cast<_Tp const *>(__this.__s_.__ptr));
499 __dest.__s_.__ptr = __this.__s_.__ptr;
509 return static_cast<void*>(__this.__s_.__ptr);
/openbsd-src/gnu/gcc/libstdc++-v3/include/ext/
H A Dvstring_util.h92 _Alloc_hider(const _Alloc1& __a, _CharT* __ptr) in _Alloc_hider()
93 : _Alloc1(__a), _M_p(__ptr) { } in _Alloc_hider()
101 _S_is_null_pointer(_Type* __ptr) in _S_is_null_pointer()
102 { return __ptr == 0; } in _S_is_null_pointer()
/openbsd-src/gnu/gcc/libstdc++-v3/include/debug/
H A Dfunctions.h62 __check_singular(const _Tp* __ptr) in __check_singular() argument
63 { return __ptr == 0; } in __check_singular()
81 __check_dereferenceable(const _Tp* __ptr) in __check_dereferenceable() argument
82 { return __ptr; } in __check_dereferenceable()
/openbsd-src/gnu/llvm/libcxx/src/support/runtime/
H A Dexception_pointer_msvc.ipp59 exception_ptr __copy_exception_ptr(void* __except, const void* __ptr) {
61 if (__ptr)
62 __ExceptionPtrCopyException(&__ret, __except, __ptr);
/openbsd-src/gnu/llvm/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