Commit Graph

4857 Commits

Author SHA1 Message Date
Evgeny Mankov c87ab05fc6 [HIPIFY] Add a compatibility for CharSourceRange if LLVM < 7 2019-11-06 14:30:39 +03:00
Alex Voicu b9faa9f8ae Remove leftover noise. 2019-11-06 02:46:21 +02:00
Alex Voicu e5bd00d06b __half2 should walk like CUDA and talk like CUDA 2019-11-06 02:43:04 +02:00
Rahul Garg 32a67c9f14 Merge pull request #1626 from mhbliao/hliao/master/fix.windows.build
Use portable macro for deprecation message.
2019-11-05 10:08:43 -08:00
Evgeny Mankov 56fc294968 Merge pull request #1595 from emankov/cmake
[HIP][cmake] Simplify `UNIX` related code (the beginning)
2019-11-05 20:30:55 +03:00
Michael LIAO a7f311cc14 Use portable macro for deprecation message. 2019-11-05 11:51:00 -05:00
Evgeny Mankov a601670cb7 Merge pull request #1624 from emankov/hipify
[HIPIFY][#1409] Fix for kernel launch macro expansion
2019-11-05 14:04:51 +03:00
Evgeny Mankov 976f8e8bf6 [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
2019-11-05 14:00:13 +03:00
Rahul Garg 54fab7c35c Deprecate HIP Markers (#1622)
* Deprecate HIP markers

* Deprecate profiler start/stop
2019-11-05 12:32:59 +05:30
Aryan Salmanpour cf92fae9e6 [hip][tests] Add two more workgroup sizes for testing hipLaunchCooperativeKernel (#1613) 2019-11-05 12:32:46 +05:30
foreman c536429a6b 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
2019-11-04 16:42:31 -05:00
foreman 571b8d625d 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
2019-11-04 16:39:35 -05:00
foreman 007687bf53 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
2019-11-04 14:44:59 -05:00
Jeff Daily 6fcff0118e fix race condition in hipEventRecord 2019-11-04 17:45:11 +00:00
foreman 60e81906f5 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
2019-11-04 11:53:27 -05:00
foreman 33038437b3 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
2019-11-04 10:13:20 -05:00
Jenkins a78a41503a Merge 'master' into 'amd-master'
Change-Id: Ic8372fe0f6b4f6edaae468e01f6c4583dc028d3c
2019-11-03 12:02:58 -05:00
Rahul Garg 815a601dcb Merge pull request #1618 from ROCm-Developer-Tools/hotfix_volatile_accessors
Separate volatile for clarity. Handle assignment.
2019-11-02 13:50:59 -07:00
Alex Voicu 99b9d5449f Separate volatile for clarity. Handle assignment. 2019-11-02 22:02:08 +02:00
Evgeny Mankov 728bd683b1 Merge pull request #1617 from emankov/hipify-clang
[HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option
2019-11-02 14:21:21 +03:00
Evgeny Mankov 02589264a0 [HIPIFY] Introduce --cuda-gpu-arch as hipify-clang's option
+ Pass it to clang if specified
2019-11-02 14:19:31 +03:00
Rahul Garg 562da597a0 Merge pull request #1616 from ROCm-Developer-Tools/hotfix_volatile_accessors
Accessors should work even when oddly volatile.
2019-11-01 13:45:54 -07:00
Alex Voicu ee5097f2c2 Accessors should work even when oddly volatile. 2019-11-01 22:18:01 +02:00
Evgeny Mankov a3f6e0eda4 Merge pull request #1615 from emankov/hipify
[HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well
2019-11-01 14:35:55 +03:00
Evgeny Mankov c48fdefee8 [HIPIFY][CUB][#1460][perl] Add "cub::" namespace prefix support in hipify-perl as well 2019-11-01 14:34:18 +03:00
Jenkins 2c436f11c8 Merge 'master' into 'amd-master'
Change-Id: I8118854c18ba050c3de9b35dcf5cc7afb11688da
2019-11-01 05:10:10 -04:00
Rahul Garg 4739e68bbe Merge pull request #1582 from amd-lthakur/hipExtMLK
Adding a directed test case for hipExtModuleLaunchKernel() api.
2019-10-31 17:13:26 -07:00
Rahul Garg 782cf1c007 Merge pull request #1598 from lmoriche/master
Fix a code object memory corruption
2019-10-31 17:12:24 -07:00
Jenkins 1f6539b749 Merge 'master' into 'amd-master'
Change-Id: If052e11355b22726cd10a40598f1a6505c81ed05
2019-10-31 14:58:54 -04:00
Rahul Garg 85d70086cb Add stream 2019-10-31 12:15:56 -04:00
Rahul Garg efe6fa86dc Fix HIP init calls in hipMemcpy2DFromArray 2019-10-31 12:15:56 -04:00
Evgeny Mankov 6986818172 Merge pull request #1612 from emankov/hipify
[HIPIFY][cmake][#1572] Fix: Do not override CMAKE_INSTALL_PREFIX
2019-10-31 16:58:36 +03:00
Evgeny Mankov f563772a25 [HIPIFY][cmake][#1572] Fix: Do not override CMAKE_INSTALL_PREFIX
Affects building with HIP, standalone building is not changed
2019-10-31 16:55:06 +03:00
Rahul Garg 55f2a38120 Formatting changes 2019-10-30 18:12:51 -07:00
Rahul Garg 4ab71216b4 Formatting changes ,variable name and check update 2019-10-30 18:09:21 -07:00
Rahul Garg ba8105e0cd Merge pull request #1515 from ansurya/tex_unbind_issue_fix
Fix undefined ref to hipUnbindTexture for texture types
2019-10-30 17:54:15 -07:00
foreman 819b29f92d 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
2019-10-30 18:11:27 -04:00
Laurent Morichetti 91748f4e6c Addressed review comments
Change comment "must exceed" to "must be no shorter than"
move the std::string instead of creating a copy
2019-10-30 13:14:41 -07:00
Evgeny Mankov 77962371e7 Merge pull request #1593 from emankov/doc
[HIP][cmake] Move all *_INSTALL_DIR variables up before first add_subdirectory()
2019-10-30 22:10:05 +03:00
foreman e833ad571f 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
2019-10-30 13:37:03 -04:00
Rahul Garg eb7813c0fb Merge pull request #1607 from mhbliao/hliao/master/missing.api.hip.clang
[HIP] Correct headers and add missing function templates for hip-clang.
2019-10-30 07:48:57 -07:00
foreman a0f8995e3a P4 to Git Change 2021608 by michliao@hliao-dev-00-hip.rocm-workspace on 2019/10/30 01:13:58
SWDEV-145570 - [HIP] Fix occupancy API prototype.

	- They need to be C API, i.e. extern "C".
	- Follow the current API and use `uint32_t` instead of `int`.
	  + TODO: We need to revert them back once that APIs are changed to be
	    compatible with CUDA.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#46 edit
2019-10-30 01:19:24 -04:00
Michael LIAO 5c8a7521f4 [HIP] Correct headers and add missing function templates for hip-clang.
- Fix 2 runtime API prototypes
  `hipOccupancyMaxActiveBlocksPerMultiprocessor` and
  `hipOccupancyMaxActiveBlocksPerMultiprocessorWithFlags`
- Add missing function templates of them in hip-clang.
2019-10-29 22:00:11 -04:00
Rahul Garg 4d04baf0cd Merge pull request #1602 from ROCm-Developer-Tools/revert-1560-satyanveshd/hipoccupy
Revert "Cooperative groups match with cuda SWDEV-205006"
2019-10-29 16:54:36 -07:00
Evgeny Mankov 7d0a10cf00 Merge pull request #1604 from emankov/hipify
[HIPIFY][#1603] Fix
2019-10-29 22:12:39 +03:00
Evgeny Mankov 389b5ec957 [HIPIFY][#1603] Fix 2019-10-29 22:10:36 +03:00
Rahul Garg e4a1e44162 Revert "Fix occupany APIs (#1560)"
This reverts commit af351d7e1b.
2019-10-29 11:41:08 -07:00
Evgeny Mankov 265d34e160 Merge pull request #1601 from emankov/hipify
[HIPIFY][Linux] Rollback --cuda-compile-host-device on Linux
2019-10-29 20:55:29 +03:00
Evgeny Mankov 85087644da [HIPIFY][Linux] Rollback --cuda-compile-host-device on Linux
[Reason] It doesn't work with LLVM 9 and higher; Windows is fine
2019-10-29 20:53:54 +03:00
Evgeny Mankov 764a1f0023 Merge pull request #1600 from emankov/hipify
[HIPIFY] Introduce --cuda-compile-host-device for LLVM >= 9
2019-10-29 19:47:15 +03:00