DPC++ Runtime
Runtime libraries for oneAPI DPC++
Classes | Typedefs | Functions
sycl::_V1::ext::oneapi::detail Namespace Reference

Classes

struct  IsValidAtomicRefType
 
struct  memory_order_traits
 
struct  memory_order_traits< memory_order::relaxed >
 
struct  memory_order_traits< memory_order::acq_rel >
 
struct  memory_order_traits< memory_order::seq_cst >
 
struct  bit_equal
 
struct  bit_equal< T, typename detail::enable_if_t< std::is_integral< T >::value > >
 
struct  bit_equal< float >
 
struct  bit_equal< double >
 
class  atomic_ref_base
 
class  atomic_ref_impl
 
class  atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_integral< T >::value > >
 
class  atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_floating_point< T >::value > >
 
class  atomic_ref_impl< T *, DefaultOrder, DefaultScope, AddressSpace >
 
struct  is_bf16_storage_type
 
struct  is_bf16_storage_type< uint16_t >
 
struct  is_bf16_storage_type< uint32_t >
 
struct  is_bf16_storage_type< vec< uint16_t, N > >
 
struct  is_bf16_storage_type< vec< uint32_t, N > >
 
struct  joint_matrix_load_impl
 
struct  joint_matrix_load_impl< S, T, Use, NumRows, NumCols, Layout, Space, IsDecorated, typename std::enable_if_t< Layout==sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major||Layout==sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major > >
 
struct  joint_matrix_store_impl
 
struct  joint_matrix_store_impl< T, NumRows, NumCols, Layout, Space, IsDecorated, typename std::enable_if_t< Layout==sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major||Layout==sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major > >
 
struct  joint_matrix_mad_impl
 
struct  joint_matrix_mad_impl< T1, T2, M, K, N, LayoutA, LayoutB, LayoutC, typename std::enable_if_t<(LayoutA==sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major||LayoutA==sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major) &&(LayoutB==sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major||LayoutB==sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major) &&(LayoutC==sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major||LayoutC==sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major)> >
 
struct  joint_matrix_cuda
 
struct  owner_less_base
 
class  weak_object_base
 
class  filter_selector_impl
 

Typedefs

using memory_order = sycl::ext::oneapi::memory_order
 
using memory_scope = sycl::ext::oneapi::memory_scope
 
template<sycl::access::address_space AS>
using IsValidAtomicAddressSpace = bool_constant< AS==access::address_space::global_space||AS==access::address_space::local_space||AS==access::address_space::ext_intel_global_device_space >
 
template<memory_order Order>
using IsValidDefaultOrder = bool_constant< Order==memory_order::relaxed||Order==memory_order::acq_rel||Order==memory_order::seq_cst >
 
using Bfloat16StorageT = uint16_t
 
typedef struct sycl::detail::device_filter filter
 

Functions

 __SYCL2020_DEPRECATED ("use 'sycl::detail::getStdMemoryOrder(sycl::memory_order)' instead") static inline const expr std
 
constexpr memory_order getLoadOrder (memory_order order)
 
Bfloat16StorageT bfloat16ToBits (const bfloat16 &Value)
 
bfloat16 bitsToBfloat16 (const Bfloat16StorageT Value)
 
template<sycl::ext::oneapi::experimental::matrix::matrix_layout Layout>
constexpr int get_layout_id ()
 
template<>
constexpr int get_layout_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major > ()
 
template<>
constexpr int get_layout_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major > ()
 
template<sycl::ext::oneapi::experimental::matrix::matrix_layout LayoutA, sycl::ext::oneapi::experimental::matrix::matrix_layout LayoutB>
constexpr int get_layout_pair_id ()
 
template<>
constexpr int get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major > ()
 
template<>
constexpr int get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major > ()
 
template<>
constexpr int get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major > ()
 
template<>
constexpr int get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major > ()
 
template<int Dims>
static range< Dims > createDummyRange ()
 
template<typename SYCLObjT >
decltype(weak_object_base< SYCLObjT >::MObjWeakPtr) getSyclWeakObjImpl (const weak_object_base< SYCLObjT > &WeakObj)
 
std::vector< std::string > tokenize (const std::string &Filter, const std::string &Delim)
 
filter create_filter (const std::string &Input)
 

Typedef Documentation

◆ Bfloat16StorageT

using sycl::_V1::ext::oneapi::detail::Bfloat16StorageT = typedef uint16_t

Definition at line 30 of file bfloat16.hpp.

◆ filter

typedef struct sycl::detail::device_filter sycl::_V1::ext::oneapi::detail::filter

Definition at line 1 of file filter_selector_impl.hpp.

◆ IsValidAtomicAddressSpace

template<sycl::access::address_space AS>
using sycl::_V1::ext::oneapi::detail::IsValidAtomicAddressSpace = typedef bool_constant<AS == access::address_space::global_space || AS == access::address_space::local_space || AS == access::address_space::ext_intel_global_device_space>

Definition at line 46 of file atomic_ref.hpp.

◆ IsValidDefaultOrder

template<memory_order Order>
using sycl::_V1::ext::oneapi::detail::IsValidDefaultOrder = typedef bool_constant<Order == memory_order::relaxed || Order == memory_order::acq_rel || Order == memory_order::seq_cst>

Definition at line 53 of file atomic_ref.hpp.

◆ memory_order

using sycl::_V1::ext::oneapi::detail::memory_order = typedef sycl::ext::oneapi::memory_order

Definition at line 32 of file atomic_ref.hpp.

◆ memory_scope

using sycl::_V1::ext::oneapi::detail::memory_scope = typedef sycl::ext::oneapi::memory_scope

Definition at line 33 of file atomic_ref.hpp.

Function Documentation

◆ __SYCL2020_DEPRECATED()

sycl::_V1::ext::oneapi::detail::__SYCL2020_DEPRECATED ( "use 'sycl::detail::getStdMemoryOrder(sycl::memory_order)' instead"  ) const

Definition at line 55 of file atomic_enums.hpp.

References __SYCL2020_DEPRECATED, sycl::_V1::memory_order_acq_rel, sycl::_V1::memory_order_acquire, sycl::_V1::memory_order_relaxed, sycl::_V1::memory_order_release, and sycl::_V1::memory_order_seq_cst.

◆ bfloat16ToBits()

Bfloat16StorageT sycl::_V1::ext::oneapi::detail::bfloat16ToBits ( const bfloat16 &  Value)
inline

Definition at line 214 of file bfloat16.hpp.

Referenced by sycl::_V1::ext::oneapi::experimental::fabs(), sycl::_V1::ext::oneapi::experimental::fma(), sycl::_V1::ext::oneapi::experimental::fmax(), sycl::_V1::ext::oneapi::experimental::fmin(), and sycl::_V1::ext::oneapi::experimental::isnan().

◆ bitsToBfloat16()

bfloat16 sycl::_V1::ext::oneapi::detail::bitsToBfloat16 ( const Bfloat16StorageT  Value)
inline

Definition at line 220 of file bfloat16.hpp.

Referenced by sycl::_V1::ext::oneapi::experimental::fabs(), sycl::_V1::ext::oneapi::experimental::fma(), sycl::_V1::ext::oneapi::experimental::fmax(), and sycl::_V1::ext::oneapi::experimental::fmin().

◆ create_filter()

filter sycl::_V1::ext::oneapi::detail::create_filter ( const std::string &  Input)

Definition at line 49 of file filter_selector_impl.cpp.

References tokenize().

Referenced by sycl::_V1::ext::oneapi::detail::filter_selector_impl::filter_selector_impl().

◆ createDummyRange()

template<int Dims>
static range<Dims> sycl::_V1::ext::oneapi::detail::createDummyRange ( )
static

Definition at line 22 of file weak_object.hpp.

◆ get_layout_id()

template<sycl::ext::oneapi::experimental::matrix::matrix_layout Layout>
constexpr int sycl::_V1::ext::oneapi::detail::get_layout_id ( )
constexpr

◆ get_layout_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major >()

template<>
constexpr int sycl::_V1::ext::oneapi::detail::get_layout_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major > ( )
constexpr

Definition at line 200 of file matrix-tensorcores-legacy.hpp.

◆ get_layout_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major >()

template<>
constexpr int sycl::_V1::ext::oneapi::detail::get_layout_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major > ( )
constexpr

Definition at line 194 of file matrix-tensorcores-legacy.hpp.

◆ get_layout_pair_id()

template<sycl::ext::oneapi::experimental::matrix::matrix_layout LayoutA, sycl::ext::oneapi::experimental::matrix::matrix_layout LayoutB>
constexpr int sycl::_V1::ext::oneapi::detail::get_layout_pair_id ( )
constexpr

◆ get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major >()

template<>
constexpr int sycl::_V1::ext::oneapi::detail::get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major > ( )
constexpr

Definition at line 511 of file matrix-tensorcores-legacy.hpp.

◆ get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major >()

template<>
constexpr int sycl::_V1::ext::oneapi::detail::get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major > ( )
constexpr

Definition at line 504 of file matrix-tensorcores-legacy.hpp.

◆ get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major >()

template<>
constexpr int sycl::_V1::ext::oneapi::detail::get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::col_major > ( )
constexpr

Definition at line 497 of file matrix-tensorcores-legacy.hpp.

◆ get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major >()

template<>
constexpr int sycl::_V1::ext::oneapi::detail::get_layout_pair_id< sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major, sycl::ext::oneapi::experimental::matrix::matrix_layout::row_major > ( )
constexpr

Definition at line 490 of file matrix-tensorcores-legacy.hpp.

◆ getLoadOrder()

constexpr memory_order sycl::_V1::ext::oneapi::detail::getLoadOrder ( memory_order  order)
inlineconstexpr

Definition at line 74 of file atomic_ref.hpp.

References sycl::_V1::memory_order_acq_rel, sycl::_V1::memory_order_acquire, sycl::_V1::memory_order_relaxed, sycl::_V1::memory_order_release, and sycl::_V1::memory_order_seq_cst.

Referenced by sycl::_V1::detail::atomic_ref_impl< T *, DefaultOrder, DefaultScope, AddressSpace >::fetch_add(), sycl::_V1::ext::oneapi::detail::atomic_ref_impl< T *, DefaultOrder, DefaultScope, AddressSpace >::fetch_add(), sycl::_V1::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_floating_point< T >::value > >::fetch_add(), sycl::_V1::ext::oneapi::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_floating_point< T >::value > >::fetch_add(), sycl::_V1::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_integral< T >::value > >::fetch_max(), sycl::_V1::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_floating_point< T >::value > >::fetch_max(), sycl::_V1::ext::oneapi::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_integral< T >::value > >::fetch_max(), sycl::_V1::ext::oneapi::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_floating_point< T >::value > >::fetch_max(), sycl::_V1::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_integral< T >::value > >::fetch_min(), sycl::_V1::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_floating_point< T >::value > >::fetch_min(), sycl::_V1::ext::oneapi::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_integral< T >::value > >::fetch_min(), sycl::_V1::ext::oneapi::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_floating_point< T >::value > >::fetch_min(), sycl::_V1::detail::atomic_ref_impl< T *, DefaultOrder, DefaultScope, AddressSpace >::fetch_sub(), sycl::_V1::ext::oneapi::detail::atomic_ref_impl< T *, DefaultOrder, DefaultScope, AddressSpace >::fetch_sub(), sycl::_V1::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_floating_point< T >::value > >::fetch_sub(), and sycl::_V1::ext::oneapi::detail::atomic_ref_impl< T, DefaultOrder, DefaultScope, AddressSpace, typename detail::enable_if_t< std::is_floating_point< T >::value > >::fetch_sub().

◆ getSyclWeakObjImpl()

template<typename SYCLObjT >
decltype(weak_object_base<SYCLObjT>::MObjWeakPtr) sycl::_V1::ext::oneapi::detail::getSyclWeakObjImpl ( const weak_object_base< SYCLObjT > &  WeakObj)

Definition at line 21 of file weak_object_base.hpp.

Referenced by sycl::_V1::detail::OwnerLessBase< SyclObjT >::ext_oneapi_owner_before().

◆ tokenize()

std::vector<std::string> sycl::_V1::ext::oneapi::detail::tokenize ( const std::string &  Filter,
const std::string &  Delim 
)

Definition at line 26 of file filter_selector_impl.cpp.

Referenced by create_filter(), and sycl::_V1::ext::oneapi::detail::filter_selector_impl::filter_selector_impl().