Commit Graph

12692 Commits

Author SHA1 Message Date
foreman 690db13054 P4 to Git Change 2028995 by jatang@jatang_win_pal_lc on 2019/11/12 11:56:20
SWDEV-207835 - Implement uniform package versioning for cmake version of OpenCL.

	Need to generate the same style of packages name as the Makefile version does.

Affected files ...

... //depot/stg/opencl/drivers/opencl/CMakeLists.txt#29 edit


[ROCm/clr commit: 1927416168]
2019-11-12 12:04:53 -05:00
Evgeny Mankov ed11ec3fa9 [HIPIFY][doc] A few words about LLVM's FileCheck in README.md
[ROCm/clr commit: bb6f1648ec]
2019-11-12 16:04:28 +03:00
foreman 4f1cdf92aa P4 to Git Change 2028744 by chui@ocl-promo-incrementor on 2019/11/12 03:00:07
SWDEV-2 - Change OpenCL version number from 3035 to 3036.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2783 edit


[ROCm/clr commit: 2a927f1c3b]
2019-11-12 03:07:45 -05:00
foreman 329ccad8c9 P4 to Git Change 2028285 by axie@axie-hip-rocm on 2019/11/11 12:03:24
SWDEV-193973 - [OpenCL][NV21] Add support for Navi21
	Add #ifndef OPENCL_MAINLINE around Navi 21 source code. This is to facilitate Open Source preparation.

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

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdefs.hpp#26 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#140 edit


[ROCm/clr commit: 131437441e]
2019-11-11 12:06:15 -05:00
Maneesh Gupta ca9eb34000 Bump version to 3.0 (#1648)
Change-Id: Id1e6eb222080a339af938212e74a52c39c305eab

[ROCm/clr commit: 0a2682625f]
2019-11-10 20:23:58 -08:00
foreman ac17b22686 P4 to Git Change 2027775 by chui@ocl-promo-incrementor on 2019/11/09 03:00:06
SWDEV-2 - Change OpenCL version number from 3034 to 3035.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2782 edit


[ROCm/clr commit: eb364125d5]
2019-11-09 03:13:41 -05:00
foreman 9eda8a1ffc P4 to Git Change 2027470 by axie@axie-hip-rocm on 2019/11/08 13:48:51
SWDEV-198863 - Options for hip-clang-vdi path to provide the chicken bits, or functional equivalents to HCC_DB (phase 3)
	Use ClPrint to implement other log functions.
	Move some funtion to use new log functions.
	This is the final change of the JIRA.

	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 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=128588&personal=true&tab=vcsModificationBuilds

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#177 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#157 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/debug.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/debug.hpp#14 edit


[ROCm/clr commit: 1f0d5016ed]
2019-11-08 13:54:34 -05:00
foreman d82a9c6eac P4 to Git Change 2027394 by axie@axie-hip-rocm on 2019/11/08 11:33:17
SWDEV-193973 - [OpenCL][NV21] Add support for Navi21
	Add IDs.

	Tests:
	http://ocltc.amd.com:8111/viewModification.html?modId=128585&personal=true&tab=vcsModificationBuilds
	http://ocltc.amd.com:8111/viewModification.html?modId=128554&personal=true&tab=vcsModificationBuilds
	http://ocltc.amd.com:8111/viewModification.html?modId=128550&personal=true&tab=vcsModificationBuilds

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdefs.hpp#25 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#139 edit


[ROCm/clr commit: 106f1cfef8]
2019-11-08 11:38:06 -05:00
foreman 8f99c9552c P4 to Git Change 2027191 by chui@ocl-promo-incrementor on 2019/11/08 03:00:05
SWDEV-2 - Change OpenCL version number from 3033 to 3034.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2781 edit


[ROCm/clr commit: 73048b9aa1]
2019-11-08 03:12:03 -05:00
foreman c9167c3f42 P4 to Git Change 2026938 by axie@axie-hip-rocm on 2019/11/07 17:44:09
SWDEV-198859 - Options for hip-clang-vdi path to provide the chicken bits, or functional equivalents to HCC_DB

	There are regression caused by this change in ocltst test.
	Back out changelist 2026859

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#176 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#156 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/debug.hpp#13 edit


[ROCm/clr commit: 7434cabbf7]
2019-11-07 17:48:59 -05:00
foreman c3c87af67d P4 to Git Change 2026859 by axie@axie-hip-rocm on 2019/11/07 15:54:13
SWDEV-198863 - Options for hip-clang-vdi path to provide the chicken bits, or functional equivalents to HCC_DB (phase 3)
	Use ClPrint to implement other log functions.
	Move some funtion to use new log functions.
	This is the final change of the JIRA.

	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 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=128490&personal=true&tab=vcsModificationBuilds

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#175 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#155 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/debug.hpp#12 edit


[ROCm/clr commit: c10b29f0e0]
2019-11-07 16:06:51 -05:00
Michael LIAO a10e227b56 Remove redundant declarations.
- The revised `hip/hip_ext.h` have that declarations.


[ROCm/clr commit: d28ad401c9]
2019-11-07 10:11:22 -05:00
Evgeny Mankov 62b86d1c76 [HIPIFY] Clang style formatting
[ROCm/clr commit: 7f143585f6]
2019-11-07 12:48:05 +03:00
Evgeny Mankov db5f0b0237 [HIPIFY][fix] Delete canCompileHostAndDeviceInOneJob declaration as well
[ROCm/clr commit: 4d2424ad36]
2019-11-07 11:32:53 +03:00
Evgeny Mankov be483c4b3e [HIPIFY][fix] Abandon canCompileHostAndDeviceInOneJob check for --cuda-compile-host-device option
[Reason] It turned out that it is not so: 2 jobs are always


[ROCm/clr commit: 21c3d25403]
2019-11-07 11:30:40 +03:00
Evgeny Mankov ba52f11231 [HIPIFY] Reorder options propagation to clang
[Reason] Leave overriding opportunity for -D, -std=c++XX, etc.


[ROCm/clr commit: f18e63b8a9]
2019-11-07 11:21:06 +03:00
foreman 56ef3fc134 P4 to Git Change 2026403 by chui@ocl-promo-incrementor on 2019/11/07 03:00:05
SWDEV-2 - Change OpenCL version number from 3032 to 3033.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2780 edit


[ROCm/clr commit: 4fbf7389b2]
2019-11-07 03:06:59 -05:00
Jeff Daily bc5596cc74 General hipMemset improvements (#1495)
* hipMemset et al can use HSA API directly for synchronous cases

* lock and flush stream in hipMemset, hold lock until complete

* move hipMemset async check to front of conditional

* use hsa_amd_memory_fill for additional sync memset cases

code cleanup/review for all memset calls

* Fix inversion of execution mutating value.

* ihipMemsetSync fall back to kernel if HSA memset fails

* Never fallback, never surrender.

* Allow NULL stream.

* Optimise memset kernel. Remove deadwood.

* Update hip_memory.cpp

* Clean up stream logic in sync memset

* Revert "Clean up stream logic in sync memset"

This reverts commit 6117dedf673367f44cc704192573a117a3d92477.


[ROCm/clr commit: 854147e911]
2019-11-07 13:19:54 +05:30
Alex Voicu 44d2a3bb73 Remove native vector support from the GCC case, since it never worked (#1637)
[ROCm/clr commit: d38cc8efba]
2019-11-07 13:19:14 +05:30
Sarbojit2019 4d0b7e65bb [HIP] Fixed hipStreamAddCallback [SWDEV#165185] (#1425)
Fixed hipStreamAddCallback() as requested in SWDEV#165185
Added unit test to test the behavior


[ROCm/clr commit: 97fca3439d]
2019-11-07 13:18:12 +05:30
ansurya f5a92e5cb6 Fixed texture 2D mapping for pitched arrays & 3D Texture read (#1415)
Texture 2D image mapping for pitched arrays:
github issue: Texture Object's Buffer seems to be Misaligned #886
JIRA ticket: SWDEV-199313

SWDEV-151670 : Fixed issue with 3D texture with 4 components
SWDEV-151671 : Issue with 2D layered texture with 4 components

[ROCm/clr commit: dc8f556460]
2019-11-07 13:17:46 +05:30
Rahul Garg cf648f7dbe Rename hip/hip_hcc.h to hip/hip_ext.h (#1341)
* Rename hip/hip_hcc.h to hip/hip_ext.h

* Deprecate hip_hcc.h


[ROCm/clr commit: dfee3ae279]
2019-11-07 13:17:10 +05:30
foreman 4c6b9f8d0c P4 to Git Change 2026174 by eshcherb@evgeny-hip on 2019/11/06 19:37:26
SWDEV-197289 - tracing callbacks call fix

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_prof_api.h#5 edit


[ROCm/clr commit: 39587efda6]
2019-11-06 19:47:10 -05:00
foreman 5cf3d1eb33 P4 to Git Change 2026159 by gandryey@gera-win10 on 2019/11/06 18:14:30
SWDEV-79445 - OCL generic changes and code clean-up
	- Fix the detection of all devices for P2P. The previous logic worked only if GPU_ENABLE_PAL was forced to 1.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#174 edit


[ROCm/clr commit: f6ce2e78ea]
2019-11-06 18:22:20 -05:00
foreman 637a82e848 P4 to Git Change 2026152 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/06 17:50:08
SWDEV-206239 - [HIP] RCCL: finegrain VRAM does not work
	Implemented fine grained VRAM allocation via ATOMICS.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#84 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#138 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#43 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#45 edit


[ROCm/clr commit: 6d0c96993d]
2019-11-06 18:00:44 -05:00
foreman 8a2d0028ba P4 to Git Change 2026152 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/06 17:50:08
SWDEV-206239 - [HIP] RCCL: finegrain VRAM does not work
	Implemented fine grained VRAM allocation via ATOMICS.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#84 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#138 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.hpp#43 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocmemory.cpp#45 edit


[ROCm/clr commit: 2506752348]
2019-11-06 18:00:44 -05:00
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 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
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 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
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
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 d5b2d0fd63 [HIPIFY][doc] Update README.md
+ Supported versions, testing


[ROCm/clr commit: 3f737625ee]
2019-11-06 19:18:13 +03: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 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
Evgeny Mankov 4ef69e128b [HIPIFY][format] Apply clang style formatting in LLVMCompat
[ROCm/clr commit: 4cad5fab78]
2019-11-06 14:43:22 +03:00
Evgeny Mankov bb93c0b039 [HIPIFY] Add a compatibility for CharSourceRange if LLVM < 7
[ROCm/clr commit: 3dcae8760d]
2019-11-06 14:30:39 +03:00
Alex Voicu 7efa901dfa Remove leftover noise.
[ROCm/clr commit: 1df423165b]
2019-11-06 02:46:21 +02:00
Alex Voicu 3ce73d1ef6 __half2 should walk like CUDA and talk like CUDA
[ROCm/clr commit: 55fd1363e2]
2019-11-06 02:43:04 +02:00
Rahul Garg b854e0a392 Merge pull request #1626 from mhbliao/hliao/master/fix.windows.build
Use portable macro for deprecation message.

[ROCm/clr commit: 6833886449]
2019-11-05 10:08:43 -08:00
Evgeny Mankov 388181ada7 Merge pull request #1595 from emankov/cmake
[HIP][cmake] Simplify `UNIX` related code (the beginning)

[ROCm/clr commit: 7b1ca3dd91]
2019-11-05 20:30:55 +03:00
Michael LIAO a1b2dcf87d Use portable macro for deprecation message.
[ROCm/clr commit: 7ca43b98d1]
2019-11-05 11:51:00 -05:00
Evgeny Mankov ecad81b794 Merge pull request #1624 from emankov/hipify
[HIPIFY][#1409] Fix for kernel launch macro expansion

[ROCm/clr commit: cf5d1caab3]
2019-11-05 14:04:51 +03:00
Evgeny Mankov 3889be3031 [HIPIFY][#1409] Fix for kernel launch macro expansion
+ Add a corresponding test kernel_launch_01.cu
+ Add isBefore() check to avoid crash on Replacement with negative length

TODO:
+ Compatibility with former LLVM versions
+ More complicated kernel launch tests


[ROCm/clr commit: a1c380f38d]
2019-11-05 14:00:13 +03:00
foreman ab31ac124a P4 to Git Change 2024896 by chui@ocl-promo-incrementor on 2019/11/05 03:00:04
SWDEV-2 - Change OpenCL version number from 3031 to 3032.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2779 edit


[ROCm/clr commit: 46c64aa3e2]
2019-11-05 03:05:18 -05:00
Rahul Garg 92393d6ecf Deprecate HIP Markers (#1622)
* Deprecate HIP markers

* Deprecate profiler start/stop


[ROCm/clr commit: 8b3fce8069]
2019-11-05 12:32:59 +05:30
Aryan Salmanpour 92a06b531d [hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel (#1613)
[ROCm/clr commit: 7a3d592ed0]
2019-11-05 12:32:46 +05:30
foreman 9121a1eef0 P4 to Git Change 2024544 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/04 16:35:14
SWDEV-145570 - [HIP] Fetched properties from current device and not default 0 one.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#21 edit


[ROCm/clr commit: cbbe0e78cf]
2019-11-04 16:42:31 -05:00
foreman 9e5f271147 P4 to Git Change 2024543 by cpaquot@cpaquot-ocl-lc-lnx on 2019/11/04 16:32:23
SWDEV-206239 - [HIP] Return hipErrorMemoryAllocation for fine grained VRAM for now

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#83 edit


[ROCm/clr commit: bd34138596]
2019-11-04 16:39:35 -05:00
foreman 0853864d4d P4 to Git Change 2024527 by gandryey@gera-win10 on 2019/11/04 16:11:31
SWDEV-209969 - SQTT missing event instrumenting token in OpenCL trace
	- SQTT trace reports memory clears if program load occurs during the capture. Avoid memory clears with GPU if CPU backing store is available

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#100 edit


[ROCm/clr commit: 029cfb4aee]
2019-11-04 16:18:08 -05:00