Haocong WANG d6de9bdcbe [Navi3x] Add Device Operations (#567) ...

* wmma_op + unit test

* add arch limitation to wmma test

* change arch limitation

* Refactor + Add all type unit test(int4 compile failed)

* Add f32_16x16x16_bf16 unit test

* tempsave

* tempsave

* tempsave

* runtime bug, cannot find symbol

* workaround for incorrect HIP warpSize return value

* debugging

* tempsave

* Correctness OK, waiting for optimization

* Tidy up + format

* temp save

* temp save, reproduce the v_bfi_b32 issue

* add inline asm for wmmaop test

* tidy up

* clean some debug purpose code

* discard some codes

* clang format

* clang format

* compiler issue fixed + increase tile size

* navi3x_multipleD+example

* temp save

* workable

* batchedgemm[OK], groupconv[debug]

* groupconv: Sanity check[OK], Performance[Bad]

* navi3x_groupconv_need_optimization

* format

* Add arch limitation to all wmma examples

* fix bug: example30 input conv args

[ROCm/composable_kernel commit: 0cfda84d05]

2023-02-15 11:50:51 -06:00

..

device_batched_contraction_multiple_d_wmma_cshuffle.hpp

[Navi3x] Add Device Operations (#567)

2023-02-15 11:50:51 -06:00

device_batched_contraction_multiple_d_xdl_cshuffle.hpp

Input/output permutation for fused attention (#460)

2022-10-27 14:58:20 -06:00

device_batched_gemm_e_permute_xdl.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_batched_gemm_gemm_xdl_cshuffle.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_batched_gemm_multi_d_xdl.hpp

fix GetTypeString

2022-11-29 14:18:10 +08:00

device_batched_gemm_multiple_d_gemm_multiple_d_xdl_cshuffle.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_batched_gemm_reduce_xdl_cshuffle.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_batched_gemm_softmax_gemm_permute_xdl_cshuffle.hpp

Add GemmAddSoftmaxGemm support for MSFT ORT (instances and client API) (#576)

2023-02-08 14:34:45 -06:00

device_batched_gemm_softmax_gemm_xdl_cshuffle.hpp

Input/output permutation for fused attention (#460)

2022-10-27 14:58:20 -06:00

device_batched_gemm_xdl.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_batchnorm_backward_impl.hpp

BatchNorm backward instance/external API/profiler/tests (#519)

2022-11-30 13:32:20 -06:00

device_batchnorm_forward_impl.hpp

BatchNorm forward instance/external api/profiler/tests/client example (#511)

2022-11-24 18:02:27 -06:00

device_cgemm_4gemm_xdl_cshuffle.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_contraction_multiple_d_xdl_cshuffle.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_conv2d_backward_weight_xdl_c_shuffle_nhwc_kyxc_nhwk.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_conv2d_bwd_data_xdl_nhwc_kyxc_nhwk.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_conv2d_fwd_xdl_c_shuffle_bias_activation_add_nhwc_kyxc_nhwk.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_conv2d_fwd_xdl_c_shuffle_bias_activation_nhwc_kyxc_nhwk.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_conv2d_fwd_xdl_c_shuffle_nhwc_kyxc_nhwk.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_conv2d_fwd_xdl_nhwc_kyxc_nhwk.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_conv3d_fwd_naive_ndhwc_kzyxc_ndhwk.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_conv3d_fwd_xdl_ndhwc_kzyxc_ndhwk.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_convnd_bwd_data_nwc_kxc_nwk_dl.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_convnd_bwd_data_nwc_kxc_nwk_xdl.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_elementwise_2d_impl.hpp

Batchnorm inference instances, external API, client examples and gtests (#531)

2023-01-25 17:09:04 -06:00

device_elementwise_impl.hpp

Batchnorm inference instances, external API, client examples and gtests (#531)

2023-01-25 17:09:04 -06:00

device_elementwise_normalization_impl.hpp

Add instance for elementwise normlization (#573)

2023-02-09 09:37:29 -08:00

device_gemm_bias_add_reduce_xdl_cshuffle.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_gemm_bias_e_permute_xdl.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_gemm_dl.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_gemm_multiple_d_dl.hpp

Add multiD Gemm client APIs (#534)

2023-01-18 11:53:56 -06:00

device_gemm_multiple_d_layernorm_xdl_cshuffle.hpp

Gemm+layernorm instance, ckProfiler, client example (#568)

2023-02-09 15:02:55 -06:00

device_gemm_multiple_d_multiple_r_xdl_cshuffle.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_gemm_multiple_d_wmma_cshuffle.hpp

[Navi3x] Add Device Operations (#567)

2023-02-15 11:50:51 -06:00

device_gemm_multiple_d_xdl_cshuffle.hpp

Wavelet (inter-wave consumer-producer) GEMM (#310)

2023-01-18 12:00:02 -06:00

device_gemm_reduce_xdl_cshuffle.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_gemm_wmma.hpp

[Navi3x-LWPCK-545] Block-wise GEMM + Real GEMM_WMMA_FP16 (#541)

2023-01-16 20:06:01 -06:00

device_gemm_xdl_cshuffle.hpp

Wavelet (inter-wave consumer-producer) GEMM (#310)

2023-01-18 12:00:02 -06:00

device_gemm_xdl_layernorm_cshuffle.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_gemm_xdl_skip_b_lds.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_gemm_xdl_splitk_c_shuffle.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_gemm_xdl.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_grouped_contraction_multiple_d_xdl_cshuffle.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_grouped_conv_bwd_data_multiple_d_xdl_cshuffle_v1.hpp

fix build (#427)

2022-09-20 14:56:33 -05:00

device_grouped_conv_bwd_weight_gnwc_gkxc_gnwk_xdl_cshuffle.hpp

Avoid reporting unused member function error (#507)

2022-11-14 19:54:37 -06:00

device_grouped_conv_fwd_multiple_d_multiple_r_xdl_cshuffle.hpp

Introduce ck::accumulate_n() (#439)

2022-11-14 19:53:39 -06:00

device_grouped_conv_fwd_multiple_d_multiple_r.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_grouped_conv_fwd_multiple_d_wmma_cshuffle.hpp

[Navi3x] Add Device Operations (#567)

2023-02-15 11:50:51 -06:00

device_grouped_conv_fwd_multiple_d_xdl_cshuffle.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_grouped_gemm_xdl.hpp

Add a flag to enable/disable debug output in many kernels. (#549)

2023-01-11 19:55:56 -06:00

device_multiple_reduce_multiblock.hpp

Use double for all scaling values and float-point constant values at the Device Op API (#557)

2023-01-18 12:02:50 -06:00

device_multiple_reduce_threadwise.hpp

Use double for all scaling values and float-point constant values at the Device Op API (#557)

2023-01-18 12:02:50 -06:00

device_normalization_impl.hpp

Use double for all scaling values and float-point constant values at the Device Op API (#557)

2023-01-18 12:02:50 -06:00

device_permute_impl.hpp

Add 'Permute' device op & example (#408)

2022-09-19 21:30:25 -05:00

device_pool2d_fwd_nhwc_nhwc.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_reduce_common.hpp

Refactor device op implementations into impl subdirectory. (#420)

2022-10-13 09:05:08 -05:00

device_reduce_multiblock.hpp

Use double for all scaling values and float-point constant values at the Device Op API (#557)

2023-01-18 12:02:50 -06:00

device_reduce_threadwise.hpp

Use double for all scaling values and float-point constant values at the Device Op API (#557)

2023-01-18 12:02:50 -06:00

device_softmax_impl.hpp

Use double for all scaling values and float-point constant values at the Device Op API (#557)

2023-01-18 12:02:50 -06:00

device_sparse_embeddings_forward_layernorm.hpp

add multi embeddings support (#542)

2023-01-18 11:32:12 -06:00