#include <sycl/atomic_ref.hpp>

Inheritance diagram for sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >:

[legend]

Collaboration diagram for sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >:

[legend]

Public Types
using	value_type = T

using	difference_type = value_type

Public Types inherited from sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >
using	value_type = T

Public Member Functions
T	fetch_add (T operand, memory_order order=default_read_modify_write_order, memory_scope scope=default_scope) const noexcept

T	operator+= (T operand) const noexcept

T	operator++ (int) const noexcept

T	operator++ () const noexcept

T	fetch_sub (T operand, memory_order order=default_read_modify_write_order, memory_scope scope=default_scope) const noexcept

T	operator-= (T operand) const noexcept

T	operator-- (int) const noexcept

T	operator-- () const noexcept

T	fetch_and (T operand, memory_order order=default_read_modify_write_order, memory_scope scope=default_scope) const noexcept

T	operator&= (T operand) const noexcept

T	fetch_or (T operand, memory_order order=default_read_modify_write_order, memory_scope scope=default_scope) const noexcept

T	operator\|= (T operand) const noexcept

T	fetch_xor (T operand, memory_order order=default_read_modify_write_order, memory_scope scope=default_scope) const noexcept

T	operator^= (T operand) const noexcept

T	fetch_min (T operand, memory_order order=default_read_modify_write_order, memory_scope scope=default_scope) const noexcept

T	fetch_max (T operand, memory_order order=default_read_modify_write_order, memory_scope scope=default_scope) const noexcept

Public Member Functions inherited from sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >
bool	is_lock_free () const noexcept

	atomic_ref_base (T &ref)

	atomic_ref_base (const atomic_ref_base &ref) noexcept

atomic_ref_base &	operator= (const atomic_ref_base &)=delete

void	store (T operand, memory_order order=default_write_order, memory_scope scope=default_scope) const noexcept

T	operator= (T desired) const noexcept

T	load (memory_order order=default_read_order, memory_scope scope=default_scope) const noexcept

	operator T () const noexcept

T	exchange (T operand, memory_order order=default_read_modify_write_order, memory_scope scope=default_scope) const noexcept

bool	compare_exchange_strong (T &expected, T desired, memory_order success, memory_order failure, memory_scope scope=default_scope) const noexcept

bool	compare_exchange_strong (T &expected, T desired, memory_order order=default_read_modify_write_order, memory_scope scope=default_scope) const noexcept

bool	compare_exchange_weak (T &expected, T desired, memory_order success, memory_order failure, memory_scope scope=default_scope) const noexcept

bool	compare_exchange_weak (T &expected, T desired, memory_order order=default_read_modify_write_order, memory_scope scope=default_scope) const noexcept

Static Public Attributes
static constexpr size_t	required_alignment = sizeof(T)

static constexpr bool	is_always_lock_free

static constexpr memory_order	default_read_order

static constexpr memory_order	default_write_order

static constexpr memory_order	default_read_modify_write_order = DefaultOrder

static constexpr memory_scope	default_scope = DefaultScope

Static Public Attributes inherited from sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >
static constexpr size_t	required_alignment = sizeof(T)

static constexpr bool	is_always_lock_free

static constexpr memory_order	default_read_order

static constexpr memory_order	default_write_order

static constexpr memory_order	default_read_modify_write_order = DefaultOrder

static constexpr memory_scope	default_scope = DefaultScope

Additional Inherited Members
Protected Attributes inherited from sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >
std::atomic< T > *	ptr

Detailed Description

template<typename T, bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>
class sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >

Definition at line 275 of file atomic_ref.hpp.

Member Typedef Documentation

◆ difference_type

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

using sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::difference_type = value_type

Definition at line 282 of file atomic_ref.hpp.

◆ value_type

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

using sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::value_type = T

Definition at line 281 of file atomic_ref.hpp.

Member Function Documentation

◆ fetch_add()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::fetch_add	(	T	operand,
		memory_order	order = `default_read_modify_write_order`,
		memory_scope	scope = `default_scope`
	)		const

inlinenoexcept

Definition at line 300 of file atomic_ref.hpp.

References sycl::_V1::detail::getStdMemoryOrder(), and sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::ptr.

◆ fetch_and()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::fetch_and	(	T	operand,
		memory_order	order = `default_read_modify_write_order`,
		memory_scope	scope = `default_scope`
	)		const

inlinenoexcept

Definition at line 348 of file atomic_ref.hpp.

References sycl::_V1::detail::getStdMemoryOrder(), and sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::ptr.

◆ fetch_max()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::fetch_max	(	T	operand,
		memory_order	order = `default_read_modify_write_order`,
		memory_scope	scope = `default_scope`
	)		const

inlinenoexcept

Definition at line 402 of file atomic_ref.hpp.

References sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::compare_exchange_weak(), sycl::_V1::detail::getLoadOrder(), sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::load(), and sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::ptr.

◆ fetch_min()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::fetch_min	(	T	operand,
		memory_order	order = `default_read_modify_write_order`,
		memory_scope	scope = `default_scope`
	)		const

inlinenoexcept

Definition at line 388 of file atomic_ref.hpp.

References sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::compare_exchange_weak(), sycl::_V1::detail::getLoadOrder(), sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::load(), and sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::ptr.

◆ fetch_or()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::fetch_or	(	T	operand,
		memory_order	order = `default_read_modify_write_order`,
		memory_scope	scope = `default_scope`
	)		const

inlinenoexcept

Definition at line 362 of file atomic_ref.hpp.

References sycl::_V1::detail::getStdMemoryOrder(), and sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::ptr.

◆ fetch_sub()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::fetch_sub	(	T	operand,
		memory_order	order = `default_read_modify_write_order`,
		memory_scope	scope = `default_scope`
	)		const

inlinenoexcept

Definition at line 324 of file atomic_ref.hpp.

References sycl::_V1::detail::getStdMemoryOrder(), and sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::ptr.

◆ fetch_xor()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::fetch_xor	(	T	operand,
		memory_order	order = `default_read_modify_write_order`,
		memory_scope	scope = `default_scope`
	)		const

inlinenoexcept

Definition at line 374 of file atomic_ref.hpp.

References sycl::_V1::detail::getStdMemoryOrder(), and sycl::_V1::detail::atomic_ref_base< T, DefaultOrder, DefaultScope, AddressSpace >::ptr.

◆ operator&=()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::operator&= ( T operand ) const

inlinenoexcept

Definition at line 358 of file atomic_ref.hpp.

◆ operator++() [1/2]

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::operator++ ( ) const

inlinenoexcept

Definition at line 319 of file atomic_ref.hpp.

◆ operator++() [2/2]

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::operator++ ( int ) const

inlinenoexcept

Definition at line 314 of file atomic_ref.hpp.

◆ operator+=()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::operator+= ( T operand ) const

inlinenoexcept

Definition at line 310 of file atomic_ref.hpp.

◆ operator--() [1/2]

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::operator-- ( ) const

inlinenoexcept

Definition at line 343 of file atomic_ref.hpp.

◆ operator--() [2/2]

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::operator-- ( int ) const

inlinenoexcept

Definition at line 338 of file atomic_ref.hpp.

◆ operator-=()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::operator-= ( T operand ) const

inlinenoexcept

Definition at line 334 of file atomic_ref.hpp.

◆ operator^=()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::operator^= ( T operand ) const

inlinenoexcept

Definition at line 384 of file atomic_ref.hpp.

◆ operator|=()

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

T sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::operator|= ( T operand ) const

inlinenoexcept

Definition at line 372 of file atomic_ref.hpp.

Member Data Documentation

◆ default_read_modify_write_order

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

constexpr memory_order sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::default_read_modify_write_order = DefaultOrder

staticconstexpr

Definition at line 290 of file atomic_ref.hpp.

◆ default_read_order

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

constexpr memory_order sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::default_read_order

staticconstexpr

Initial value:

=

detail::memory_order_traits<DefaultOrder>::read_order

Definition at line 286 of file atomic_ref.hpp.

◆ default_scope

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

constexpr memory_scope sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::default_scope = DefaultScope

staticconstexpr

Definition at line 291 of file atomic_ref.hpp.

◆ default_write_order

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

constexpr memory_order sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::default_write_order

staticconstexpr

Initial value:

=

detail::memory_order_traits<DefaultOrder>::write_order

Definition at line 288 of file atomic_ref.hpp.

◆ is_always_lock_free

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

constexpr bool sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::is_always_lock_free

staticconstexpr

Initial value:

=

detail::IsValidAtomicRefType<T>::value

sycl::_V1::detail::IsValidAtomicRefType::value

static constexpr bool value

Definition: atomic_ref.hpp:34

Definition at line 284 of file atomic_ref.hpp.

◆ required_alignment

template<typename T , bool IsAspectAtomic64AttrUsed, memory_order DefaultOrder, memory_scope DefaultScope, access::address_space AddressSpace>

constexpr size_t sycl::_V1::detail::atomic_ref_impl< T, IsAspectAtomic64AttrUsed, DefaultOrder, DefaultScope, AddressSpace, typename std::enable_if_t< std::is_integral_v< T > > >::required_alignment = sizeof(T)

staticconstexpr

Definition at line 283 of file atomic_ref.hpp.

The documentation for this class was generated from the following file:

include/sycl/atomic_ref.hpp

Public Types

Public Member Functions

Static Public Attributes

Additional Inherited Members

Detailed Description

Member Typedef Documentation

◆ difference_type

◆ value_type

Member Function Documentation

◆ fetch_add()

◆ fetch_and()

◆ fetch_max()

◆ fetch_min()

◆ fetch_or()

◆ fetch_sub()

◆ fetch_xor()

◆ operator&=()

◆ operator++() [1/2]

◆ operator++() [2/2]

◆ operator+=()

◆ operator--() [1/2]

◆ operator--() [2/2]

◆ operator-=()

◆ operator^=()

◆ operator|=()

Member Data Documentation

◆ default_read_modify_write_order

◆ default_read_order

◆ default_scope

◆ default_write_order

◆ is_always_lock_free

◆ required_alignment