Wenkai Du
00f421ccbd
Add topology explorer
...
[ROCm/rccl commit: 55f8e2dec7 ]
2020-02-19 14:42:06 -08:00
Stanley Tsang
e5419407c4
Updating copyright notices for 2020.
...
[ROCm/rccl commit: 20fa04d9b6 ]
2020-01-29 15:28:08 -08:00
Wenkai Du
e6b5933d7e
Merge remote-tracking branch 'remotes/rccl/master' into rccl_2.5.6_cleanup
...
[ROCm/rccl commit: fe6d012eb0 ]
2020-01-29 15:28:03 -08:00
Wenkai Du
d2fbcfea02
Misc fixes and improvements for 2.5.6
...
1. Fix RCCL unit test
2. Add ROME detection and tuning
3. Change default P2P level
4. Fix search algorithm for XGMI
5. Remove explicit channel duplication with implicit by using half of link speed
6. Add collective trace support
7. Correct Intel Skylake CPU detection and bandwidth
8. Fix topo connect function
9. Disable GDR read and remove unreachable code
10. Disable LL128 kernels
11. Add tuning parameters
12. Use original clock64() implementation which returns RTC counter value
13. Print out timestamp of collective trace
14. Do not use struct ncclColl in kernel launch parameter
15. Fix abort handling and add tracing
17. Add __launch_bounds__ to kernel functions
18. Remove unused abortCount
19. Unset default MIN_NRINGS and MIN_NCHANNELS
20. Do not allocate shared memory when not using LL128 kernels
21. Correct time print out in tuning log
[ROCm/rccl commit: 1e55645d97 ]
2020-01-29 15:27:05 -08:00
Gilbert Lee
5783917a75
Changing single sync mode to time all iterations instead of just last
...
[ROCm/rccl commit: e5074ce94d ]
2019-12-20 17:08:39 -08:00
gilbertlee-amd
a461b6d139
Adding new sleep after sync capability for data fabric profiling ( #162 )
...
Fixing missing header include for ROCM 3.0 changes
[ROCm/rccl commit: 2f4269d06d ]
2019-12-12 15:20:54 -07:00
Wenkai Du
25b3175e82
rccl_prim_test: Generalize ring topology and duplications
...
Allow user specified ring topology from command line and duplicated
to requested number of workgroups:
./rccl_prim_test -w 12 -p copy -r "0 1 2 3|3 2 1 0|0 2 1 3|3 1 2 0|0 2 3 1|1 3 2 0"
[ROCm/rccl commit: 07bb6fce8f ]
2019-11-11 15:42:24 -08:00
Wenkai Du
66e4337c6e
Merge pull request #149 from wenkaidu/rtc
...
Correct RTC frequencies for profiling purpose
[ROCm/rccl commit: 277c72a638 ]
2019-11-06 08:02:58 -08:00
gilbertlee-amd
22cbbb9004
Adding interactive mode for profiling purposes ( #150 )
...
[ROCm/rccl commit: fd94f4fa25 ]
2019-11-05 17:10:16 -07:00
Wenkai Du
62042e47bc
Correct RTC frequencies for profiling purpose
...
[ROCm/rccl commit: 8995047830 ]
2019-11-05 11:36:45 -08:00
Wenkai Du
0d6b476b08
Merge pull request #145 from wenkaidu/prim_test
...
rccl-prim-test: use hipExtLaunchMultiKernelMultiDevice and minor cleanup
[ROCm/rccl commit: 90b2921207 ]
2019-11-01 13:30:01 -07:00
gilbertlee-amd
f9ef1553aa
Single Sync Timing mode ( #144 )
...
* Adding single sync timing mode to emulate timing reported by rccl-prim-test / rccl-tests
* Adding duration / overhead info
[ROCm/rccl commit: 2f9edd2432 ]
2019-11-01 10:18:25 -06:00
Wenkai Du
91b906cf88
rccl-prim-test: use hipExtLaunchMultiKernelMultiDevice and minor cleanup
...
[ROCm/rccl commit: ab91cdd5c9 ]
2019-10-30 13:15:02 -07:00
Gilbert Lee
a99accb2cb
Adding ability to switch between fine/coarse grain destination GPU memory
...
Adding ability to switch between memset/memcpy
[ROCm/rccl commit: 648c1ee7cc ]
2019-10-29 12:00:32 -06:00
rohit pathania
31670133a1
Read operation throughput
...
[ROCm/rccl commit: a270ee080e ]
2019-09-03 14:58:40 +05:30
rohit pathania
bc51b5bc28
display each workgroup ,links and directions with throughputs
...
[ROCm/rccl commit: e5b13d69e5 ]
2019-08-30 13:28:23 +05:30
rpathani
c441f2ff9b
Update rccl_prim_test.cpp
...
[ROCm/rccl commit: 40e30b5168 ]
2019-08-19 12:44:11 +05:30
rpathani
eaa1cdb48c
Merge branch 'master' into xgmi_bench
...
[ROCm/rccl commit: deea20d49c ]
2019-08-16 10:56:56 +05:30
Wenkai Du
6047487815
RCCL 2.4 update
...
[ROCm/rccl commit: f11c8f60cd ]
2019-08-14 10:42:35 -07:00
rohit pathania
2dbcb62caf
Modified the code to use RTC clock frequency based on gpu gcn id
...
[ROCm/rccl commit: 65e2f5d87b ]
2019-08-14 12:55:12 +05:30
rohit pathania
042261445d
Merge branch 'xgmi_bench' of https://github.com/rpathani/rccl into xgmi_bench
...
# Conflicts:
# tools/rccl-prim-test/rccl_prim_test.cpp
[ROCm/rccl commit: 0f74929dab ]
2019-08-13 11:36:56 +05:30
rohit pathania
86f6d95b06
Adding linkinfo and srcGPU to destGPU info
...
[ROCm/rccl commit: 3bbf924ff8 ]
2019-08-13 11:28:50 +05:30
rohit pathania
95162665c7
Adding linkinfo and srcGPU to destGPU info
...
[ROCm/rccl commit: 5a2f74b8d0 ]
2019-08-09 12:44:06 +05:30
gilbertlee-amd
8645391260
Adding TransferBench tool ( #113 )
...
* Adding standalone TransferBench tool
[ROCm/rccl commit: b8cf48fc16 ]
2019-08-07 17:21:41 -06:00
Wenkai Du
b7322c800a
Refactor primitive test to support multiple GPUs in rings ( #94 )
...
* Refactor primitive test to support multiple GPUs in rings
* Make GPUs sync before transfer optional
* Use same ring format as RCCL
* Extend to 8 GPUs and report errors if there is no P2P access
* Control GPUs sync before ops from command line with "-s" option
* Change buffer size through command line option "-n"
Rename iterations command line option to "-i"
[ROCm/rccl commit: 70804da15b ]
2019-07-05 14:29:20 -07:00
Wenkai Du
90b7a02944
Match primitives unroll counts with latest RCCL ( #91 )
...
[ROCm/rccl commit: e6a0da444f ]
2019-06-26 15:09:13 -07:00
Wenkai Du
87d5441552
Calculate and print kernel throughput ( #78 )
...
* rccl-prim-test: print GPU info and set iterations
* Calculate and print kernel throughput
[ROCm/rccl commit: ee14676064 ]
2019-06-07 10:39:30 -07:00
Wenkai Du
dcb2801f25
rccl-prim-test: print GPU info and set iterations ( #77 )
...
[ROCm/rccl commit: 42b488507d ]
2019-06-05 15:16:33 -07:00
Wenkai Du
0ed10b1e4d
Add RCCL primitive testing ( #70 )
...
[ROCm/rccl commit: 1bb6d2104c ]
2019-05-23 16:52:17 -06:00