ROCm/composable_kernel
1
0
Fork 0
mirror of https://github.com/ROCm/composable_kernel.git synced 2026-06-07 08:15:04 +00:00
Code Issues Packages Projects Releases Wiki Activity
Files
bec4968e480fa254f5382d09aa768e17bea48117
composable_kernel/include/ck/tensor_operation/gpu/device/impl
History
JonathanLichtnerAMD 3c7fef7f80 Conditionally log a DeviceGroupedConvBwdWeightTwoStage_Xdl_CShuffle warning (#1860) 
The code was emitting a warning if MIOpen did not create a workspace
prior to invoking the IsSupportedArgument method, but the
condition for MIOpen to create a workspace was not met, and so this
condition was not really an error but more of a log message.  This commit
addresses this issue by using the CK_LOGGING facility to only generate the
log message if the CK_LOGGING environment variable is set.
2025-02-11 17:25:00 -07:00
..
codegen_device_grouped_conv_fwd_multiple_abd_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_avgpool2d_bwd_nhwc_nhwc.hpp
Pool2d max/avg kernel in the BWD version (#1494)
2024-09-12 11:47:52 +02:00
device_avgpool3d_bwd_ndhwc_ndhwc.hpp
…
device_batched_contraction_multiple_d_wmma_cshuffle.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_batched_contraction_multiple_d_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_batched_gemm_e_permute_xdl.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_batched_gemm_gemm_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_batched_gemm_multi_d_xdl.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_batched_gemm_multiple_d_dl.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_batched_gemm_multiple_d_gemm_multiple_d_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_batched_gemm_multiple_d_xdl_cshuffle_v3.hpp
Add SplitK support into Batched GEMM V3 (#1729)
2024-12-13 21:08:35 +01:00
device_batched_gemm_reduce_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_batched_gemm_softmax_gemm_permute_wmma_cshuffle.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_batched_gemm_softmax_gemm_permute_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_batched_gemm_softmax_gemm_xdl_cshuffle.hpp
Introduce gemm_softmax_gemm to codegen (#1542)
2025-02-11 08:07:24 -08:00
device_batched_gemm_xdl_fpAintB_b_scale.hpp
Added Int4 mixed batch gemm support (#1839)
2025-02-10 11:17:02 +08:00
device_batched_gemm_xdl.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_batchnorm_backward_impl.hpp
…
device_batchnorm_forward_impl_obsolete.hpp
…
device_batchnorm_forward_impl.hpp
…
device_cgemm_4gemm_xdl_cshuffle.hpp
Implement GetWorkSpaceSize from BaseOperator. (#1564)
2024-10-12 14:05:11 +08:00
device_column_to_image_impl.hpp
Codegen hipRTC compilation (#1579)
2025-01-31 09:48:39 -08:00
device_contraction_multiple_abd_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_contraction_multiple_d_xdl_cshuffle.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_contraction_utils.hpp
Fix continous dim selection in contraction (#1336)
2024-06-18 10:26:49 +02:00
device_conv2d_backward_weight_xdl_c_shuffle_nhwc_kyxc_nhwk.hpp
…
device_conv2d_bwd_data_xdl_nhwc_kyxc_nhwk.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_conv2d_fwd_xdl_c_shuffle_bias_activation_add_nhwc_kyxc_nhwk.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_conv2d_fwd_xdl_c_shuffle_bias_activation_nhwc_kyxc_nhwk.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_conv2d_fwd_xdl_c_shuffle_nhwc_kyxc_nhwk.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_conv2d_fwd_xdl_nhwc_kyxc_nhwk.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_conv3d_fwd_naive_ndhwc_kzyxc_ndhwk.hpp
…
device_conv3d_fwd_xdl_ndhwc_kzyxc_ndhwk.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_convnd_bwd_data_nwc_kxc_nwk_dl.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_convnd_bwd_data_nwc_kxc_nwk_xdl.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_elementwise_dynamic_vector_dims_impl.hpp
…
device_elementwise_normalization_impl.hpp
…
device_elementwise_scale_impl.hpp
…
device_fpAintB_gemm_wmma.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_gemm_bias_add_reduce_xdl_cshuffle.hpp
…
device_gemm_dl.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_gemm_dpp.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_gemm_multiple_abd_xdl_cshuffle.hpp
bf16A_Int8B with fastgelu/bias (#1264)
2024-04-26 07:26:30 -05:00
device_gemm_multiple_d_dl.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_gemm_multiple_d_layernorm_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_gemm_multiple_d_multiple_r_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_gemm_multiple_d_wmma_cshuffle.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_gemm_multiple_d_xdl_cshuffle_lds_direct_load.hpp
…
device_gemm_multiple_d_xdl_cshuffle_v3_ab_scale.hpp
[GEMM] F8 GEMM, performance optimized. (#1384)
2024-07-19 22:06:52 +08:00
device_gemm_multiple_d_xdl_cshuffle_v3.hpp
Add gemm universal bf16 instances (#1484)
2024-09-04 20:58:54 -07:00
device_gemm_multiple_d_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_gemm_reduce_xdl_cshuffle.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_gemm_wmma.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_gemm_xdl_cshuffle_lds_direct_load.hpp
…
device_gemm_xdl_cshuffle_streamk_v3.hpp
BF16 GEMM Stream-K (#1541)
2025-01-02 10:30:04 -08:00
device_gemm_xdl_cshuffle_v2.hpp
…
device_gemm_xdl_cshuffle_v3_b_scale.hpp
Implement the fp16xint4 scale weight only kernel for Ali (#1786)
2025-01-03 18:35:21 +08:00
device_gemm_xdl_cshuffle_v3.hpp
CK Tile - small fix to hotloop scheduler & KPack value. (#1867)
2025-02-07 15:07:07 -07:00
device_gemm_xdl_cshuffle_v3r1.hpp
Universal gemm splitk using reduce (with multi-d) (#1341)
2024-07-19 22:01:22 +08:00
device_gemm_xdl_cshuffle.hpp
…
device_gemm_xdl_layernorm_cshuffle.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_gemm_xdl_skip_b_lds.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_gemm_xdl_splitk_c_shuffle_lds_direct_load.hpp
Codegen hipRTC compilation (#1579)
2025-01-31 09:48:39 -08:00
device_gemm_xdl_splitk_c_shuffle.hpp
Codegen hipRTC compilation (#1579)
2025-01-31 09:48:39 -08:00
device_gemm_xdl_streamk.hpp
…
device_gemm_xdl_waveletmodel_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_gemm_xdl.hpp
…
device_grouped_contraction_multiple_d_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_conv_bwd_data_multiple_d_wmma_cshuffle.hpp
Support large batch tensors in grouped conv bwd data (#1711)
2024-12-06 10:55:23 +01:00
device_grouped_conv_bwd_data_multiple_d_xdl_cshuffle_v1.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_conv_bwd_weight_dl.hpp
Add support for NGCHW in grouped conv bwd wei (#1491)
2024-09-03 10:52:03 +02:00
device_grouped_conv_bwd_weight_multiple_d_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_conv_bwd_weight_two_stage_xdl_cshuffle.hpp
Conditionally log a DeviceGroupedConvBwdWeightTwoStage_Xdl_CShuffle warning (#1860)
2025-02-11 17:25:00 -07:00
device_grouped_conv_bwd_weight_wmma_cshuffle.hpp
Add support for NGCHW in grouped conv bwd wei (#1491)
2024-09-03 10:52:03 +02:00
device_grouped_conv_bwd_weight_xdl_cshuffle.hpp
Grouped convolution backward weight special vector size loads (#1772)
2025-01-10 22:02:30 +08:00
device_grouped_conv_fwd_dl_multiple_d_nhwc_kyxc_nhwk.hpp
Statically Cast Pointer Offset (#1631)
2024-11-05 09:59:08 -08:00
device_grouped_conv_fwd_dl_nhwc_kyxc_nhwk.hpp
Add Grouped Conv Fwd Large Tensor kernel (#1432)
2024-08-06 10:06:10 +02:00
device_grouped_conv_fwd_multiple_abd_xdl_cshuffle_v3.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_conv_fwd_multiple_abd_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_conv_fwd_multiple_d_multiple_r_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_conv_fwd_multiple_d_multiple_r.hpp
…
device_grouped_conv_fwd_multiple_d_wmma_cshuffle.hpp
Add Grouped Conv Fwd Large Tensor kernel (#1432)
2024-08-06 10:06:10 +02:00
device_grouped_conv_fwd_multiple_d_xdl_cshuffle.hpp
…
device_grouped_conv_fwd_multiple_d_xdl_large_tensor_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_conv_utils.hpp
Add support for NGCHW in grouped conv fwd (#1499)
2024-09-20 10:45:46 +02:00
device_grouped_gemm_multi_abd_xdl_fixed_nk.hpp
Fix grouped gemm check to avoid overflow (#1545)
2024-10-04 17:32:43 +02:00
device_grouped_gemm_multiple_d_dl.hpp
LWPCK-2429: Device grouped GEMM uses Async Memcpy (#1695)
2024-12-02 09:13:56 +01:00
device_grouped_gemm_multiple_d_splitk_xdl_cshuffle_two_stage.hpp
LWPCK-2429: Device grouped GEMM uses Async Memcpy (#1695)
2024-12-02 09:13:56 +01:00
device_grouped_gemm_multiple_d_xdl_cshuffle_tile_loop.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_gemm_softmax_gemm_permute_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_gemm_xdl_fixed_nk.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_gemm_xdl_splitk_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_gemm_xdl.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00
device_grouped_query_attention_forward_wmma.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_image_to_column_impl.hpp
Codegen hipRTC compilation (#1579)
2025-01-31 09:48:39 -08:00
device_max_pool_bwd_impl.hpp
…
device_multi_query_attention_forward_wmma.hpp
Merging the gfx12 code into public repo. (#1362)
2024-06-27 00:33:34 -07:00
device_multiple_reduce_multiblock.hpp
…
device_multiple_reduce_threadwise.hpp
…
device_normalization_bwd_data_impl.hpp
…
device_normalization_bwd_gamma_beta_impl.hpp
…
device_normalization_fwd_impl.hpp
…
device_normalization_fwd_splitk_impl.hpp
…
device_permute_impl.hpp
…
device_pool2d_fwd_nhwc_nhwc.hpp
Rewrite pool2d fwd (#1462)
2024-09-11 15:21:00 +02:00
device_pool3d_fwd_ndhwc_ndhwc.hpp
…
device_put_element_impl.hpp
…
device_reduce_common.hpp
Support large: 12d tensor size for reduction kenrel (#1465)
2024-08-13 16:15:47 +02:00
device_reduce_multiblock.hpp
Support large: 12d tensor size for reduction kenrel (#1465)
2024-08-13 16:15:47 +02:00
device_reduce_threadwise_multi_d.hpp
Support large: 12d tensor size for reduction kenrel (#1465)
2024-08-13 16:15:47 +02:00
device_reduce_threadwise.hpp
Support large: 12d tensor size for reduction kenrel (#1465)
2024-08-13 16:15:47 +02:00
device_softmax_impl.hpp
…
device_sparse_embeddings_forward_layernorm.hpp
…
device_splitk_contraction_multiple_d_xdl_cshuffle.hpp
Merge from internal (#1857)
2025-02-07 15:05:05 -07:00