Wenkai Du
2f99c7bbad
topo_expl: each rank needs to have its own memory for graphs ( #225 )
...
[ROCm/rccl commit: d3548cc474 ]
2020-07-01 15:11:02 -07:00
Wenkai Du
e8da2a0da6
topo_expl: fix broken build ( #224 )
...
[ROCm/rccl commit: a6be82f5ab ]
2020-06-30 11:11:23 -07:00
Wenkai Du
effafd456b
Merge pull request #223 from wenkaidu/sendrecv
...
Use separate threads for send and receive
[ROCm/rccl commit: a144a85465 ]
2020-06-30 10:50:06 -07:00
Wenkai Du
ac87c9db37
gtest: extend testing up to 8 GPUs
...
[ROCm/rccl commit: 8db0aa8f4c ]
2020-06-29 09:32:31 -07:00
Wenkai Du
77d94493c3
Merge sendrecv kernel from NCCL 2.7.3
...
This commit was cherry-picked and modified from
https://github.com/NVIDIA/nccl/commit/89072c82e551d7c8bf7bd5ca77780ef540b7611e
[ROCm/rccl commit: 964c4c2061 ]
2020-06-29 08:47:46 -07:00
Wenkai Du
3c674c9c1f
Use separate threads for send and receive
...
[ROCm/rccl commit: b90735c935 ]
2020-06-29 08:47:15 -07:00
Wenkai Du
117f0f6e6e
Revert use posix_memalign for network buffer allocation on host memory ( #222 )
...
[ROCm/rccl commit: 84f8ba3bb0 ]
2020-06-24 11:25:55 -07:00
Wenkai Du
e7d664200f
Use posix_memalign for network buffer allocation on host memory ( #221 )
...
* Use posix_memalign for network buffer allocation on host memory
* ib-test: add ability to specify run iterations
* ib-test: define iterations as multiple of default cycles
* Add checking to posix_memalign return value
[ROCm/rccl commit: 0eb19a563a ]
2020-06-22 13:06:25 -07:00
Wenkai Du
2dc0cfcbf5
ib-test: support host memory allocation through posix_memalign ( #220 )
...
* ib-test: support host memory allocation through posix_memalign
* ib-test: add missing CUDACHECK to hip calls
[ROCm/rccl commit: dc739c4e70 ]
2020-06-17 16:16:54 -07:00
Stanley Tsang
dafe176570
Documentation updates for NCCL 2.7.0 ( #219 )
...
* Making hip-clang the default compiler; documentation update
* Adding back --hip-clang to install.sh as a silent option for CI
* Documentation updates for NCCL 2.7
* Restoring deleted line in install script
[ROCm/rccl commit: 8d21adb5e3 ]
2020-06-16 16:48:11 -06:00
Wenkai Du
efcf211458
Merge pull request #218 from wenkaidu/develop
...
Develop
[ROCm/rccl commit: 0023b9b081 ]
2020-06-16 13:30:50 -07:00
Wenkai Du
9ca3176346
Add IB/RDMA unit test
...
[ROCm/rccl commit: cfa97eccd3 ]
2020-06-16 18:29:17 +00:00
Wenkai Du
5d93f83ae3
Limit network profiling support to simple protocol and avoid overflow
...
[ROCm/rccl commit: 95b8f70d15 ]
2020-06-15 20:51:36 +00:00
Wenkai Du
3389838def
Rework network proxy profiling
...
[ROCm/rccl commit: 7484e53ff7 ]
2020-06-13 03:13:58 +00:00
Wenkai Du
a8952356d1
Reduce RCCL kernel count as we don't pass first coll in argument
...
[ROCm/rccl commit: b257676f30 ]
2020-06-12 21:30:04 +00:00
Wenkai Du
a90fac8579
Sender rank's opCount maybe ahead by one if it finishes earlier
...
[ROCm/rccl commit: a6d621176c ]
2020-06-12 03:39:45 +00:00
Wenkai Du
d1f8fdc3a8
gtest: add scatter, gather and all to all unit tests
...
[ROCm/rccl commit: fee1a20b74 ]
2020-06-09 17:44:15 -07:00
Wenkai Du
e7dd92dc87
Log NUMA node of RDMA host buffer allocation
...
[ROCm/rccl commit: e98891d039 ]
2020-06-09 17:44:15 -07:00
Wenkai Du
846e1a4427
Add network proxy profiling support
...
[ROCm/rccl commit: 812543104d ]
2020-06-09 17:44:15 -07:00
Wenkai Du
bc6840f937
Calculate and use total wait cycles for RCCL profiling
...
[ROCm/rccl commit: c9aa11928a ]
2020-06-09 17:44:15 -07:00
Wenkai Du
15cd2aff3c
Add gather, scatter and alltoall collectives
...
Introducing 3 new APIs:
ncclResult_t ncclGather(const void* sendbuff, void* recvbuff, size_t sendcount,
ncclDataType_t datatype, int root, ncclComm_t comm, hipStream_t stream);
ncclResult_t ncclScatter(const void* sendbuff, void* recvbuff,
size_t recvcount, ncclDataType_t datatype, int root, ncclComm_t comm,
hipStream_t stream);
ncclResult_t ncclAllToAll(const void* sendbuff, void* recvbuff, size_t count,
ncclDataType_t datatype, ncclComm_t comm, hipStream_t stream);
Only out of place operation is supported.
Preprocessor symbol RCCL_GATHER_SCATTER=1 indicates API availibility.
By default the APIs launche RCCL kernel implementation, which can be disabled by
RCCL_ALLTOALL_KERNEL_DISABLE=1. Then the APIs use wrapper around ncclSend and ncclRecv.
[ROCm/rccl commit: e80e29573c ]
2020-06-09 17:44:08 -07:00
Wenkai Du
69eb70ce43
tpol_expl: update to 2.7
...
[ROCm/rccl commit: 71ec3e09df ]
2020-06-09 17:40:24 -07:00
Wenkai Du
67fb4f6cdb
Merge remote-tracking branch 'nccl/master' into develop
...
[ROCm/rccl commit: 26a0fd2517 ]
2020-06-09 17:40:11 -07:00
Sylvain Jeaugey
89072c82e5
2.7.3-1
...
Add support for A100 GPU and related platforms.
Add support for CUDA 11.
Add support for send/receive operations (beta).
[ROCm/rccl commit: 5949d96f36 ]
2020-06-08 09:31:44 -07:00
saadrahim
3077902de6
Fixing CI as install.sh script should not install dependencies without user request ( #217 )
...
[ROCm/rccl commit: 87db65f22d ]
2020-06-05 11:04:03 -06:00
Stanley Tsang
8e43b854f1
Making hip-clang the default compiler; documentation update ( #216 )
...
* Making hip-clang the default compiler; documentation update
* Adding back --hip-clang to install.sh as a silent option for CI
[ROCm/rccl commit: dc403e0ca2 ]
2020-06-04 11:58:27 -06:00
Wenkai Du
55d3b0aa68
Merge pull request #214 from wenkaidu/gdr
...
Use cached value for detecting GDR support only once
[ROCm/rccl commit: 2a4514772c ]
2020-05-22 13:36:23 -07:00
Wenkai Du
0108a1219d
Use cached value for detecting GDR support only once
...
[ROCm/rccl commit: 67c8e72ce3 ]
2020-05-22 17:19:10 +00:00
Wenkai Du
730fddfcf3
Merge pull request #212 from wenkaidu/version
...
Report HIP version in logs
[ROCm/rccl commit: 957be85944 ]
2020-05-20 16:25:54 -07:00
Wenkai Du
b449a3b36d
Report HIP version in logs
...
[ROCm/rccl commit: e41ab173cf ]
2020-05-20 18:15:32 +00:00
Wenkai Du
fbd7d2d0d7
Merge pull request #210 from wenkaidu/unroll
...
Revert "Tuning the inline and unroll to reduce the scratch usage"
[ROCm/rccl commit: af703877cf ]
2020-05-15 15:35:27 -07:00
Wenkai Du
e7eff47be4
Revert "Tuning the inline and unroll to reduce the scratch usage"
...
This reverts commit d8a06589c9 .
[ROCm/rccl commit: ca493a6b51 ]
2020-05-15 14:15:40 -07:00
Wenkai Du
5780637fff
Merge pull request #209 from wenkaidu/hip-clang
...
Rename files which only diffs in extension
[ROCm/rccl commit: c245f1507e ]
2020-05-15 13:51:12 -07:00
Wenkai Du
61a82ff572
Merge pull request #208 from wenkaidu/perf_xgmi
...
Give preference to path with more XGMI connections
[ROCm/rccl commit: 706de76046 ]
2020-05-15 10:07:22 -07:00
Wenkai Du
c2afb1f4ca
Rename files which only diffs in extension
...
[ROCm/rccl commit: e7b36304c8 ]
2020-05-15 09:16:32 -07:00
Wenkai Du
da05861904
Merge pull request #207 from wenkaidu/hip-clang
...
rccl-prim-test: add flags when calling hipExtLaunchMultiKernelMultiDe…
[ROCm/rccl commit: ca4987e5fb ]
2020-05-14 18:31:56 -07:00
Wenkai Du
27519fd019
Give preference to path with more XGMI connections
...
[ROCm/rccl commit: b3c9852634 ]
2020-05-14 15:33:16 -07:00
Wenkai Du
ced9958094
rccl-prim-test: add flags when calling hipExtLaunchMultiKernelMultiDevice in hip-clang
...
[ROCm/rccl commit: f1058b6353 ]
2020-05-12 23:54:07 +00:00
Stanley Tsang
5b01a901b7
Merge pull request #206 from stanleytsang-amd/develop
...
Updating RCCL documentation
[ROCm/rccl commit: 66a9f11910 ]
2020-05-12 17:24:40 -06:00
Stanley Tsang
abba9d5504
Restoring doxygen documentation to nccl.h.in.
...
[ROCm/rccl commit: 787ac13486 ]
2020-05-12 22:03:31 +00:00
Stanley Tsang
e35e4d3401
Updating README and readthedocs documentation.
...
[ROCm/rccl commit: b59b9d328b ]
2020-05-12 20:11:49 +00:00
Wenkai Du
d1cd60fbf4
Merge pull request #205 from wenkaidu/bf16
...
Update rccl_bfloat16.h to match rocBLAS
[ROCm/rccl commit: 52752aba6e ]
2020-05-11 09:55:06 -07:00
Wenkai Du
5ba51914f1
Update rccl_bfloat16.h to match rocBLAS
...
[ROCm/rccl commit: d5a07a7b5c ]
2020-05-08 22:48:07 +00:00
Wenkai Du
0d642448d7
Merge pull request #204 from wenkaidu/launch_flags
...
Set flags when calling hipExtLaunchMultiKernelMultiDevice in hip-clang
[ROCm/rccl commit: 94d16c0f0a ]
2020-05-08 11:20:50 -07:00
Wenkai Du
069322d05a
Set flags when calling hipExtLaunchMultiKernelMultiDevice in hip-clang
...
[ROCm/rccl commit: 24ea2ef6dd ]
2020-05-08 15:57:14 +00:00
Saad Rahim
65ad48404b
Merge remote-tracking branch 'upstream/master' into develop
...
[ROCm/rccl commit: 33c23fdcda ]
2020-04-29 16:12:37 -07:00
saadrahim
75863c97a4
Refactoring packaging ( #193 )
...
[ROCm/rccl commit: 308e96877e ]
2020-04-29 16:24:21 -06:00
Wenkai Du
2badecfa20
Merge pull request #199 from wenkaidu/para_jobs
...
Enable parallel jobs for hip-clang build
[ROCm/rccl commit: 914b6ca27c ]
2020-04-29 13:49:48 -07:00
saadrahim
fa25190ddb
Junit test storage call corrected ( #197 )
...
* Focus testing on Centos for now
* storing junit
* Reducing test suite to Ubuntu
[ROCm/rccl commit: 65390f9872 ]
2020-04-29 14:22:03 -06:00
Wenkai Du
52096f2cb6
Enable parallel jobs for hip-clang build
...
[ROCm/rccl commit: 3f471ab5b1 ]
2020-04-29 17:58:16 +00:00