DPC++ Runtime
Runtime libraries for oneAPI DPC++
Classes | Functions | Variables
cl::sycl::ext::intel::detail Namespace Reference

Classes

struct  elems_per_dword
 
class  submatrix
 

Functions

template<typename Group , typename T , size_t NumRows, size_t NumCols, matrix::matrix_layout Layout>
static __SYCL_ALWAYS_INLINE std::enable_if<(NumRows > matrix::tile_size)||(NumCols *sizeof(T)/4 > matrix::tile_size), void >::type submatrix_load (detail::submatrix< T > &sub_m, matrix::joint_matrix< Group, T, NumRows, NumCols, Layout > jm, uint32_t row, uint32_t col, size_t stride, matrix::matrix_layout layout, bool shouldreload)
 
template<typename Group , typename T , size_t NumRows, size_t NumCols, matrix::matrix_layout Layout>
static __SYCL_ALWAYS_INLINE std::enable_if<(NumRows<=matrix::tile_size) &&(NumCols *sizeof(T)/4<=matrix::tile_size), void >::type submatrix_load (detail::submatrix< T > &sub_m, matrix::joint_matrix< Group, T, NumRows, NumCols, Layout > &jm, uint32_t row, uint32_t col, size_t stride, matrix::matrix_layout layout, bool shouldreload)
 
static __SYCL_ALWAYS_INLINE void submatrix_mad (detail::submatrix< int8_t > &sub_ma, detail::submatrix< int8_t > &sub_mb, detail::submatrix< int32_t > &sub_mc)
 
static __SYCL_ALWAYS_INLINE void submatrix_mad (detail::submatrix< unsigned short > &sub_ma, detail::submatrix< unsigned short > &sub_mb, detail::submatrix< float > &sub_mc)
 
template<typename Group , typename T , size_t NumRows, size_t NumCols>
static __SYCL_ALWAYS_INLINE std::enable_if<(NumRows > matrix::tile_size)||(NumCols *sizeof(T)/4 > matrix::tile_size), void >::type submatrix_store (detail::submatrix< T > &sub_m, matrix::joint_matrix< Group, T, NumRows, NumCols > &jm, uint32_t row, uint32_t col, size_t stride, matrix::matrix_layout layout, bool shouldreload)
 
template<typename Group , typename T , size_t NumRows, size_t NumCols>
static __SYCL_ALWAYS_INLINE std::enable_if<(NumRows<=matrix::tile_size) &&(NumCols *sizeof(T)/4<=matrix::tile_size), void >::type submatrix_store (detail::submatrix< T > &sub_m, matrix::joint_matrix< Group, T, NumRows, NumCols > &jm, uint32_t row, uint32_t col, size_t stride, matrix::matrix_layout layout, bool shouldreload)
 

Variables

constexpr size_t dynamic_extent = std::numeric_limits<size_t>::max()
 

Function Documentation

◆ submatrix_load() [1/2]

template<typename Group , typename T , size_t NumRows, size_t NumCols, matrix::matrix_layout Layout>
static __SYCL_ALWAYS_INLINE std::enable_if<(NumRows <= matrix::tile_size) && (NumCols * sizeof(T) / 4 <= matrix::tile_size), void>::type cl::sycl::ext::intel::detail::submatrix_load ( detail::submatrix< T > &  sub_m,
matrix::joint_matrix< Group, T, NumRows, NumCols, Layout > &  jm,
uint32_t  row,
uint32_t  col,
size_t  stride,
matrix::matrix_layout  layout,
bool  shouldreload 
)
inlinestatic

Definition at line 229 of file matrix-aot-amx.hpp.

◆ submatrix_load() [2/2]

template<typename Group , typename T , size_t NumRows, size_t NumCols, matrix::matrix_layout Layout>
static __SYCL_ALWAYS_INLINE std::enable_if<(NumRows > matrix::tile_size) || (NumCols * sizeof(T) / 4 > matrix::tile_size), void>::type cl::sycl::ext::intel::detail::submatrix_load ( detail::submatrix< T > &  sub_m,
matrix::joint_matrix< Group, T, NumRows, NumCols, Layout >  jm,
uint32_t  row,
uint32_t  col,
size_t  stride,
matrix::matrix_layout  layout,
bool  shouldreload 
)
inlinestatic

Definition at line 209 of file matrix-aot-amx.hpp.

◆ submatrix_mad() [1/2]

static __SYCL_ALWAYS_INLINE void cl::sycl::ext::intel::detail::submatrix_mad ( detail::submatrix< int8_t > &  sub_ma,
detail::submatrix< int8_t > &  sub_mb,
detail::submatrix< int32_t > &  sub_mc 
)
inlinestatic

Definition at line 254 of file matrix-aot-amx.hpp.

◆ submatrix_mad() [2/2]

static __SYCL_ALWAYS_INLINE void cl::sycl::ext::intel::detail::submatrix_mad ( detail::submatrix< unsigned short > &  sub_ma,
detail::submatrix< unsigned short > &  sub_mb,
detail::submatrix< float > &  sub_mc 
)
inlinestatic

Definition at line 263 of file matrix-aot-amx.hpp.

◆ submatrix_store() [1/2]

template<typename Group , typename T , size_t NumRows, size_t NumCols>
static __SYCL_ALWAYS_INLINE std::enable_if<(NumRows > matrix::tile_size) || (NumCols * sizeof(T) / 4 > matrix::tile_size), void>::type cl::sycl::ext::intel::detail::submatrix_store ( detail::submatrix< T > &  sub_m,
matrix::joint_matrix< Group, T, NumRows, NumCols > &  jm,
uint32_t  row,
uint32_t  col,
size_t  stride,
matrix::matrix_layout  layout,
bool  shouldreload 
)
inlinestatic

Definition at line 276 of file matrix-aot-amx.hpp.

◆ submatrix_store() [2/2]

template<typename Group , typename T , size_t NumRows, size_t NumCols>
static __SYCL_ALWAYS_INLINE std::enable_if<(NumRows <= matrix::tile_size) && (NumCols * sizeof(T) / 4 <= matrix::tile_size), void>::type cl::sycl::ext::intel::detail::submatrix_store ( detail::submatrix< T > &  sub_m,
matrix::joint_matrix< Group, T, NumRows, NumCols > &  jm,
uint32_t  row,
uint32_t  col,
size_t  stride,
matrix::matrix_layout  layout,
bool  shouldreload 
)
inlinestatic

Definition at line 294 of file matrix-aot-amx.hpp.

Variable Documentation

◆ dynamic_extent

constexpr size_t cl::sycl::ext::intel::detail::dynamic_extent = std::numeric_limits<size_t>::max()
constexpr

Definition at line 50 of file matrix-aot-amx.hpp.

Referenced by cl::sycl::ext::intel::experimental::matrix::joint_matrix< Group, T, NumRows, NumCols, Layout, Enabled >::joint_matrix().