ROCm/composable_kernel
1
0
Fork 0
mirror of https://github.com/ROCm/composable_kernel.git synced 2026-05-16 02:54:21 +00:00
Code Issues Packages Projects Releases Wiki Activity
443 Commits 745 Branches 38 Tags
0dc65eae461da2cf191c7605d599f2c21c4a5a1e
Commit Graph

443 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Chao Liu
0dc65eae46 Misc fixes (#24) 
* use cast_pointer_to_generic_address_space() in v6r1 kernel wrapper, DynamcBuffer and buffer_load take customized invalid-element-value, add buffer_load/store for fp64

* use remove_cvref_t

[ROCm/composable_kernel commit: 10bb811060]
 2021-08-26 20:05:19 -05:00
zjing14
346651889b GlobalAtomicAdd for fp32/int32 (#23) 
* add f32/i32 atomicAdd support into dynamicBuffer, and enable it in v1r3

* fixed

* fixed

* update comment

Co-authored-by: Chao Liu <chao.liu2@amd.com>

[ROCm/composable_kernel commit: a7a758d8ce]
 2021-08-25 10:55:55 -05:00
zjing14
6d56ee7d00 Xdlops refactor fix (#22) 
* added constexpr ahead of adptor; clean unused driver; rename M/NPerWave to M/NPerXDL

* fixed bwd

* fixed comment

[ROCm/composable_kernel commit: 9d3f634a3c]
 2021-08-23 11:22:10 -05:00
Chao Liu
818e5cbfe7 magic division use __umulhi() (#19) 
[ROCm/composable_kernel commit: c6f26bb480]
 2021-08-23 10:40:27 -05:00
zjing14
3cacb0c037 refactor dynamic xdlops iGemm (#13) 
* xdlops refactor

* fixed commnt

* clean xdlops_gemm

* add make c into xldops-gemm

* change mfma_info

* refactor xdlops, hide c desc

* clean

* clean

* clean

* apply hacks changes to v4r4r4_nhwc

* rename hacks and use single stage adapter

* enable fp16 mfma

[ROCm/composable_kernel commit: a2ad6d3531]
 2021-08-19 09:54:10 -05:00
zjing14
13dab08075 Added host_conv_wrw for verification (#15) 
* added host conv wrw

[ROCm/composable_kernel commit: ba6f79a75e]
 2021-08-19 01:00:41 -05:00
Chao Liu
dd3e30e224 Merge pull request #14 from ROCmSoftwarePlatform/miopen_downstream_init_integration 
MIOpen Downstream: Initial integration 2nd PR

[ROCm/composable_kernel commit: b62bf8c3f8]
 2021-08-16 16:39:40 -05:00
Chao Liu
a364868bcf Merge pull request #8 from ROCmSoftwarePlatform/miopen_downstream_init_integration 
[ROCm/composable_kernel commit: ccc4a1d365]
 2021-08-16 16:28:53 -05:00
Chao Liu
bf335705ef refactor 
[ROCm/composable_kernel commit: 67ad47e7c1]
 2021-08-16 21:01:33 +00:00
Chao Liu
04d90a65c5 refactor 
[ROCm/composable_kernel commit: 16effa767c]
 2021-08-16 20:36:47 +00:00
Chao Liu
a222af4530 DynamicBuffer, StaticBuffer, amd_buffer_load support customized value for invalid element 
[ROCm/composable_kernel commit: a91b68dfcb]
 2021-08-13 23:40:19 +00:00
Chao Liu
e145aa0e29 use int instead of index_t in kernel wrapper 
[ROCm/composable_kernel commit: 2cbabbba54]
 2021-08-13 20:55:39 +00:00
Chao Liu
d49b0e5239 compiler parameter use stream 
[ROCm/composable_kernel commit: 0834bc7635]
 2021-08-13 01:05:14 +00:00
Chao Liu
c5ea28dc43 make innner product compatiable on gfx900 
[ROCm/composable_kernel commit: f2ac7832c6]
 2021-08-11 09:42:53 -05:00
Chao Liu
0bbcd05e4e rename 
[ROCm/composable_kernel commit: 4e57b30a6a]
 2021-08-11 00:08:42 +00:00
Chao Liu
c5a4edb9e8 rename 
[ROCm/composable_kernel commit: c03045ce2d]
 2021-08-10 23:45:36 +00:00
Chao Liu
400efa2b88 update CK build script 
[ROCm/composable_kernel commit: b2589957f3]
 2021-08-10 22:19:13 +00:00
Chao Liu
a0df0eb029 fix kernel filename 
[ROCm/composable_kernel commit: 2c48039d0e]
 2021-08-10 22:15:23 +00:00
Chao Liu
7d53faec4e fix enum issue 
[ROCm/composable_kernel commit: d626dccc95]
 2021-08-10 20:55:13 +00:00
Chao Liu
2e7587d6db tidy 
[ROCm/composable_kernel commit: 643ebd4f3e]
 2021-08-10 07:07:11 +00:00
Chao Liu
a15f7c025f fix clang warning suppression 
[ROCm/composable_kernel commit: ddd49ec9e7]
 2021-08-10 06:20:24 +00:00
Chao Liu
ab465fca4c vector/scalar pointer cast use c-style pointer cast instead of reinterpret_cast 
[ROCm/composable_kernel commit: 4f566c6221]
 2021-08-10 05:55:20 +00:00
Chao Liu
17b084ce2c add c-style pointer cast 
[ROCm/composable_kernel commit: 172036d728]
 2021-08-10 00:01:52 -05:00
Chao Liu
72c6d11a3b tidy 
[ROCm/composable_kernel commit: 76f3131939]
 2021-08-09 18:49:59 -05:00
Chao Liu
7b306ba01c tidy 
[ROCm/composable_kernel commit: d18428901e]
 2021-08-09 18:20:02 -05:00
Chao Liu
eb778cb91b tidy 
[ROCm/composable_kernel commit: f885c131d8]
 2021-08-09 22:13:47 +00:00
Chao Liu
922b72948d tidy 
[ROCm/composable_kernel commit: 80120f0a0c]
 2021-08-09 21:10:09 +00:00
Chao Liu
a913d48b07 tidy 
[ROCm/composable_kernel commit: c3efeb5e20]
 2021-08-09 19:32:07 +00:00
Chao Liu
590dde14c8 tidy 
[ROCm/composable_kernel commit: 56fc0842b3]
 2021-08-09 19:27:49 +00:00
Chao Liu
7885261dc6 tidy 
[ROCm/composable_kernel commit: 54fba515b3]
 2021-08-09 17:33:32 +00:00
Chao Liu
193f7cbbcf tidy 
[ROCm/composable_kernel commit: e62bae7a4a]
 2021-08-09 15:11:35 +00:00
Chao Liu
71a28fc501 add tidy 
[ROCm/composable_kernel commit: 24c8728942]
 2021-08-08 17:41:54 +00:00
Chao Liu
c2922caeb1 fix 
[ROCm/composable_kernel commit: 61487e0a00]
 2021-08-07 02:31:19 +00:00
Chao Liu
b0ab2054a9 remove online compilation from CK 
[ROCm/composable_kernel commit: ae98b52ad8]
 2021-08-07 00:51:05 +00:00
Chao Liu
23239fa618 refactor 
[ROCm/composable_kernel commit: cb95421311]
 2021-08-06 22:17:51 +00:00
Chao Liu
3bbe4dae99 Merge commit '437cc595c6e206dfebb118985b5171bbc1e29eab' into composable_kernel_init_integration_v3 
[ROCm/composable_kernel commit: 73ca970155]
 2021-08-06 21:32:27 +00:00
Chao Liu
51d5010798 Merge pull request #7 from ROCmSoftwarePlatform/master 
Master

[ROCm/composable_kernel commit: 3b86646115]
 2021-08-06 16:29:58 -05:00
Chao Liu
98d5803d26 Update develop (#5) 
* refactor

[ROCm/composable_kernel commit: d09ea4f4e5]
 2021-08-06 16:11:15 -05:00
Chao Liu
37a9932cfc refactor 
[ROCm/composable_kernel commit: 7b1ec41e5b]
 2021-08-06 20:50:01 +00:00
Chao Liu
101d8ecf21 refactor 
[ROCm/composable_kernel commit: 49c33aaea7]
 2021-08-06 19:59:53 +00:00
Chao Liu
53e5d36013 rename 
[ROCm/composable_kernel commit: 54b3e73d17]
 2021-08-06 18:07:15 +00:00
Chao Liu
55cdfe9695 add solver ConvIgemmFwdV6r1DlopsNchwKcyxNkhw; rename static ck source files 
[ROCm/composable_kernel commit: 3d32ae9404]
 2021-07-30 17:50:17 -05:00
Chao Liu
67d45b2ee6 update to clang-format-10 
[ROCm/composable_kernel commit: 82fae390fb]
 2021-07-30 16:37:00 -05:00
Chao Liu
ce7d015e51 Merge pull request #2 from asroy/master 
Update readme

[ROCm/composable_kernel commit: bd27ed6c38]
 2021-07-28 09:43:56 -05:00
Chao Liu
1b8b55fc61 Update README.md 
[ROCm/composable_kernel commit: 85a1429301]
 2021-07-28 09:41:38 -05:00
Chao Liu
18bec192f5 Update README.md 
[ROCm/composable_kernel commit: 56f93c6f33]
 2021-07-28 09:40:44 -05:00
Chao Liu
3bcdb7879d fix building 
[ROCm/composable_kernel commit: 6a1bc5939c]
 2021-07-27 13:12:43 -05:00
Chao Liu
e02d6a0f21 [MIOpen Downstream] Initial MIOpen integration (#52) 
* update online kernel wrapper bundle all descriptors in a tuple

* change __CONSTANT__ to CONSTANT

* rename

* adding tuning

* added IsValidCompileParameter

* reorginze

* adding tunable for fp16 and int8

* fix kernel compile warning and bug fixes

* suppress warning about cast CONSTANT (address space 4) pointer

* fix building issue

[ROCm/composable_kernel commit: f63a23acb1]
 2021-07-27 00:02:27 -05:00
Chao Liu
f94e566273 reorganize files to prepare for MIOpen integration (#51) 
* change olc cmake

* adding online compile to fwd-v4r5r2

* update scripts

* remane fwd-v4r5r2 to fwd-v6r1

* clean up

[ROCm/composable_kernel commit: 1264925422]
 2021-07-18 00:43:05 -05:00
zjing14
440e2126bb Add xdlops v4r4r4 into online compilation (#48) 
* init for v4r4 xdlops olc

* refactor wrap

* init impl of v4r4 nchw xdlops olc

* tuning

* test perf

* fixed v4r4 nhwc

* tuned v4r4 nhwc

* use gridwise_gemm_xdlops_v2r3

* swap a/b

* add pointer support into offline v2r3

* debugging v4r4r4 transform for olc

* change timer of olc

* refactor v4r4 xdlops nchw olc

* remove transform fun in v4r4 xdlops nhwc olc

Co-authored-by: Chao Liu <chao.liu2@amd.com>

[ROCm/composable_kernel commit: fbdf4332c7]
 2021-07-16 23:27:08 -05:00