StreamKHostArgs Struct Reference

StreamKHostArgs Struct Reference#

Composable Kernel: ck_tile::StreamKHostArgs Struct Reference
Public Member Functions | Public Attributes | List of all members
ck_tile::StreamKHostArgs Struct Reference

The Stream K GEMM kernel host arguments. More...

#include <streamk_gemm_kernel.hpp>

Inheritance diagram for ck_tile::StreamKHostArgs:
ck_tile::UniversalGemmHostArgs< NumATensor, NumBTensor, NumDTensor >

Public Member Functions

CK_TILE_HOST StreamKHostArgs (const void *a_ptr_, const void *b_ptr_, void *c_ptr_, index_t M_, index_t N_, index_t K_, index_t stride_A_, index_t stride_B_, index_t stride_C_, StreamKReductionStrategy reduction_strategy_, uint32_t num_sk_blocks_=0xffffffff)
Public Member Functions inherited from ck_tile::UniversalGemmHostArgs< NumATensor, NumBTensor, NumDTensor >
CK_TILE_HOST UniversalGemmHostArgs (const std::array< const void *, NumATensor > &as_ptr_, const std::array< const void *, NumBTensor > &bs_ptr_, const std::array< const void *, NumDTensor > &ds_ptr_, void *e_ptr_, index_t k_batch_, index_t M_, index_t N_, index_t K_, const std::array< index_t, NumATensor > &stride_As_, const std::array< index_t, NumBTensor > &stride_Bs_, const std::array< index_t, NumDTensor > &stride_Ds_, index_t stride_E_)

Public Attributes

ck_tile::StreamKReductionStrategy reduction_strategy
uint32_t num_sk_blocks
Public Attributes inherited from ck_tile::UniversalGemmHostArgs< NumATensor, NumBTensor, NumDTensor >
const std::array< const void *, NumATensor > as_ptr
const std::array< const void *, NumBTensor > bs_ptr
const std::array< const void *, NumDTensor > ds_ptr
union { 
   void *   e_ptr 
   void *   c_ptr 
}; 
index_t M
index_t N
index_t K
const std::array< index_t, NumATensor > stride_As
const std::array< index_t, NumBTensor > stride_Bs
const std::array< index_t, NumDTensor > stride_Ds
union { 
   index_t   stride_E 
   index_t   stride_C 
}; 
index_t k_batch

Detailed Description

The Stream K GEMM kernel host arguments.

Overview
This structure is passed to StreamKKernel when creating the kernel arguments object. It contains all necessary information required to build proper kernel arguments and launch the kernel on GPU. This structure defines the GEMM problem configuration by stating all required information like M,N,K sizes and respective strides.

Constructor & Destructor Documentation

◆ StreamKHostArgs()

CK_TILE_HOST ck_tile::StreamKHostArgs::StreamKHostArgs ( const void * a_ptr_,
const void * b_ptr_,
void * c_ptr_,
index_t M_,
index_t N_,
index_t K_,
index_t stride_A_,
index_t stride_B_,
index_t stride_C_,
StreamKReductionStrategy reduction_strategy_,
uint32_t num_sk_blocks_ = 0xffffffff )
inlineexplicit

Member Data Documentation

◆ num_sk_blocks

uint32_t ck_tile::StreamKHostArgs::num_sk_blocks

◆ reduction_strategy

ck_tile::StreamKReductionStrategy ck_tile::StreamKHostArgs::reduction_strategy
The documentation for this struct was generated from the following file: