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
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
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
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
60cb8e4b56
Merge pull request #1634 from emankov/hipify-clang
...
[HIPIFY][format] Apply clang style formatting in LLVMCompat
[ROCm/clr commit: 2777b24abb ]
2019-11-06 14:46:45 +03: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
564feedbd5
Merge pull request #1633 from emankov/hipify-clang
...
[HIPIFY] Add a compatibility for CharSourceRange if LLVM < 7
[ROCm/clr commit: d0c5ab0e00 ]
2019-11-06 14:32:47 +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
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
684d1c3271
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/clr commit: 759a2c2ce5 ]
2019-11-04 14:44:59 -05:00
Jeff Daily
f7e255c3c4
fix race condition in hipEventRecord
...
[ROCm/clr commit: 6c3479a155 ]
2019-11-04 17:45:11 +00:00
foreman
4038857474
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/clr commit: 1405654d70 ]
2019-11-04 11:53:27 -05:00
foreman
fc6d4d47a3
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/clr commit: f55f2b8cee ]
2019-11-04 10:13:20 -05:00
Jenkins
776b5c75e0
Merge 'master' into 'amd-master'
...
Change-Id: Ic8372fe0f6b4f6edaae468e01f6c4583dc028d3c
[ROCm/clr commit: e146bbb3fe ]
2019-11-03 12:02:58 -05:00
Rahul Garg
9d078409e3
Merge pull request #1618 from ROCm-Developer-Tools/hotfix_volatile_accessors
...
Separate volatile for clarity. Handle assignment.
[ROCm/clr commit: 3b8a5cff2f ]
2019-11-02 13:50:59 -07:00
Alex Voicu
1a3d02fb08
Separate volatile for clarity. Handle assignment.
...
[ROCm/clr commit: ed0d6ec51e ]
2019-11-02 22:02:08 +02:00
Evgeny Mankov
8e369f9c7d
Merge pull request #1617 from emankov/hipify-clang
...
[HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option
[ROCm/clr commit: 758ab23b8f ]
2019-11-02 14:21:21 +03:00
Evgeny Mankov
bc9690328f
[HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option
...
+ Pass it to clang if specified
[ROCm/clr commit: 7142b884ab ]
2019-11-02 14:19:31 +03:00
Rahul Garg
91832b3b13
Merge pull request #1616 from ROCm-Developer-Tools/hotfix_volatile_accessors
...
Accessors should work even when oddly volatile.
[ROCm/clr commit: dc702f5ffe ]
2019-11-01 13:45:54 -07:00
Alex Voicu
5c2503f0bd
Accessors should work even when oddly volatile.
...
[ROCm/clr commit: 2d76dde05b ]
2019-11-01 22:18:01 +02:00
Evgeny Mankov
3b84d8e638
Merge pull request #1615 from emankov/hipify
...
[HIPIFY][CUB][#1460 ][perl] Add "cub::" namespace prefix support in hipify-perl as well
[ROCm/clr commit: 48bb6df7e2 ]
2019-11-01 14:35:55 +03:00
Evgeny Mankov
43d286e9ce
[HIPIFY][CUB][ #1460 ][perl] Add "cub::" namespace prefix support in hipify-perl as well
...
[ROCm/clr commit: c5a2a2daf2 ]
2019-11-01 14:34:18 +03:00
Jenkins
f3abfdfe5d
Merge 'master' into 'amd-master'
...
Change-Id: I8118854c18ba050c3de9b35dcf5cc7afb11688da
[ROCm/clr commit: 618e798ef0 ]
2019-11-01 05:10:10 -04:00
Rahul Garg
2cf205bc7b
Merge pull request #1582 from amd-lthakur/hipExtMLK
...
Adding a directed test case for hipExtModuleLaunchKernel() api.
[ROCm/clr commit: 1bec1445bb ]
2019-10-31 17:13:26 -07:00
Rahul Garg
e61ff0408c
Merge pull request #1598 from lmoriche/master
...
Fix a code object memory corruption
[ROCm/clr commit: 2199f8a6c6 ]
2019-10-31 17:12:24 -07:00
Jenkins
fa1cb040a3
Merge 'master' into 'amd-master'
...
Change-Id: If052e11355b22726cd10a40598f1a6505c81ed05
[ROCm/clr commit: 8eea3bfc9a ]
2019-10-31 14:58:54 -04:00
Rahul Garg
138b0327da
Add stream
...
[ROCm/clr commit: f556e15361 ]
2019-10-31 12:15:56 -04:00
Rahul Garg
440a172f0e
Fix HIP init calls in hipMemcpy2DFromArray
...
[ROCm/clr commit: 0718ba0f00 ]
2019-10-31 12:15:56 -04:00
Evgeny Mankov
f472257a40
Merge pull request #1612 from emankov/hipify
...
[HIPIFY][cmake][#1572 ] Fix: Do not override CMAKE_INSTALL_PREFIX
[ROCm/clr commit: 8b99b0ffd8 ]
2019-10-31 16:58:36 +03:00
Evgeny Mankov
0cfdeda490
[HIPIFY][cmake][ #1572 ] Fix: Do not override CMAKE_INSTALL_PREFIX
...
Affects building with HIP, standalone building is not changed
[ROCm/clr commit: e79fd55d01 ]
2019-10-31 16:55:06 +03:00
Rahul Garg
31fc374120
Formatting changes
...
[ROCm/clr commit: 07f4431de8 ]
2019-10-30 18:12:51 -07:00
Rahul Garg
5bcc1f66c5
Formatting changes ,variable name and check update
...
[ROCm/clr commit: cd1435cbc7 ]
2019-10-30 18:09:21 -07:00
Rahul Garg
04785f2d54
Merge pull request #1515 from ansurya/tex_unbind_issue_fix
...
Fix undefined ref to hipUnbindTexture for texture types
[ROCm/clr commit: aeb7cebbad ]
2019-10-30 17:54:15 -07:00
foreman
7ee03ae3d3
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/clr commit: e0107c5792 ]
2019-10-30 18:11:27 -04:00
Laurent Morichetti
f1f649e57c
Addressed review comments
...
Change comment "must exceed" to "must be no shorter than"
move the std::string instead of creating a copy
[ROCm/clr commit: 3243f06eef ]
2019-10-30 13:14:41 -07:00
Evgeny Mankov
5403e7edcc
Merge pull request #1593 from emankov/doc
...
[HIP][cmake] Move all *_INSTALL_DIR variables up before first add_subdirectory()
[ROCm/clr commit: 961bc5737e ]
2019-10-30 22:10:05 +03:00
foreman
da45649b24
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/clr commit: 234e21e08c ]
2019-10-30 13:37:03 -04:00
Rahul Garg
434231ac69
Merge pull request #1607 from mhbliao/hliao/master/missing.api.hip.clang
...
[HIP] Correct headers and add missing function templates for hip-clang.
[ROCm/clr commit: b94f5bd667 ]
2019-10-30 07:48:57 -07:00