rtmadduri 529dfe7c93 LWPCK-2429: Device grouped GEMM uses Async Memcpy (#1695) ...

* LWPCK-2429: Device grouped GEMM uses Async Memcpy
Resolving merge conflicts

* reverting changes to profile_grouped_gemm

* revert date change

---------

Co-authored-by: Illia Silin <98187287+illsilin@users.noreply.github.com>

[ROCm/composable_kernel commit: 9488f1c981]

2024-12-02 09:13:56 +01:00

..

impl

LWPCK-2429: Device grouped GEMM uses Async Memcpy (#1695)

2024-12-02 09:13:56 +01:00

conv_tensor_rearrange_op.hpp

…

convolution_backward_data_specialization.hpp

…

convolution_backward_weight_specialization.hpp

…

convolution_forward_specialization.hpp

Support access per groups and filter3x3 in grouped conv fwd (#1382)

2024-07-12 11:08:42 -07:00

device_avgpool_bwd.hpp

…

device_base.hpp

Fixed GroupedGemmFixedNK with hipGraph (#1065)

2023-11-30 15:09:27 -06:00

device_batched_contraction_multiple_d.hpp

…

device_batched_gemm_e_permute.hpp

…

device_batched_gemm_gemm.hpp

…

device_batched_gemm_multi_d.hpp

Batched GEMM Multiple D based on Universal GEMM (#1655)

2024-11-18 14:03:45 +01:00

device_batched_gemm_multiple_d_gemm_multiple_d.hpp

…

device_batched_gemm_softmax_gemm_permute.hpp

…

device_batched_gemm_softmax_gemm.hpp

…

device_batched_gemm.hpp

…

device_batchnorm_backward.hpp

…

device_batchnorm_forward.hpp

…

device_batchnorm_infer.hpp

…

device_cgemm.hpp

Implement GetWorkSpaceSize from BaseOperator. (#1564)

2024-10-12 14:05:11 +08:00

device_contraction_multiple_abd.hpp

Add contraction_multi_abd (#972)

2023-10-17 20:17:58 -05:00

device_contraction_multiple_d.hpp

Add support for mixed precision in contraction scale and bilinear (#973)

2023-11-02 14:26:33 -07:00

device_conv_bwd_data.hpp

…

device_conv_fwd_bias_activation_add.hpp

…

device_conv_fwd_bias_activation.hpp

…

device_conv_fwd.hpp

…

device_conv_tensor_rearrange.hpp

Add support for groups in Img2Col/Col2Img (#1007)

2023-10-31 10:46:32 +01:00

device_elementwise_normalization.hpp

…

device_elementwise_scale.hpp

Refactor elementwise kernels (#1222)

2024-04-19 13:31:17 +02:00

device_elementwise.hpp

…

device_gemm_bias_e_permute.hpp

…

device_gemm_dequantB.hpp

Navi3 rel (#1176)

2024-03-08 17:11:51 -08:00

device_gemm_multiple_abd.hpp

…

device_gemm_multiple_d_ab_scale.hpp

[GEMM] F8 GEMM, performance optimized. (#1384)

2024-07-19 22:06:52 +08:00

device_gemm_multiple_d_layernorm.hpp

…

device_gemm_multiple_d_multiple_r.hpp

…

device_gemm_multiple_d.hpp

[GEMM] gemm_universal related optimization (#1453)

2024-08-14 10:42:30 +08:00

device_gemm_reduce.hpp

…

device_gemm_splitk.hpp

…

device_gemm_streamk_v2.hpp

Universal streamk with atomics (#1360)

2024-07-05 21:40:30 -07:00

device_gemm_streamk.hpp

…

device_gemm_v2.hpp

Universal gemm splitk using reduce (with multi-d) (#1341)

2024-07-19 22:01:22 +08:00

device_gemm.hpp

…

device_grouped_contraction_multiple_d.hpp

…

device_grouped_conv_bwd_data_multiple_d.hpp

…

device_grouped_conv_bwd_weight_multiple_d.hpp

Add grouped conv bwd weight multi d kernel (#1237)

2024-04-18 23:35:04 +02:00

device_grouped_conv_bwd_weight.hpp

…

device_grouped_conv_fwd_multiple_abd.hpp

Add Grouped Conv Fwd Large Tensor kernel (#1432)

2024-08-06 10:06:10 +02:00

device_grouped_conv_fwd_multiple_d.hpp

Introduce multiABD api and deprecate multiD (#1035)

2023-11-14 17:00:40 +01:00

device_grouped_conv_fwd.hpp

…

device_grouped_gemm_fixed_nk.hpp

Polished Grouped GEMM APIs and new BF16 instances (#1600)

2024-11-27 13:02:44 +01:00

device_grouped_gemm_multi_abd_fixed_nk.hpp

Added Multi_ABD support into Gemm and GroupedGemmFixedNK (#978)

2024-04-15 21:09:45 -05:00

device_grouped_gemm_multi_abd.hpp

Added Multi_ABD support into Gemm and GroupedGemmFixedNK (#978)

2024-04-15 21:09:45 -05:00

device_grouped_gemm_softmax_gemm_permute.hpp

…

device_grouped_gemm_splitk.hpp

Polished Grouped GEMM APIs and new BF16 instances (#1600)

2024-11-27 13:02:44 +01:00

device_grouped_gemm_tile_loop.hpp

Polished Grouped GEMM APIs and new BF16 instances (#1600)

2024-11-27 13:02:44 +01:00

device_grouped_gemm.hpp

Polished Grouped GEMM APIs and new BF16 instances (#1600)

2024-11-27 13:02:44 +01:00

device_max_pool_bwd.hpp

…

device_multiple_reduce.hpp

…

device_normalization_bwd_data.hpp

layernorm and groupnorm backward data (#1083)

2023-12-19 04:23:11 +08:00

device_normalization_bwd_gamma_beta.hpp

Backward of gamma and beta for layernorm and groupnorm (#1013)

2023-11-10 18:02:03 +08:00

device_normalization_fwd.hpp

Layernorm4d (#1022)

2023-11-09 08:34:51 +08:00

device_permute.hpp

…

device_pool_fwd.hpp

…

device_put_element.hpp

…

device_reduce_multi_d.hpp

Universal gemm splitk using reduce (with multi-d) (#1341)

2024-07-19 22:01:22 +08:00

device_reduce.hpp

…

device_softmax.hpp

…

device_splitk_contraction_multiple_d.hpp

…

gemm_specialization.hpp

…

helper.hpp

Refactor transform conv to gemm fwd (#1391)

2024-07-19 09:29:25 +02:00

masking_specialization.hpp

Navi3 rel (#1176)

2024-03-08 17:11:51 -08:00

matrix_padder.hpp

CK Instance Gen (#1145)

2024-06-25 16:37:35 -05:00

reduction_operator_mapping.hpp

…

tensor_layout.hpp

Add support for NGCHW in grouped conv bwd wei (#1491)

2024-09-03 10:52:03 +02:00

tensor_specialization.hpp

…

welford_helper.hpp

…