Commit Graph

12340 Commits

Author SHA1 Message Date
foreman 46a6201be0 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: 3f6e18bf6b]
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
Alex Voicu 1a3d02fb08 Separate volatile for clarity. Handle assignment.
[ROCm/clr commit: ed0d6ec51e]
2019-11-02 22:02:08 +02: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
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
foreman cf6b79ccd0 P4 to Git Change 2023164 by chui@ocl-promo-incrementor on 2019/11/01 03:00:11
SWDEV-2 - Change OpenCL version number from 3030 to 3031.

Affected files ...

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


[ROCm/clr commit: 68340fee18]
2019-11-01 03:06:49 -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
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 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
foreman d72b16eac9 P4 to Git Change 2022345 by chui@ocl-promo-incrementor on 2019/10/31 03:00:12
SWDEV-2 - Change OpenCL version number from 3029 to 3030.

Affected files ...

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


[ROCm/clr commit: 60eea61dd7]
2019-10-31 03:13:59 -04:00
foreman 9066c4aca4 P4 to Git Change 2022337 by todli@todli-win-opencl-kv1 on 2019/10/31 02:34:19
SWDEV-200688 - Correct some misalignment between DeviceInfo and CALtarget, so that VEGAM can be correctly recognized as gfx804 instead of gfx902

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/gpu/gslbe/src/rt/caltarget.h#10 edit


[ROCm/clr commit: ec18fcbc84]
2019-10-31 02:36:59 -04: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
foreman 4d6967fa7e P4 to Git Change 2021639 by chui@ocl-promo-incrementor on 2019/10/30 03:00:53
SWDEV-2 - Change OpenCL version number from 3028 to 3029.

Affected files ...

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


[ROCm/clr commit: 6b680186bc]
2019-10-30 03:07:02 -04:00
foreman d3b9a50c57 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


[ROCm/clr commit: 988882bb4f]
2019-10-30 01:19:24 -04:00
Michael LIAO 64f2d5e861 [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.


[ROCm/clr commit: 61bc68a5f4]
2019-10-29 22:00:11 -04:00
Rahul Garg 42ab7b830e Merge pull request #1602 from ROCm-Developer-Tools/revert-1560-satyanveshd/hipoccupy
Revert "Cooperative groups match with cuda SWDEV-205006"

[ROCm/clr commit: 9840cdac99]
2019-10-29 16:54:36 -07:00
Evgeny Mankov dc0186720c [HIPIFY][#1603] Fix
[ROCm/clr commit: 050fdad7b7]
2019-10-29 22:10:36 +03:00
Rahul Garg 72c686ed67 Revert "Fix occupany APIs (#1560)"
This reverts commit ad1e409a24.


[ROCm/clr commit: 27221bc823]
2019-10-29 11:41:08 -07:00
Evgeny Mankov d8e846fc91 [HIPIFY][Linux] Rollback --cuda-compile-host-device on Linux
[Reason] It doesn't work with LLVM 9 and higher; Windows is fine


[ROCm/clr commit: dd2243f2fa]
2019-10-29 20:53:54 +03:00
Evgeny Mankov 21d798394a [HIPIFY] Introduce --cuda-compile-host-device for LLVM >= 9
* LLVM < 9 continues using --cuda-host-only


[ROCm/clr commit: 411b18a124]
2019-10-29 19:42:53 +03:00
foreman 048e47d190 P4 to Git Change 2021171 by gandryey@gera-win10 on 2019/10/29 12:06:07
SWDEV-208424 - ROCr language runtime should not free code object until executable destroy
	- Reshuffle the code to make sure HSA runtime can keep the pointer to the code object

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#67 edit


[ROCm/clr commit: 783f1a506c]
2019-10-29 12:23:34 -04:00
Evgeny Mankov bb75fa46f0 [HIPIFY] cudaMemcpy2DFromArray(Async) support
[ROCm/clr commit: 5dd00bdf52]
2019-10-29 19:12:42 +03:00
Laurent Morichetti 0113961674 Fix a code object memory corruption
The lifetime of the buffer given to
hsa_code_object_reader_create_from_memory must exceed that of the
code object reader. We need to create a copy of the code object
binary memory (file) that is kept allocated until the code object
reader is destroyed.


[ROCm/clr commit: 66c91b42e6]
2019-10-29 08:23:57 -07:00
foreman 5591526562 P4 to Git Change 2020900 by chui@ocl-promo-incrementor on 2019/10/29 03:00:53
SWDEV-2 - Change OpenCL version number from 3027 to 3028.

Affected files ...

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


[ROCm/clr commit: c081898145]
2019-10-29 03:02:40 -04:00
foreman d4643d3325 P4 to Git Change 2020678 by gandryey@gera-win10 on 2019/10/28 18:06:48
SWDEV-79445 - OCL generic changes and code clean-up
	- Fix memory leaks in COMGR path. Make sure  metadata_ object is properly destroyed in COMGR.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.cpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devkernel.hpp#18 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#66 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.hpp#34 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#84 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/rocm/rockernel.cpp#53 edit


[ROCm/clr commit: 720ea66859]
2019-10-28 18:13:35 -04:00
Evgeny Mankov a4c7894255 [HIP][cmake] Simplify UNIX related code (the beginning)
[REASONS]
1. Make OS-dependent code more clear and readable
2. To ease Windows support


[ROCm/clr commit: 4c5c6b4910]
2019-10-28 23:22:27 +03:00
Evgeny Mankov 4e02b285d6 [HIP][doc] NVIDIA-nvcc -> HIP-nvcc
[ROCm/clr commit: 3df22b2fde]
2019-10-28 22:46:33 +03:00
Evgeny Mankov 935dd4ce94 [HIP][doc] AMD-hcc -> HIP-hcc
[ROCm/clr commit: d312bce79d]
2019-10-28 21:41:12 +03:00
Evgeny Mankov 20b127bf45 [HIP][doc] Fix typo: AMD-clang -> HIP-clang
HIP-clang is already used below instead of AMD-clang


[ROCm/clr commit: 6284b041e5]
2019-10-28 21:19:21 +03:00
Evgeny Mankov 0737167ee4 [HIP][cmake] Move all *_INSTALL_DIR variables up before first add_subdirectory()
[REASON]
Those vars (may) used by cmake in subdirectories (#1571)


[ROCm/clr commit: 8100e084b8]
2019-10-28 21:07:00 +03:00
foreman cc02406257 P4 to Git Change 2019944 by chui@ocl-promo-incrementor on 2019/10/26 03:00:52
SWDEV-2 - Change OpenCL version number from 3026 to 3027.

Affected files ...

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


[ROCm/clr commit: a8e96b1d3d]
2019-10-26 03:10:02 -04:00
foreman c228e91ff6 P4 to Git Change 2019867 by gandryey@gera-win10 on 2019/10/25 18:12:01
SWDEV-79445 - OCL generic changes and code clean-up
	- Fix memory leaks in COMGR path. Don't create binaryData, since it will be overwritten with action_data_get_data() call.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/devprogram.cpp#65 edit


[ROCm/clr commit: e22fe683e7]
2019-10-25 18:17:54 -04:00
foreman 3fd285e26b P4 to Git Change 2019864 by axie@axie_opencl_pal on 2019/10/25 18:03:56
SWDEV-204995 - Linux Pro: Houdini18 Application hang is seen with pyro sample on OpenCL selection.
	The new Houdini application has around 286.6K byte TLS. In Linux, the TLS resides in thread stack. TLS is allocated and initialized during pthread_create.
	If command queue thread stack size is only 256k byte, pthread_create function failed with return value EINVAL.

	The above information is verified by this test:
	I printed out the address of a __thread variable. Then I printed out an address of a local variable. I confirmed both variables are in the same memory segment according to /proc/id/maps. This memory segment is same size of CQ_THREAD_STACK_SIZE and changed with this environment variable.

	The __thread variable is 286.6K byte away from the bottom of the stack but still inside the stack.

	I have added printf to verify function guessTlsSize can guess tlsSize correctly. And pthread_create succeeded in first invocation with tls size adjustment.

	Tests:
	1. Test houdini - PASS
	2. http://ocltc.amd.com:8111/viewModification.html?modId=128021&personal=true&tab=vcsModificationBuilds

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

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/os/os_posix.cpp#47 edit


[ROCm/clr commit: be8023429a]
2019-10-25 17:08:39 -05:00
foreman 3888033482 P4 to Git Change 2019704 by cpaquot@cpaquot-ocl-lc-lnx on 2019/10/25 14:07:38
SWDEV-208972 - [HIP] Enable LOG_LEVEL in release bits.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/debug.hpp#9 edit
... //depot/stg/opencl/drivers/opencl/runtime/utils/flags.hpp#322 edit


[ROCm/clr commit: 0ce1ad6acb]
2019-10-25 14:17:24 -04:00
Evgeny Mankov bcc9d88b20 [HIPIFY][tests] Rename the ambiguous call as well
[ROCm/clr commit: f68bee02f5]
2019-10-25 16:07:31 +03:00
Evgeny Mankov 91732f98c0 [HIPIFY][tests] Fix ambiguous call to cusparseGetErrorString declared in cusparse.h
[ROCm/clr commit: 9529e1d91d]
2019-10-25 16:04:20 +03:00
Anusha Godavarthy Surya dfa019bdf6 Merge branch 'master' into tex_unbind_issue_fix
[ROCm/clr commit: 9332a39838]
2019-10-25 15:54:25 +05:30
amd-lthakur 6bb2cba965 Excluded the test case for nvcc platform
[ROCm/clr commit: 626cd5d07a]
2019-10-25 15:52:11 +05:30