Evgeny
b033453537
concurrent sqtt support
...
Change-Id: I0e1515d4b0aab30b0a9b673120eee28d96f64d9e
2020-06-10 22:45:30 -04:00
Evgeny
80687c9c03
concurrent sqtt support
...
Change-Id: I0e1515d4b0aab30b0a9b673120eee28d96f64d9e
[ROCm/ROCR-Runtime commit: b033453537 ]
2020-06-10 22:45:30 -04:00
Wenkai Du
0b235b136a
Correct szie when init sendbuff
...
[ROCm/rccl-tests commit: 83b846cf4f ]
2020-06-10 23:24:08 +00:00
Wenkai Du
83b846cf4f
Correct szie when init sendbuff
2020-06-10 23:24:08 +00:00
Saleel Kudchadker
fca301772c
Add logging support for AQL packet
...
Use AMD_LOG_LEVEL=4 and AMD_LOG_MASK=8 to print AQL log
explicitly
Change-Id: I4209d91b460e64be44261d3ab773580067e47c29
[ROCm/clr commit: 2b771d2f5f ]
2020-06-10 14:04:47 -07:00
Saleel Kudchadker
2b771d2f5f
Add logging support for AQL packet
...
Use AMD_LOG_LEVEL=4 and AMD_LOG_MASK=8 to print AQL log
explicitly
Change-Id: I4209d91b460e64be44261d3ab773580067e47c29
2020-06-10 14:04:47 -07:00
Siu Chi Chan
3d7612af8d
fix uninitialized value in hipcc
...
Change-Id: I90b070c491f0efc328fcf97de0e111658ec772de
[ROCm/clr commit: 32f3374af9 ]
2020-06-10 16:07:51 -04:00
Siu Chi Chan
32f3374af9
fix uninitialized value in hipcc
...
Change-Id: I90b070c491f0efc328fcf97de0e111658ec772de
2020-06-10 16:07:51 -04:00
Siu Chi Chan
ee30f289b4
fix uninitialized value in hipcc
...
Change-Id: I90b070c491f0efc328fcf97de0e111658ec772de
[ROCm/hip commit: 85e3b37052 ]
2020-06-10 16:07:51 -04:00
Siu Chi Chan
85e3b37052
fix uninitialized value in hipcc
...
Change-Id: I90b070c491f0efc328fcf97de0e111658ec772de
2020-06-10 16:07:51 -04:00
Jason Tang
83153d4a2d
Enable OCLReadWriteImage test on Linux
...
Change-Id: I613e5ff6dd0234515409b8d3f7277f5bbdd1bd20
[ROCm/clr commit: 17dafe33de ]
2020-06-10 15:30:23 -04:00
Jason Tang
17dafe33de
Enable OCLReadWriteImage test on Linux
...
Change-Id: I613e5ff6dd0234515409b8d3f7277f5bbdd1bd20
2020-06-10 15:30:23 -04:00
jujiang
83c3939c6c
Fix for SWDEV-239415 to handle hipGetDevice properly while no GPU present
...
Change-Id: I252cbbf9a89fc76fe1be1fbb8f45778e96c70fb2
[ROCm/clr commit: bb32492438 ]
2020-06-10 14:18:56 -04:00
jujiang
bb32492438
Fix for SWDEV-239415 to handle hipGetDevice properly while no GPU present
...
Change-Id: I252cbbf9a89fc76fe1be1fbb8f45778e96c70fb2
2020-06-10 14:18:56 -04:00
jujiang
572efac7a5
Fix for SWDEV-239415 to handle hipGetDevice properly while no GPU present
...
Change-Id: I252cbbf9a89fc76fe1be1fbb8f45778e96c70fb2
[ROCm/hip commit: c54590ebbd ]
2020-06-10 14:18:56 -04:00
jujiang
c54590ebbd
Fix for SWDEV-239415 to handle hipGetDevice properly while no GPU present
...
Change-Id: I252cbbf9a89fc76fe1be1fbb8f45778e96c70fb2
2020-06-10 14:18:56 -04:00
Chris Freehill
b07fd8fca7
Update XGMI perf counter test to show utilization
...
Also:
* When destroying a counter, make sure to stop the counter first
* In the test, do not stop (disable) the counter before
reading it.
* Clean up some whitespace in other tests
* Re-add manual pdf file
Change-Id: I0786ef3a994ca568299c77e44f092af8943ac33d
[ROCm/rocm_smi_lib commit: f946ea37ef ]
2020-06-10 12:49:49 -04:00
Chris Freehill
f946ea37ef
Update XGMI perf counter test to show utilization
...
Also:
* When destroying a counter, make sure to stop the counter first
* In the test, do not stop (disable) the counter before
reading it.
* Clean up some whitespace in other tests
* Re-add manual pdf file
Change-Id: I0786ef3a994ca568299c77e44f092af8943ac33d
2020-06-10 12:49:49 -04:00
Chris Freehill
b30200cd48
Update XGMI perf counter test to show utilization
...
Also:
* When destroying a counter, make sure to stop the counter first
* In the test, do not stop (disable) the counter before
reading it.
* Clean up some whitespace in other tests
* Re-add manual pdf file
Change-Id: I0786ef3a994ca568299c77e44f092af8943ac33d
[ROCm/amdsmi commit: f946ea37ef ]
2020-06-10 12:49:49 -04:00
kjayapra-amd
5593475c37
SWDEV-231701 - Remove amd::memory->svm_ptr from MemObj, instead of the ptr to the object.
...
Change-Id: I5aab450a2320cfa5417c284e2a8454102df6f99d
[ROCm/clr commit: 9ff22151d2 ]
2020-06-10 11:49:02 -04:00
kjayapra-amd
9ff22151d2
SWDEV-231701 - Remove amd::memory->svm_ptr from MemObj, instead of the ptr to the object.
...
Change-Id: I5aab450a2320cfa5417c284e2a8454102df6f99d
2020-06-10 11:49:02 -04:00
kjayapra-amd
707ec427bc
SWDEV-231701 - Remove amd::memory->svm_ptr from MemObj, instead of the ptr to the object.
...
Change-Id: I5aab450a2320cfa5417c284e2a8454102df6f99d
[ROCm/hip commit: 2f8e180f01 ]
2020-06-10 11:49:02 -04:00
kjayapra-amd
2f8e180f01
SWDEV-231701 - Remove amd::memory->svm_ptr from MemObj, instead of the ptr to the object.
...
Change-Id: I5aab450a2320cfa5417c284e2a8454102df6f99d
2020-06-10 11:49:02 -04:00
Evgeny
78fc334ec3
run_ci fix
...
Change-Id: Ibf07cb92c55790be723dc2e97d09f3232983747e
[ROCm/roctracer commit: 5a0fd11cf8 ]
2020-06-10 10:01:35 -05:00
Evgeny
5a0fd11cf8
run_ci fix
...
Change-Id: Ibf07cb92c55790be723dc2e97d09f3232983747e
2020-06-10 10:01:35 -05:00
Dittakavi Satyanvesh
a0fbc8fd08
SWDEV-236670 Address Eigen unit test failure by adding __host__ attribute to half2 functions
...
Change-Id: Ifdc852c30a1b3704871e0ee58cb7a55d3d37fc6e
[ROCm/clr commit: bb785840b9 ]
2020-06-10 03:01:42 -04:00
Dittakavi Satyanvesh
bb785840b9
SWDEV-236670 Address Eigen unit test failure by adding __host__ attribute to half2 functions
...
Change-Id: Ifdc852c30a1b3704871e0ee58cb7a55d3d37fc6e
2020-06-10 03:01:42 -04:00
Dittakavi Satyanvesh
7b1ff8fe8b
SWDEV-236670 Address Eigen unit test failure by adding __host__ attribute to half2 functions
...
Change-Id: Ifdc852c30a1b3704871e0ee58cb7a55d3d37fc6e
[ROCm/hip commit: 6ed1868203 ]
2020-06-10 03:01:42 -04:00
Dittakavi Satyanvesh
6ed1868203
SWDEV-236670 Address Eigen unit test failure by adding __host__ attribute to half2 functions
...
Change-Id: Ifdc852c30a1b3704871e0ee58cb7a55d3d37fc6e
2020-06-10 03:01:42 -04:00
Chauncey Hui
cdd067bca6
SWDEV-2 - Change OpenCL version number from 3158 to 3159
...
[ROCm/clr commit: 4cd1579d46 ]
2020-06-10 03:00:02 -04:00
Chauncey Hui
4cd1579d46
SWDEV-2 - Change OpenCL version number from 3158 to 3159
2020-06-10 03:00:02 -04: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
fee1a20b74
gtest: add scatter, gather and all to all unit tests
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
e98891d039
Log NUMA node of RDMA host buffer allocation
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
812543104d
Add network proxy profiling support
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
c9aa11928a
Calculate and use total wait cycles for RCCL profiling
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
e80e29573c
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.
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
71ec3e09df
tpol_expl: update to 2.7
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
Wenkai Du
26a0fd2517
Merge remote-tracking branch 'nccl/master' into develop
2020-06-09 17:40:11 -07:00
Evgeny
9ae5b91ec2
packaging fix1
...
Change-Id: Ifc8941b2a720628d76e0697debe6a861fa349b2b
[ROCm/roctracer commit: f2d3fd943d ]
2020-06-09 19:31:37 -05:00
Evgeny
f2d3fd943d
packaging fix1
...
Change-Id: Ifc8941b2a720628d76e0697debe6a861fa349b2b
2020-06-09 19:31:37 -05:00
Christophe Paquot
4206cfddc5
Do not deferred stream creation now that we multiplex HW queues
...
SWDEV-239856
Change-Id: I156650faf832f86891f00ee167269509edd844ec
[ROCm/clr commit: 20ae4d709f ]
2020-06-09 19:16:25 -04:00
Christophe Paquot
20ae4d709f
Do not deferred stream creation now that we multiplex HW queues
...
SWDEV-239856
Change-Id: I156650faf832f86891f00ee167269509edd844ec
2020-06-09 19:16:25 -04:00
Christophe Paquot
5a8857b3e9
Do not deferred stream creation now that we multiplex HW queues
...
SWDEV-239856
Change-Id: I156650faf832f86891f00ee167269509edd844ec
[ROCm/hip commit: c8f9afa9da ]
2020-06-09 19:16:25 -04:00