/home/docs/checkouts/readthedocs.org/user_builds/advanced-micro-devices-composable-kernel/checkouts/develop/include/ck_tile/core/config.hpp File Reference

/home/docs/checkouts/readthedocs.org/user_builds/advanced-micro-devices-composable-kernel/checkouts/develop/include/ck_tile/core/config.hpp File Reference#

Composable Kernel: /home/docs/checkouts/readthedocs.org/user_builds/advanced-micro-devices-composable-kernel/checkouts/develop/include/ck_tile/core/config.hpp File Reference
Classes | Namespaces | Macros
config.hpp File Reference
#include "hip/hip_version.h"
#include "hip/hip_runtime.h"
#include "hip/hip_fp16.h"

Go to the source code of this file.

Classes

struct  ck_tile::core::amdgcn_compiler_target_state
 Defines compiler states for supported AMDGCN devices. More...
 

Namespaces

 ck_tile
 
 ck_tile::core
 

Macros

#define CK_TILE_HOST   inline
 
#define CK_TILE_DEVICE   inline
 
#define CK_TILE_HOST_DEVICE   inline
 
#define CK_TILE_DEVICE_EXTERN
 
#define CK_TILE_HOST_DEVICE_EXTERN
 
#define CK_TILE_GENERIC_ADDR
 
#define CK_TILE_GLOBAL_ADDR
 
#define CK_TILE_LDS_ADDR
 
#define CK_TILE_BUF_RES_ADDR
 
#define CK_TILE_USE_CUSTOM_DATA_TYPE   0
 
#define CK_TILE_FLOAT_TO_BFLOAT16_STANDARD   0
 
#define CK_TILE_FLOAT_TO_BFLOAT16_TRUNCATE_WITH_NAN   1
 
#define CK_TILE_FLOAT_TO_BFLOAT16_TRUNCATE   2
 
#define CK_TILE_FLOAT_TO_BFLOAT16_STANDARD_ASM   3
 
#define CK_TILE_FLOAT_TO_BFLOAT16_RTA_ASM   4
 
#define CK_TILE_FLOAT_TO_BFLOAT16_DEFAULT   CK_TILE_FLOAT_TO_BFLOAT16_TRUNCATE
 
#define CK_TILE_FLOAT_TO_FP8_STANDARD   0
 
#define CK_TILE_FLOAT_TO_FP8_STOCHASTIC   1
 
#define CK_TILE_FLOAT_TO_FP8_DEFAULT   CK_TILE_FLOAT_TO_FP8_STANDARD
 
#define CK_TILE_STATICALLY_INDEXED_ARRAY_USE_ARRAY   0
 
#define CK_TILE_STATICALLY_INDEXED_ARRAY_USE_TUPLE   1
 
#define CK_TILE_STATICALLY_INDEXED_ARRAY_DEFAULT   CK_TILE_STATICALLY_INDEXED_ARRAY_USE_TUPLE
 
#define CK_TILE_THREAD_BUFFER_USE_ARRAY   0
 
#define CK_TILE_THREAD_BUFFER_USE_TUPLE   1
 
#define CK_TILE_THREAD_BUFFER_DEFAULT   CK_TILE_THREAD_BUFFER_USE_ARRAY
 
#define CK_TILE_TUPLE_CTOR_WITH_INITIALIZER_LIST   0
 
#define CK_TILE_USE_LAUNCH_BOUNDS   1
 
#define CK_TILE_TIME_KERNEL   1
 
#define CK_TILE_MAX_THREAD_PER_BLOCK   256
 
#define CK_TILE_MIN_BLOCK_PER_CU   2
 
#define CK_TILE_EXPERIMENTAL_USE_BUFFER_LOAD_OOB_CHECK_OFFSET_TRICK   0
 
#define CK_TILE_EXPERIMENTAL_USE_BUFFER_STORE_OOB_CHECK_OFFSET_TRICK   1
 
#define CK_TILE_EXPERIMENTAL_USE_BUFFER_ATOMIC_ADD_OOB_CHECK_OFFSET_TRICK   1
 
#define CK_TILE_EXPERIMENTAL_USE_BUFFER_ATOMIC_MAX_OOB_CHECK_OFFSET_TRICK   1
 
#define CK_TILE_USE_AMD_LDS_DIRECT_LOAD_INLINE_ASM   1
 
#define CK_TILE_USE_AMD_BUFFER_LOAD   1
 
#define CK_TILE_USE_AMD_BUFFER_STORE   1
 
#define CK_TILE_USE_AMD_BUFFER_ATOMIC_ADD_INTEGER   1
 
#define CK_TILE_USE_PK4_LAYOUT_SHUFFLE   1
 
#define CK_TILE_USE_AMD_BUFFER_ATOMIC_ADD_FLOAT   1
 
#define CK_TILE_USE_AMD_BUFFER_ATOMIC_MAX_FLOAT64   0
 
#define CK_TILE_EXPERIMENTAL_USE_MEMCPY_FOR_VECTOR_ACCESS   0
 
#define CK_TILE_WORKAROUND_SWDEV_XXXXXX_INT8_DS_WRITE_ISSUE   1
 
#define CK_TILE_WORKAROUND_ROCM_6_1_SCRATCH_MEMORY_ISSUE   0
 
#define CK_TILE_WORKAROUND_ROCM_6_2_SCRATCH_MEMORY_ISSUE   0
 
#define CK_TILE_USE_LLVM_BUILTIN_BF16   0
 
#define CK_TILE_DEBUG_LOG   0
 
#define CK_TILE_BUFFER_RESOURCE_3RD_DWORD   0xffffffff
 
#define CK_TILE_EXPERIMENTAL_BLOCK_SYNC_LDS_WITHOUT_SYNC_VMEM   1
 
#define CK_TILE_USE_SUBDWORD_TILE_CAST   0
 
#define CK_TILE_USE_PK_FP16_TILE_CAST   0
 
#define CK_TILE_FMHA_FWD_FAST_EXP2   0
 
#define CK_TILE_FMHA_FLOAT_TO_FLOAT16_RTN   0
 
#define CK_TILE_BUFFER_LOAD_RAW_BF16_WA   1
 
#define CK_TILE_WORKAROUND_SWDEV_383542   1
 
#define CK_TILE_REFERENCE_MOE_SORTING_MOCK_ID   1
 
#define CK_TILE_USE_OCP_FP8   0
 
#define CK_TILE_USE_BUFFER_ADDRESSING_BUILTIN   0
 
#define CK_TILE_WA_ISSUE_2028   0
 
#define CK_TILE_ENC_SUPPORT_Y_TO_R   0
 
#define CK_TILE_UNSUPPORTED_IMPL(MSG)   __attribute__((deprecated(MSG)))
 
#define CK_TILE_COMPILER_TARGETS_LIST
 

Macro Definition Documentation

◆ CK_TILE_BUF_RES_ADDR

#define CK_TILE_BUF_RES_ADDR

◆ CK_TILE_BUFFER_LOAD_RAW_BF16_WA

#define CK_TILE_BUFFER_LOAD_RAW_BF16_WA   1

◆ CK_TILE_BUFFER_RESOURCE_3RD_DWORD

#define CK_TILE_BUFFER_RESOURCE_3RD_DWORD   0xffffffff

◆ CK_TILE_COMPILER_TARGETS_LIST

#define CK_TILE_COMPILER_TARGETS_LIST
Value:
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX908, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX90A, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX942, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX950, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1030, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1031, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1032, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1034, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1035, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1036, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX10_3_GENERIC, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1100, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1101, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1102, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1103, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1150, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1151, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1152, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX11_GENERIC, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1200, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX1201, \
amdgcn_compiler_target_state::CK_TILE_ARCH_GFX12_GENERIC

◆ CK_TILE_DEBUG_LOG

#define CK_TILE_DEBUG_LOG   0

◆ CK_TILE_DEVICE

#define CK_TILE_DEVICE   inline

◆ CK_TILE_DEVICE_EXTERN

#define CK_TILE_DEVICE_EXTERN

◆ CK_TILE_ENC_SUPPORT_Y_TO_R

#define CK_TILE_ENC_SUPPORT_Y_TO_R   0

◆ CK_TILE_EXPERIMENTAL_BLOCK_SYNC_LDS_WITHOUT_SYNC_VMEM

#define CK_TILE_EXPERIMENTAL_BLOCK_SYNC_LDS_WITHOUT_SYNC_VMEM   1

◆ CK_TILE_EXPERIMENTAL_USE_BUFFER_ATOMIC_ADD_OOB_CHECK_OFFSET_TRICK

#define CK_TILE_EXPERIMENTAL_USE_BUFFER_ATOMIC_ADD_OOB_CHECK_OFFSET_TRICK   1

◆ CK_TILE_EXPERIMENTAL_USE_BUFFER_ATOMIC_MAX_OOB_CHECK_OFFSET_TRICK

#define CK_TILE_EXPERIMENTAL_USE_BUFFER_ATOMIC_MAX_OOB_CHECK_OFFSET_TRICK   1

◆ CK_TILE_EXPERIMENTAL_USE_BUFFER_LOAD_OOB_CHECK_OFFSET_TRICK

#define CK_TILE_EXPERIMENTAL_USE_BUFFER_LOAD_OOB_CHECK_OFFSET_TRICK   0

◆ CK_TILE_EXPERIMENTAL_USE_BUFFER_STORE_OOB_CHECK_OFFSET_TRICK

#define CK_TILE_EXPERIMENTAL_USE_BUFFER_STORE_OOB_CHECK_OFFSET_TRICK   1

◆ CK_TILE_EXPERIMENTAL_USE_MEMCPY_FOR_VECTOR_ACCESS

#define CK_TILE_EXPERIMENTAL_USE_MEMCPY_FOR_VECTOR_ACCESS   0

◆ CK_TILE_FLOAT_TO_BFLOAT16_DEFAULT

#define CK_TILE_FLOAT_TO_BFLOAT16_DEFAULT   CK_TILE_FLOAT_TO_BFLOAT16_TRUNCATE

◆ CK_TILE_FLOAT_TO_BFLOAT16_RTA_ASM

#define CK_TILE_FLOAT_TO_BFLOAT16_RTA_ASM   4

◆ CK_TILE_FLOAT_TO_BFLOAT16_STANDARD

#define CK_TILE_FLOAT_TO_BFLOAT16_STANDARD   0

◆ CK_TILE_FLOAT_TO_BFLOAT16_STANDARD_ASM

#define CK_TILE_FLOAT_TO_BFLOAT16_STANDARD_ASM   3

◆ CK_TILE_FLOAT_TO_BFLOAT16_TRUNCATE

#define CK_TILE_FLOAT_TO_BFLOAT16_TRUNCATE   2

◆ CK_TILE_FLOAT_TO_BFLOAT16_TRUNCATE_WITH_NAN

#define CK_TILE_FLOAT_TO_BFLOAT16_TRUNCATE_WITH_NAN   1

◆ CK_TILE_FLOAT_TO_FP8_DEFAULT

#define CK_TILE_FLOAT_TO_FP8_DEFAULT   CK_TILE_FLOAT_TO_FP8_STANDARD

◆ CK_TILE_FLOAT_TO_FP8_STANDARD

#define CK_TILE_FLOAT_TO_FP8_STANDARD   0

◆ CK_TILE_FLOAT_TO_FP8_STOCHASTIC

#define CK_TILE_FLOAT_TO_FP8_STOCHASTIC   1

◆ CK_TILE_FMHA_FLOAT_TO_FLOAT16_RTN

#define CK_TILE_FMHA_FLOAT_TO_FLOAT16_RTN   0

◆ CK_TILE_FMHA_FWD_FAST_EXP2

#define CK_TILE_FMHA_FWD_FAST_EXP2   0

◆ CK_TILE_GENERIC_ADDR

#define CK_TILE_GENERIC_ADDR

◆ CK_TILE_GLOBAL_ADDR

#define CK_TILE_GLOBAL_ADDR

◆ CK_TILE_HOST

#define CK_TILE_HOST   inline

◆ CK_TILE_HOST_DEVICE

#define CK_TILE_HOST_DEVICE   inline

◆ CK_TILE_HOST_DEVICE_EXTERN

#define CK_TILE_HOST_DEVICE_EXTERN

◆ CK_TILE_LDS_ADDR

#define CK_TILE_LDS_ADDR

◆ CK_TILE_MAX_THREAD_PER_BLOCK

#define CK_TILE_MAX_THREAD_PER_BLOCK   256

◆ CK_TILE_MIN_BLOCK_PER_CU

#define CK_TILE_MIN_BLOCK_PER_CU   2

◆ CK_TILE_REFERENCE_MOE_SORTING_MOCK_ID

#define CK_TILE_REFERENCE_MOE_SORTING_MOCK_ID   1

◆ CK_TILE_STATICALLY_INDEXED_ARRAY_DEFAULT

#define CK_TILE_STATICALLY_INDEXED_ARRAY_DEFAULT   CK_TILE_STATICALLY_INDEXED_ARRAY_USE_TUPLE

◆ CK_TILE_STATICALLY_INDEXED_ARRAY_USE_ARRAY

#define CK_TILE_STATICALLY_INDEXED_ARRAY_USE_ARRAY   0

◆ CK_TILE_STATICALLY_INDEXED_ARRAY_USE_TUPLE

#define CK_TILE_STATICALLY_INDEXED_ARRAY_USE_TUPLE   1

◆ CK_TILE_THREAD_BUFFER_DEFAULT

#define CK_TILE_THREAD_BUFFER_DEFAULT   CK_TILE_THREAD_BUFFER_USE_ARRAY

◆ CK_TILE_THREAD_BUFFER_USE_ARRAY

#define CK_TILE_THREAD_BUFFER_USE_ARRAY   0

◆ CK_TILE_THREAD_BUFFER_USE_TUPLE

#define CK_TILE_THREAD_BUFFER_USE_TUPLE   1

◆ CK_TILE_TIME_KERNEL

#define CK_TILE_TIME_KERNEL   1

◆ CK_TILE_TUPLE_CTOR_WITH_INITIALIZER_LIST

#define CK_TILE_TUPLE_CTOR_WITH_INITIALIZER_LIST   0

◆ CK_TILE_UNSUPPORTED_IMPL

#define CK_TILE_UNSUPPORTED_IMPL (   MSG)    __attribute__((deprecated(MSG)))

◆ CK_TILE_USE_AMD_BUFFER_ATOMIC_ADD_FLOAT

#define CK_TILE_USE_AMD_BUFFER_ATOMIC_ADD_FLOAT   1

◆ CK_TILE_USE_AMD_BUFFER_ATOMIC_ADD_INTEGER

#define CK_TILE_USE_AMD_BUFFER_ATOMIC_ADD_INTEGER   1

◆ CK_TILE_USE_AMD_BUFFER_ATOMIC_MAX_FLOAT64

#define CK_TILE_USE_AMD_BUFFER_ATOMIC_MAX_FLOAT64   0

◆ CK_TILE_USE_AMD_BUFFER_LOAD

#define CK_TILE_USE_AMD_BUFFER_LOAD   1

◆ CK_TILE_USE_AMD_BUFFER_STORE

#define CK_TILE_USE_AMD_BUFFER_STORE   1

◆ CK_TILE_USE_AMD_LDS_DIRECT_LOAD_INLINE_ASM

#define CK_TILE_USE_AMD_LDS_DIRECT_LOAD_INLINE_ASM   1

◆ CK_TILE_USE_BUFFER_ADDRESSING_BUILTIN

#define CK_TILE_USE_BUFFER_ADDRESSING_BUILTIN   0

◆ CK_TILE_USE_CUSTOM_DATA_TYPE

#define CK_TILE_USE_CUSTOM_DATA_TYPE   0

◆ CK_TILE_USE_LAUNCH_BOUNDS

#define CK_TILE_USE_LAUNCH_BOUNDS   1

◆ CK_TILE_USE_LLVM_BUILTIN_BF16

#define CK_TILE_USE_LLVM_BUILTIN_BF16   0

◆ CK_TILE_USE_OCP_FP8

#define CK_TILE_USE_OCP_FP8   0

◆ CK_TILE_USE_PK4_LAYOUT_SHUFFLE

#define CK_TILE_USE_PK4_LAYOUT_SHUFFLE   1

◆ CK_TILE_USE_PK_FP16_TILE_CAST

#define CK_TILE_USE_PK_FP16_TILE_CAST   0

◆ CK_TILE_USE_SUBDWORD_TILE_CAST

#define CK_TILE_USE_SUBDWORD_TILE_CAST   0

◆ CK_TILE_WA_ISSUE_2028

#define CK_TILE_WA_ISSUE_2028   0

◆ CK_TILE_WORKAROUND_ROCM_6_1_SCRATCH_MEMORY_ISSUE

#define CK_TILE_WORKAROUND_ROCM_6_1_SCRATCH_MEMORY_ISSUE   0

◆ CK_TILE_WORKAROUND_ROCM_6_2_SCRATCH_MEMORY_ISSUE

#define CK_TILE_WORKAROUND_ROCM_6_2_SCRATCH_MEMORY_ISSUE   0

◆ CK_TILE_WORKAROUND_SWDEV_383542

#define CK_TILE_WORKAROUND_SWDEV_383542   1

◆ CK_TILE_WORKAROUND_SWDEV_XXXXXX_INT8_DS_WRITE_ISSUE

#define CK_TILE_WORKAROUND_SWDEV_XXXXXX_INT8_DS_WRITE_ISSUE   1