76333 Commits
Author SHA1 Message Date
foreman a1ebb70b22 P4 to Git Change 2026151 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/06 17:49:50
SWDEV-145570 - Revert CL 2026045.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.cpp#34 edit


[ROCm/clr commit: 86ca698d2f]
2019-11-06 17:55:50 -05:00
foreman 86ca698d2f P4 to Git Change 2026151 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/06 17:49:50
SWDEV-145570 - Revert CL 2026045.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.cpp#34 edit
2019-11-06 17:55:50 -05:00
Philip Yang 59c857476f libhsakmt: use the closest NUMA node to allocate queue ctx area
On NUMA system, allocate queue ctx save restore area on the closest NUMA
node to the GPU which the queue is going to run. This will improve
performance on NUMA system generally by reducing schedule latency and
fix the multi-node rccl-tests unstable performance issue.

If the closest NUMA node has no memory available, set flags NoNUMABind=1
to bypass mbind, to use default NUMA memory policy to allocate system
memory.



Change-Id: Ic62bfa5bb2efbf4f6ae79ff403e9610ddf18d45c
Signed-off-by: Philip Yang <Philip.Yang@amd.com>
2019-11-06 17:33:26 -05:00
Philip Yang bdb519bd35 libhsakmt: use the closest NUMA node to allocate queue ctx area
On NUMA system, allocate queue ctx save restore area on the closest NUMA
node to the GPU which the queue is going to run. This will improve
performance on NUMA system generally by reducing schedule latency and
fix the multi-node rccl-tests unstable performance issue.

If the closest NUMA node has no memory available, set flags NoNUMABind=1
to bypass mbind, to use default NUMA memory policy to allocate system
memory.



Change-Id: Ic62bfa5bb2efbf4f6ae79ff403e9610ddf18d45c
Signed-off-by: Philip Yang <Philip.Yang@amd.com>


[ROCm/ROCR-Runtime commit: 59c857476f]
2019-11-06 17:33:26 -05:00
Ramesh Errabolu 086b4b686c Fix Aql Header initialization
Change-Id: If23c12b28d22fb62b673038890f40bb0f3c3948b
2019-11-06 16:13:58 -05:00
Ramesh Errabolu 1798d1386b Fix Aql Header initialization
Change-Id: If23c12b28d22fb62b673038890f40bb0f3c3948b


[ROCm/ROCR-Runtime commit: 086b4b686c]
2019-11-06 16:13:58 -05:00
foreman 3a51f9be1b P4 to Git Change 2026045 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/06 15:01:45
SWDEV-145570 - [HIP] Report submitted when actually submitted to the HW.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.cpp#33 edit


[ROCm/clr commit: 438eb7d9ce]
2019-11-06 15:19:25 -05:00
foreman 438eb7d9ce P4 to Git Change 2026045 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/06 15:01:45
SWDEV-145570 - [HIP] Report submitted when actually submitted to the HW.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.cpp#33 edit
2019-11-06 15:19:25 -05:00
Rahul Garg 7cde192635 Merge pull request #1630 from ROCm-Developer-Tools/hotfix_volatile_accessors
__half2 should walk like CUDA and talk like CUDA

[ROCm/clr commit: d8e9a09064]
2019-11-06 10:25:03 -08:00
Rahul Garg d8e9a09064 Merge pull request #1630 from ROCm-Developer-Tools/hotfix_volatile_accessors
__half2 should walk like CUDA and talk like CUDA
2019-11-06 10:25:03 -08:00
Rahul Garg 9248fcd9bc Merge pull request #1630 from ROCm-Developer-Tools/hotfix_volatile_accessors
__half2 should walk like CUDA and talk like CUDA

[ROCm/hip commit: 2fa45c215a]
2019-11-06 10:25:03 -08:00
Rahul Garg 2fa45c215a Merge pull request #1630 from ROCm-Developer-Tools/hotfix_volatile_accessors
__half2 should walk like CUDA and talk like CUDA
2019-11-06 10:25:03 -08:00
Rahul Garg 15c457396d Merge pull request #1620 from jeffdaily/hipEventRecord_patch
fix race condition in hipEventRecord

[ROCm/clr commit: 5af7ca4445]
2019-11-06 10:23:24 -08:00
Rahul Garg 5af7ca4445 Merge pull request #1620 from jeffdaily/hipEventRecord_patch
fix race condition in hipEventRecord
2019-11-06 10:23:24 -08:00
Rahul Garg a48954ef98 Merge pull request #1620 from jeffdaily/hipEventRecord_patch
fix race condition in hipEventRecord

[ROCm/hip commit: 85446dbd6a]
2019-11-06 10:23:24 -08:00
Rahul Garg 85446dbd6a Merge pull request #1620 from jeffdaily/hipEventRecord_patch
fix race condition in hipEventRecord
2019-11-06 10:23:24 -08:00
foreman 82d0aa350a P4 to Git Change 2025942 by axie@axie-hip-rocm on 2019/11/06 11:58:18
SWDEV-198863 - Options for hip-clang-vdi path to provide the chicken bits, or functional equivalents to HCC_DB (phase 2)
	Enable the log functions for release build.

	Tests:
	1. Linux HIP ROCM platform. VEGA10. Driver is release build.
	1.1 export LOG_LEVEL=3
	      ./hipModule
	      There are many logs.
	1.2 export GPU_LOG_MASK=0
	     ./hipModule
	     There is no log
	2. Windows HIP PAL platform. VEGA10, Driver is release or fastdbg build.
	2.1 set LOG_LEVEL=3
	    run test hipPrintfKernel
	    There are many logs
	2.2 set GPU_LOG_MASK=0
	    run test hipPrintfKernel
	    There is no log

	3. http://ocltc.amd.com:8111/viewModification.html?modId=128481&personal=true&tab=vcsModificationBuilds

	ReviewBoard: http://ocltc.amd.com/reviews/r/18240/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/debug.hpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#324 edit


[ROCm/clr commit: d16ccc8dcc]
2019-11-06 12:11:11 -05:00
foreman d16ccc8dcc P4 to Git Change 2025942 by axie@axie-hip-rocm on 2019/11/06 11:58:18
SWDEV-198863 - Options for hip-clang-vdi path to provide the chicken bits, or functional equivalents to HCC_DB (phase 2)
	Enable the log functions for release build.

	Tests:
	1. Linux HIP ROCM platform. VEGA10. Driver is release build.
	1.1 export LOG_LEVEL=3
	      ./hipModule
	      There are many logs.
	1.2 export GPU_LOG_MASK=0
	     ./hipModule
	     There is no log
	2. Windows HIP PAL platform. VEGA10, Driver is release or fastdbg build.
	2.1 set LOG_LEVEL=3
	    run test hipPrintfKernel
	    There are many logs
	2.2 set GPU_LOG_MASK=0
	    run test hipPrintfKernel
	    There is no log

	3. http://ocltc.amd.com:8111/viewModification.html?modId=128481&personal=true&tab=vcsModificationBuilds

	ReviewBoard: http://ocltc.amd.com/reviews/r/18240/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/debug.hpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#324 edit
2019-11-06 12:11:11 -05:00
Wen-Heng (Jack) Chung 0510b2c23b Revise the return type of roctracer_next_record to roctracer_status_t.
[ROCm/roctracer commit: f730fb6a4e]
2019-11-06 10:54:45 -06:00
Wen-Heng (Jack) Chung f730fb6a4e Revise the return type of roctracer_next_record to roctracer_status_t. 2019-11-06 10:54:45 -06:00
Chris Freehill 6a4ba6ff2a Use "-" instead of "_" for package name
This is part of fix to SWDEV-208805. The other part will
be in the build_* script.

Change-Id: I36397e3f918d08170db8bb228722a2b7389af83b


[ROCm/rocm_smi_lib commit: 0e5c44de2a]
2019-11-06 11:31:50 -05:00
Chris Freehill 0e5c44de2a Use "-" instead of "_" for package name
This is part of fix to SWDEV-208805. The other part will
be in the build_* script.

Change-Id: I36397e3f918d08170db8bb228722a2b7389af83b
2019-11-06 11:31:50 -05:00
Chris Freehill d4e8ab37d5 Use "-" instead of "_" for package name
This is part of fix to SWDEV-208805. The other part will
be in the build_* script.

Change-Id: I36397e3f918d08170db8bb228722a2b7389af83b


[ROCm/amdsmi commit: 0e5c44de2a]
2019-11-06 11:31:50 -05:00
Evgeny Mankov ffff62ed03 Merge pull request #1636 from emankov/hipify-clang
[HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10

[ROCm/clr commit: c0f9c854a6]
2019-11-06 19:27:40 +03:00
Evgeny Mankov c0f9c854a6 Merge pull request #1636 from emankov/hipify-clang
[HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10
2019-11-06 19:27:40 +03:00
Evgeny Mankov 8ddaf844d7 Merge pull request #1636 from emankov/hipify-clang
[HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10

[ROCm/hip commit: 30c138eda2]
2019-11-06 19:27:40 +03:00
Evgeny Mankov 30c138eda2 Merge pull request #1636 from emankov/hipify-clang
[HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10
2019-11-06 19:27:40 +03:00
Evgeny Mankov c3a76d58da [HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10
[ROCm/clr commit: 97a0670d29]
2019-11-06 19:25:42 +03:00
Evgeny Mankov 97a0670d29 [HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10 2019-11-06 19:25:42 +03:00
Evgeny Mankov 282c76c26f [HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10
[ROCm/hip commit: 9ca4e96641]
2019-11-06 19:25:42 +03:00
Evgeny Mankov 9ca4e96641 [HIPIFY][Win][fix] canCompileHostAndDeviceInOneJob is true only for LLVM >= 10 2019-11-06 19:25:42 +03:00
Evgeny Mankov ef205f5e80 Merge pull request #1635 from emankov/hipify-clang
[HIPIFY][doc] Update README.md

[ROCm/clr commit: d9016ab9b7]
2019-11-06 19:20:02 +03:00
Evgeny Mankov d9016ab9b7 Merge pull request #1635 from emankov/hipify-clang
[HIPIFY][doc] Update README.md
2019-11-06 19:20:02 +03:00
Evgeny Mankov 223897c24c Merge pull request #1635 from emankov/hipify-clang
[HIPIFY][doc] Update README.md

[ROCm/hip commit: 7875bb789b]
2019-11-06 19:20:02 +03:00
Evgeny Mankov 7875bb789b Merge pull request #1635 from emankov/hipify-clang
[HIPIFY][doc] Update README.md
2019-11-06 19:20:02 +03:00
Chris Freehill edc222faea Docs., error checking and test improvements
* Update doc. on api-support function
* Check for valid integer value when reading a monitor int. val.
* If fan-write test attempts to set speed higher than max.
   possible, then skip the test

Change-Id: I01ad0ab1f4caffdb0d2c26e9575f278c35a6b017


[ROCm/rocm_smi_lib commit: 52dfa4bcca]
2019-11-06 11:19:47 -05:00
Chris Freehill 52dfa4bcca Docs., error checking and test improvements
* Update doc. on api-support function
* Check for valid integer value when reading a monitor int. val.
* If fan-write test attempts to set speed higher than max.
   possible, then skip the test

Change-Id: I01ad0ab1f4caffdb0d2c26e9575f278c35a6b017
2019-11-06 11:19:47 -05:00
Chris Freehill 106c87ad0e Docs., error checking and test improvements
* Update doc. on api-support function
* Check for valid integer value when reading a monitor int. val.
* If fan-write test attempts to set speed higher than max.
   possible, then skip the test

Change-Id: I01ad0ab1f4caffdb0d2c26e9575f278c35a6b017


[ROCm/amdsmi commit: 52dfa4bcca]
2019-11-06 11:19:47 -05:00
Evgeny Mankov d5b2d0fd63 [HIPIFY][doc] Update README.md
+ Supported versions, testing


[ROCm/clr commit: 3f737625ee]
2019-11-06 19:18:13 +03:00
Evgeny Mankov 3f737625ee [HIPIFY][doc] Update README.md
+ Supported versions, testing
2019-11-06 19:18:13 +03:00
Evgeny Mankov 7b216ca51c [HIPIFY][doc] Update README.md
+ Supported versions, testing


[ROCm/hip commit: 96483d0de5]
2019-11-06 19:18:13 +03:00
Evgeny Mankov 96483d0de5 [HIPIFY][doc] Update README.md
+ Supported versions, testing
2019-11-06 19:18:13 +03: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
Wenkai Du 277c72a638 Merge pull request #149 from wenkaidu/rtc
Correct RTC frequencies for profiling purpose
2019-11-06 08:02:58 -08:00
Jeff Daily 39a98df790 hipEventRecord only needs one lock; remove locked_eventIsReady
[ROCm/clr commit: b2af1820f5]
2019-11-06 15:56:32 +00:00
Jeff Daily b2af1820f5 hipEventRecord only needs one lock; remove locked_eventIsReady 2019-11-06 15:56:32 +00:00
Jeff Daily f9ad564380 hipEventRecord only needs one lock; remove locked_eventIsReady
[ROCm/hip commit: 85080905c0]
2019-11-06 15:56:32 +00:00
Jeff Daily 85080905c0 hipEventRecord only needs one lock; remove locked_eventIsReady 2019-11-06 15:56:32 +00:00
Jeff Daily 539d0c2ae3 remove ihipEvent_t::refreshEventStatus(), new hipEventElapsedTime
This fixes possible races in hipEventElapsedTime.


[ROCm/clr commit: 444122dfb9]
2019-11-06 15:46:46 +00:00
Jeff Daily 444122dfb9 remove ihipEvent_t::refreshEventStatus(), new hipEventElapsedTime
This fixes possible races in hipEventElapsedTime.
2019-11-06 15:46:46 +00:00