ROCm/composable_kernel
1
0
Fork 0
mirror of https://github.com/ROCm/composable_kernel.git synced 2026-05-18 12:00:07 +00:00
Code Issues Packages Projects Releases Wiki Activity
Files
9bdae6116c5c6bc3f00206448d08abbb9b9a5d3c
composable_kernel/include/ck/tensor_operation/gpu/device/impl
History
Bartłomiej Kocot b4b436d29a Optimize grouped conv bwd weight for small M and N (#1303) 
* Optimize grouped conv bwd weight for small M and N

* Fixes

[ROCm/composable_kernel commit: fd72380aeb]
2024-05-22 21:01:01 +02:00
..
device_avgpool3d_bwd_ndhwc_ndhwc.hpp
…
device_batched_contraction_multiple_d_wmma_cshuffle.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_batched_contraction_multiple_d_xdl_cshuffle.hpp
…
device_batched_gemm_e_permute_xdl.hpp
…
device_batched_gemm_gemm_xdl_cshuffle.hpp
…
device_batched_gemm_multi_d_xdl.hpp
…
device_batched_gemm_multiple_d_dl.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_batched_gemm_multiple_d_gemm_multiple_d_xdl_cshuffle.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_batched_gemm_reduce_xdl_cshuffle.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_batched_gemm_softmax_gemm_permute_wmma_cshuffle.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_batched_gemm_softmax_gemm_permute_xdl_cshuffle.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_batched_gemm_softmax_gemm_xdl_cshuffle.hpp
…
device_batched_gemm_xdl.hpp
…
device_batchnorm_backward_impl.hpp
…
device_batchnorm_forward_impl_obsolete.hpp
…
device_batchnorm_forward_impl.hpp
…
device_cgemm_4gemm_xdl_cshuffle.hpp
…
device_column_to_image_impl.hpp
…
device_contraction_multiple_abd_xdl_cshuffle.hpp
…
device_contraction_multiple_d_xdl_cshuffle.hpp
aggregate device macros in ck_tile config header (#1297)
2024-05-20 08:34:45 -07:00
device_contraction_utils.hpp
…
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
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_convnd_bwd_data_nwc_kxc_nwk_dl.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -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
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_gemm_bias_add_reduce_xdl_cshuffle.hpp
…
device_gemm_dl.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -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
…
device_gemm_multiple_d_dl.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_gemm_multiple_d_layernorm_xdl_cshuffle.hpp
…
device_gemm_multiple_d_multiple_r_xdl_cshuffle.hpp
…
device_gemm_multiple_d_wmma_cshuffle.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_gemm_multiple_d_xdl_cshuffle_lds_direct_load.hpp
…
device_gemm_multiple_d_xdl_cshuffle.hpp
…
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
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_gemm_xdl_cshuffle_lds_direct_load.hpp
…
device_gemm_xdl_cshuffle_v2.hpp
…
device_gemm_xdl_cshuffle_v3.hpp
[GEMM] UniversalGemm update (#1262)
2024-04-26 12:56:07 -05: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
…
device_gemm_xdl_splitk_c_shuffle.hpp
…
device_gemm_xdl_streamk.hpp
…
device_gemm_xdl_waveletmodel_cshuffle.hpp
…
device_gemm_xdl.hpp
…
device_grouped_contraction_multiple_d_xdl_cshuffle.hpp
…
device_grouped_conv_bwd_data_multiple_d_wmma_cshuffle.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_grouped_conv_bwd_data_multiple_d_xdl_cshuffle_v1.hpp
…
device_grouped_conv_bwd_weight_dl.hpp
…
device_grouped_conv_bwd_weight_multiple_d_xdl_cshuffle.hpp
Change output gemm type to AccDataType in two stage conv bwd wei (#1283)
2024-05-10 10:57:42 +02:00
device_grouped_conv_bwd_weight_two_stage_xdl_cshuffle.hpp
Optimize grouped conv bwd weight for small M and N (#1303)
2024-05-22 21:01:01 +02:00
device_grouped_conv_bwd_weight_wmma_cshuffle.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_grouped_conv_bwd_weight_xdl_cshuffle.hpp
…
device_grouped_conv_fwd_dl_multiple_d_nhwc_kyxc_nhwk.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_grouped_conv_fwd_dl_nhwc_kyxc_nhwk.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_grouped_conv_fwd_multiple_abd_xdl_cshuffle.hpp
…
device_grouped_conv_fwd_multiple_d_multiple_r_xdl_cshuffle.hpp
…
device_grouped_conv_fwd_multiple_d_multiple_r.hpp
…
device_grouped_conv_fwd_multiple_d_wmma_cshuffle.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_grouped_conv_fwd_multiple_d_xdl_cshuffle.hpp
…
device_grouped_conv_utils.hpp
…
device_grouped_gemm_multi_abd_xdl_fixed_nk.hpp
aggregate device macros in ck_tile config header (#1297)
2024-05-20 08:34:45 -07:00
device_grouped_gemm_multiple_d_dl.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_grouped_gemm_multiple_d_splitk_xdl_cshuffle_two_stage.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_grouped_gemm_multiple_d_xdl_cshuffle_tile_loop.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_grouped_gemm_softmax_gemm_permute_xdl_cshuffle.hpp
…
device_grouped_gemm_xdl_fixed_nk.hpp
…
device_grouped_gemm_xdl_splitk_cshuffle.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_grouped_gemm_xdl.hpp
replace the ENV macro with CK_ENV (#1296)
2024-05-17 10:42:51 -07:00
device_grouped_query_attention_forward_wmma.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -07:00
device_image_to_column_impl.hpp
…
device_max_pool_bwd_impl.hpp
…
device_multi_query_attention_forward_wmma.hpp
Code clean-up (#1285)
2024-05-10 09:41:39 -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
…
device_pool3d_fwd_ndhwc_ndhwc.hpp
…
device_put_element_impl.hpp
…
device_reduce_common.hpp
…
device_reduce_multiblock.hpp
…
device_reduce_threadwise.hpp
…
device_softmax_impl.hpp
…
device_sparse_embeddings_forward_layernorm.hpp
…
device_splitk_contraction_multiple_d_xdl_cshuffle.hpp
…