AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
5 416 Commits 3 Branches 0 Tags
cddd09b85d8a2ebbae87235425ef1ffbe3ece99d
Commit Graph

5416 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
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 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 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 7b216ca51c [HIPIFY][doc] Update README.md 
+ Supported versions, testing


[ROCm/hip commit: 96483d0de5]
 2019-11-06 19:18:13 +03: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 8f033af434 remove ihipEvent_t::refreshEventStatus(), new hipEventElapsedTime 
This fixes possible races in hipEventElapsedTime.


[ROCm/hip commit: 7986090d9c]
 2019-11-06 15:46:46 +00:00
Evgeny Mankov b77feedcd9 Merge pull request #1634 from emankov/hipify-clang 
[HIPIFY][format] Apply clang style formatting in LLVMCompat

[ROCm/hip commit: 514180b83c]
 2019-11-06 14:46:45 +03:00
Evgeny Mankov 1b6e4b495a [HIPIFY][format] Apply clang style formatting in LLVMCompat 
[ROCm/hip commit: 3b76fd0b1c]
 2019-11-06 14:43:22 +03:00
Evgeny Mankov 9e3c107549 Merge pull request #1633 from emankov/hipify-clang 
[HIPIFY] Add a compatibility for CharSourceRange if LLVM < 7

[ROCm/hip commit: 89e4330890]
 2019-11-06 14:32:47 +03:00
Evgeny Mankov 1776ff55d3 [HIPIFY] Add a compatibility for CharSourceRange if LLVM < 7 
[ROCm/hip commit: c87ab05fc6]
 2019-11-06 14:30:39 +03:00
Alex Voicu f8506bb669 Remove leftover noise. 
[ROCm/hip commit: b9faa9f8ae]
 2019-11-06 02:46:21 +02:00
Alex Voicu 1baaf44179 __half2 should walk like CUDA and talk like CUDA 
[ROCm/hip commit: e5bd00d06b]
 2019-11-06 02:43:04 +02:00
Rahul Garg 93bd983bbf Merge pull request #1626 from mhbliao/hliao/master/fix.windows.build 
Use portable macro for deprecation message.

[ROCm/hip commit: 32a67c9f14]
 2019-11-05 10:08:43 -08:00
Evgeny Mankov 15406422fe Merge pull request #1595 from emankov/cmake 
[HIP][cmake] Simplify `UNIX` related code (the beginning)

[ROCm/hip commit: 56fc294968]
 2019-11-05 20:30:55 +03:00
Michael LIAO e250f76183 Use portable macro for deprecation message. 
[ROCm/hip commit: a7f311cc14]
 2019-11-05 11:51:00 -05:00
Evgeny Mankov b4a30a0c7a Merge pull request #1624 from emankov/hipify 
[HIPIFY][#1409] Fix for kernel launch macro expansion

[ROCm/hip commit: a601670cb7]
 2019-11-05 14:04:51 +03:00
Evgeny Mankov 5a9c8168c1 [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/hip commit: 976f8e8bf6]
 2019-11-05 14:00:13 +03:00
Rahul Garg 1b8973d6be Deprecate HIP Markers (#1622) 
* Deprecate HIP markers

* Deprecate profiler start/stop


[ROCm/hip commit: 54fab7c35c]
 2019-11-05 12:32:59 +05:30
Aryan Salmanpour 2ad99a6326 [hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel (#1613) 
[ROCm/hip commit: cf92fae9e6]
 2019-11-05 12:32:46 +05:30
foreman c1400c5234 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/hip commit: c536429a6b]
 2019-11-04 16:42:31 -05:00
foreman ba23455719 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/hip commit: 571b8d625d]
 2019-11-04 16:39:35 -05:00
foreman 187d089afa P4 to Git Change 2024454 by axie@axie-hip-rocm on 2019/11/04 14:38:31 
SWDEV-198863 - Options for hip-clang-vdi path to provide the chicken bits, or functional equivalents to HCC_DB (phase 1)

	1. The log macros is turned off for release build.  So log functions has zero impact to release build.
	2. The log macros have level, mask, condition control. So we can have more control to avoid log flooding.

	I also adjusted some existing log to use new log functions.
	1. To excercise and test the new log functions.
	2. To improve performance slightly.
	3. The change is mainly for HIP-ROCM, we can move more in next phases for PAL or ORCA.
	4. I make these log feature unavailable for release build. We can revert to old log functions for release build in a case by case method.

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

	2. release build, run hip program, there is no log
	3. fastdebug build, run hip program,
	export LOG_LEVEL=3
	export GPU_LOG_MASK=4294967295
	There was a lot of logs.

	4. fastdebug build, run hip program,
	export LOG_LEVEL=2
	export GPU_LOG_MASK=4294967295
	There was no logs.

	5. fastdebug build, run hip program,
	export LOG_LEVEL=3
	export GPU_LOG_MASK=4294967294
	There was much less logs.

	6. fastdebug build, run hip program,
	export LOG_LEVEL=3
	export GPU_LOG_MASK=47102
	There was even much less logs. The logs was expected according to the mask.

	7. Tested step 2 to 6 similarily in Windows and Linux

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#46 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#82 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#26 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hiprtc_internal.hpp#2 edit
... //depot/stg/opencl/drivers/opencl/api/opencl/amdocl/cl_svm.cpp#29 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/comgrctx.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.cpp#29 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#68 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocdevice.cpp#137 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rocvirtual.cpp#91 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/command.cpp#100 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.cpp#32 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/runtime.cpp#40 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/debug.hpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#323 edit


[ROCm/hip commit: 007687bf53]
 2019-11-04 14:44:59 -05:00
Jeff Daily cdf59d1de0 fix race condition in hipEventRecord 
[ROCm/hip commit: 6fcff0118e]
 2019-11-04 17:45:11 +00:00
foreman fa734a8ade P4 to Git Change 2024314 by kjayapra@0_HIPWS_LNX1_ROCM on 2019/11/04 11:44:45 
SWDEV-206759 - Fixing Compilation error.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#47 edit


[ROCm/hip commit: 60e81906f5]
 2019-11-04 11:53:27 -05:00
foreman e77419eb2a P4 to Git Change 2024251 by kjayapra@0_HIPWS_LNX1_ROCM on 2019/11/04 10:07:42 
SWDEV-206759 - Adding support for duplicate global vars

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#45 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#81 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#46 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#48 edit
... //depot/stg/opencl/drivers/opencl/make/hip.git/tests/build/Makefile.hip_tests#30 edit


[ROCm/hip commit: 33038437b3]
 2019-11-04 10:13:20 -05:00
Jenkins 4173159cd1 Merge 'master' into 'amd-master' 
Change-Id: Ic8372fe0f6b4f6edaae468e01f6c4583dc028d3c


[ROCm/hip commit: a78a41503a]
 2019-11-03 12:02:58 -05:00
Rahul Garg dfbbe8119e Merge pull request #1618 from ROCm-Developer-Tools/hotfix_volatile_accessors 
Separate volatile for clarity. Handle assignment.

[ROCm/hip commit: 815a601dcb]
 2019-11-02 13:50:59 -07:00
Alex Voicu e87f9b1944 Separate volatile for clarity. Handle assignment. 
[ROCm/hip commit: 99b9d5449f]
 2019-11-02 22:02:08 +02:00
Evgeny Mankov 093d205c24 Merge pull request #1617 from emankov/hipify-clang 
[HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option

[ROCm/hip commit: 728bd683b1]
 2019-11-02 14:21:21 +03:00
Evgeny Mankov 92cd5e4fc1 [HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option 
+ Pass it to clang if specified


[ROCm/hip commit: 02589264a0]
 2019-11-02 14:19:31 +03:00
Rahul Garg d688b66b31 Merge pull request #1616 from ROCm-Developer-Tools/hotfix_volatile_accessors 
Accessors should work even when oddly volatile.

[ROCm/hip commit: 562da597a0]
 2019-11-01 13:45:54 -07:00
Alex Voicu b30a42f678 Accessors should work even when oddly volatile. 
[ROCm/hip commit: ee5097f2c2]
 2019-11-01 22:18:01 +02:00
Evgeny Mankov 0e30eb9a31 Merge pull request #1615 from emankov/hipify 
[HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well

[ROCm/hip commit: a3f6e0eda4]
 2019-11-01 14:35:55 +03:00
Evgeny Mankov 07cca5b6bb [HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well 
[ROCm/hip commit: c48fdefee8]
 2019-11-01 14:34:18 +03:00
Jenkins 19c133ef05 Merge 'master' into 'amd-master' 
Change-Id: I8118854c18ba050c3de9b35dcf5cc7afb11688da


[ROCm/hip commit: 2c436f11c8]
 2019-11-01 05:10:10 -04:00
Rahul Garg 25a5ca94de Merge pull request #1582 from amd-lthakur/hipExtMLK 
Adding a directed test case for hipExtModuleLaunchKernel() api.

[ROCm/hip commit: 4739e68bbe]
 2019-10-31 17:13:26 -07:00
Rahul Garg 3e3cebe614 Merge pull request #1598 from lmoriche/master 
Fix a code object memory corruption

[ROCm/hip commit: 782cf1c007]
 2019-10-31 17:12:24 -07:00
Jenkins d971fd2c47 Merge 'master' into 'amd-master' 
Change-Id: If052e11355b22726cd10a40598f1a6505c81ed05


[ROCm/hip commit: 1f6539b749]
 2019-10-31 14:58:54 -04:00
Rahul Garg 75cf902cdb Add stream 
[ROCm/hip commit: 85d70086cb]
 2019-10-31 12:15:56 -04:00
Rahul Garg 73ca647852 Fix HIP init calls in hipMemcpy2DFromArray 
[ROCm/hip commit: efe6fa86dc]
 2019-10-31 12:15:56 -04:00
Evgeny Mankov 3506efd8ea Merge pull request #1612 from emankov/hipify 
[HIPIFY][cmake][#1572] Fix: Do not override CMAKE_INSTALL_PREFIX

[ROCm/hip commit: 6986818172]
 2019-10-31 16:58:36 +03:00
Evgeny Mankov 0feee792b8 [HIPIFY][cmake][#1572] Fix: Do not override CMAKE_INSTALL_PREFIX 
Affects building with HIP, standalone building is not changed


[ROCm/hip commit: f563772a25]
 2019-10-31 16:55:06 +03:00
Rahul Garg b68c8d2f60 Formatting changes 
[ROCm/hip commit: 55f2a38120]
 2019-10-30 18:12:51 -07:00
Rahul Garg 8429e15052 Formatting changes ,variable name and check update 
[ROCm/hip commit: 4ab71216b4]
 2019-10-30 18:09:21 -07:00
Rahul Garg 7e742b1216 Merge pull request #1515 from ansurya/tex_unbind_issue_fix 
Fix undefined ref to hipUnbindTexture for texture types

[ROCm/hip commit: ba8105e0cd]
 2019-10-30 17:54:15 -07:00
foreman aa87a6a41d P4 to Git Change 2022168 by jujiang@JJ-OCL-hip on 2019/10/30 18:06:41 
SWDEV-208594 - [HIP][Windows] Output mismatch with texture ref test functions with float4 type

	-Fix TexRef1D float/float4, and TexRef2D tests.
	http://ocltc.amd.com/reviews/r/18203/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#26 edit


[ROCm/hip commit: 819b29f92d]
 2019-10-30 18:11:27 -04:00
Laurent Morichetti 1056ca35dc Addressed review comments 
Change comment "must exceed" to "must be no shorter than"
move the std::string instead of creating a copy


[ROCm/hip commit: 91748f4e6c]
 2019-10-30 13:14:41 -07:00
Evgeny Mankov cee5e37f57 Merge pull request #1593 from emankov/doc 
[HIP][cmake] Move all *_INSTALL_DIR variables up before first add_subdirectory()

[ROCm/hip commit: 77962371e7]
 2019-10-30 22:10:05 +03:00
foreman e76231a330 P4 to Git Change 2021977 by kjayapra@1_HIPWS_LNX1_PAL on 2019/10/30 13:27:19 
SWDEV-209747 - Improve HIP Error codes and debug messages.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_context.cpp#24 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device.cpp#25 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#20 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#18 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_memory.cpp#80 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#45 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_peer.cpp#8 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#47 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_profile.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_surface.cpp#6 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_texture.cpp#25 edit


[ROCm/hip commit: e833ad571f]
 2019-10-30 13:37:03 -04:00
Rahul Garg 5d5d8774f5 Merge pull request #1607 from mhbliao/hliao/master/missing.api.hip.clang 
[HIP] Correct headers and add missing function templates for hip-clang.

[ROCm/hip commit: eb7813c0fb]
 2019-10-30 07:48:57 -07:00