Commit Graph

12733 Commits

Author SHA1 Message Date
foreman 7748e50666 P4 to Git Change 1780469 by chui@ocl-promo-incrementor on 2019/05/09 03:00:04
SWDEV-2 - Change OpenCL version number from 2893 to 2894.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2641 edit
2019-05-09 03:12:44 -04:00
Maneesh Gupta 4b38188e1e [dtests] Add hipModule test to unit tests
Change-Id: I1dac38f8580265e2e9c82d88e4f070a2ff87f60b
2019-05-09 11:36:46 +05:30
Maneesh Gupta dac20b7736 [hit] Add support for BUILD_CMD 2019-05-09 11:36:26 +05:30
Maneesh Gupta db52b0f60f [hit] Remove CUSTOM_CMD
Change-Id: Ia156fe6aab9cfcc11284823ea5131e33eaf962bc
2019-05-09 09:59:18 +05:30
Maneesh Gupta 53dd1df3fa [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074
2019-05-09 09:59:18 +05:30
foreman 699a12bfa2 P4 to Git Change 1780358 by gandryey@gera-win10 on 2019/05/08 18:46:22
SWDEV-79445 - OCL generic changes and code clean-up
	- Run google autoformat over the PAL backend. It will allow to enable autoformat in VS for the future changes.
	- No functional changes

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palappprofile.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palappprofile.hpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.cpp#29 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palblit.hpp#8 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palconstbuf.cpp#12 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palconstbuf.hpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palcounters.cpp#20 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palcounters.hpp#10 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldebugger.hpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldebugmanager.cpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldefs.hpp#52 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#133 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.hpp#37 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldeviced3d10.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldeviced3d11.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldeviced3d9.cpp#3 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevicegl.cpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.cpp#13 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palgpuopen.hpp#9 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.cpp#78 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palkernel.hpp#28 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.cpp#24 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palmemory.hpp#11 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprintf.hpp#6 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.cpp#93 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palprogram.hpp#38 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.cpp#73 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palresource.hpp#27 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#79 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.hpp#22 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paltimestamp.hpp#4 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.cpp#132 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palvirtual.hpp#60 edit
2019-05-08 19:22:02 -04:00
foreman 54021e0264 P4 to Git Change 1780298 by gandryey@gera-win10 on 2019/05/08 17:04:56
SWDEV-188605 - [CQE OCL][QR][mGPU][Vega][DTB-Blocker][Windows][RS5] Observed Failure of OCLP2PBuffer sub test of ocltst_runtime both 64 &32 bit due to faultyCL 1775995
	- Count offline GPU devices during PAL device detection

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/paldevice.cpp#132 edit
2019-05-08 17:16:07 -04:00
Evgeny Mankov b6ff82a2e6 Merge pull request #1090 from emankov/master
[HIPIFY][python] Initial support of hipify-python generation from hipify-clang
2019-05-08 19:12:08 +03:00
Evgeny Mankov 0f4affde9c [HIPIFY][python] Initial support of hipify-python generation from hipify-clang
+ Only a generation of transformation map of CUDA entities is implemented.
+ 2 hipify-clang options are added: -python, -o-python-map-dir.
+ Explicitly set -roc option for cuda_to_hip_mappings.py generation.
+ Generated file already might be used by pytorch team.
2019-05-08 19:08:55 +03:00
Evgeny Mankov c7243ebdae Merge pull request #1089 from emankov/master
[HIPIFY][perl] Support of hipify-perl generation from hipify-clang: n…
2019-05-08 15:59:45 +03:00
Evgeny Mankov 82efa64f55 [HIPIFY][perl] Support of hipify-perl generation from hipify-clang: next steps
+ Generate transformation map sorted by entity type.
+ Add a generation of supported header files.
2019-05-08 15:25:06 +03:00
foreman 0449bf058e P4 to Git Change 1779910 by chui@ocl-promo-incrementor on 2019/05/08 03:00:03
SWDEV-2 - Change OpenCL version number from 2892 to 2893.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2640 edit
2019-05-08 05:12:29 -04:00
Maneesh Gupta b3c159344e Merge pull request #1088 from ROCm-Developer-Tools/mangupta-patch-1
[ci] Enable tests on ROCm 2.4
2019-05-08 12:44:02 +05:30
Maneesh Gupta a78e719835 [ci] Enable tests on ROCm 2.4 2019-05-08 12:07:33 +05:30
Jenkins 5dfa7129e7 Merge 'master' into 'amd-master'
Change-Id: I0b8ccb710d733f41d62227750daf4adc38f401da
2019-05-07 12:15:02 -07:00
Evgeny Mankov df8909d73d Merge pull request #1085 from emankov/master
[HIPIFY][perl] Initial support of hipify-perl generation from hipify-clang
2019-05-07 17:30:39 +03:00
Evgeny Mankov 849155d865 [HIPIFY][perl] Initial support of hipify-perl generation from hipify-clang
+ Only a generation of transformation map of CUDA entities supported by HIP is implemented.
+ 3 hipify-clang options are added: -perl, -o-perl-map, -o-perl-map-dir.
+ OptionsParser mode is changed from OneOrMore to Optional to support hipify-perl generation without actual hipification.
+ Add explicit control of source files specification absence in case of no perl generation.
2019-05-07 17:27:34 +03:00
Maneesh Gupta c6cf2a9e26 Merge pull request #1082 from gargrahul/fix_hipmemcpy_symbol_nvcc
Fix symbol address issue on NVCC path
2019-05-07 16:17:01 +05:30
Maneesh Gupta c6c5e4cee8 Merge pull request #1081 from mangupta/swdev-181624
Implement hipExtGetLinkTypeAndHopCount for ROCm devices
2019-05-07 16:15:41 +05:30
Maneesh Gupta 51e158c633 Merge pull request #1075 from mhbliao/hliao/master/test_fix2
[test] Add device variant of `std::declval`.
2019-05-07 16:15:01 +05:30
Maneesh Gupta 7f759750d1 Merge pull request #1074 from mhbliao/hliao/master/test_fix
[test] Use explicit cast for address space cast.
2019-05-07 16:09:15 +05:30
Maneesh Gupta d71afeccc8 Merge pull request #1073 from kpyzhov/multi-thread-device-test
hipMultiThreadDevice test: Reduced maximum number of created HIP stre…
2019-05-07 16:08:37 +05:30
Maneesh Gupta 8f352427f4 Merge pull request #1072 from kpyzhov/master
Refined hipSetDevice test.
2019-05-07 16:07:36 +05:30
Maneesh Gupta 0fffbbe67a Merge pull request #1069 from mhbliao/hliao/master/test_cleanup
[test] Remove unused common routines.
2019-05-07 16:02:57 +05:30
Maneesh Gupta 11972049c6 Merge pull request #1068 from mhbliao/hliao/master/dev_vec_func
[devfunc] Add necessary `__device__` and `__host__` attributes.
2019-05-07 16:01:48 +05:30
Yaxun (Sam) Liu 0b43b24d3f Add documentation for supported clang options (#1065)
* Add documentation for supported clang options

* Fix typo
2019-05-07 15:59:40 +05:30
wkwchau ebf986dcee Return hipErrorInsufficientDriver status when CPU device not found (#1064)
* Return hipErrorInsufficientDriver status when CPU device not found - no exception thrown

* Return hipErrorInsufficientDriver status when CPU device not found
2019-05-07 15:58:25 +05:30
Maneesh Gupta 46ac83a429 Merge pull request #1061 from mhbliao/hliao/master/hipcc
[hip] Repace `--rpath` with `--rpath-link`
2019-05-07 15:57:57 +05:30
Maneesh Gupta 1a1feb600f Merge pull request #1054 from ssahasra/dry
minor cleanup: eliminate repetition
2019-05-07 15:57:46 +05:30
foreman c1cb3fd812 P4 to Git Change 1779175 by chui@ocl-promo-incrementor on 2019/05/07 03:00:06
SWDEV-2 - Change OpenCL version number from 2891 to 2892.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2639 edit
2019-05-07 03:17:33 -04:00
Michael LIAO de768c22ae [hip] Add API hipExtModuleLaunchKernel in HIP runtime 2019-05-06 21:20:28 -04:00
Rahul Garg 3be54a903c Maintain HIP_VISIBLE_DEVICES for kernel launch 2019-05-07 05:09:02 +05:30
Rahul Garg 6cbc70d238 Fix symbol address issue on NVCC path 2019-05-07 03:59:43 +05:30
foreman 9aecfde4a5 P4 to Git Change 1778985 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/06 17:21:57
SWDEV-188668 - [HIP] Implemented hipExtModuleLaunchKernel. Ignoring the flag for now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#15 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#25 edit
2019-05-06 18:02:54 -04:00
foreman 84d257cf3b P4 to Git Change 1778971 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/06 17:03:12
SWDEV-187125 - [HIP] Protect hip::Event with lock and add threadId to logs.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.cpp#9 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_event.hpp#3 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_internal.hpp#30 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_module.cpp#24 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#18 edit
2019-05-06 17:43:06 -04:00
foreman 0da954f20e P4 to Git Change 1778949 by michliao@hliao-dev-00-hip.rocm-workspace on 2019/05/06 16:36:53
SWDEV-144570 - Fix build failure after switching to gcc-7

	- Hex representation of float needs gnu++11. We'd better not relying on
	  that. Change the float in hex format into alternative representation.

	RBT: http://ocltc.amd.com/reviews/r/17300/

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#29 edit
2019-05-06 17:20:00 -04:00
Maneesh Gupta 2f43f110d9 Implement hipExtGetLinkTypeAndHopCount for ROCm devices
Change-Id: Ie5bb4f640ac6d189c7fceeab22627a7494fd10bd
2019-05-06 15:54:31 +05:30
foreman e37953f099 P4 to Git Change 1778587 by chui@ocl-promo-incrementor on 2019/05/06 03:00:17
SWDEV-2 - Change OpenCL version number from 2890 to 2891.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2638 edit
2019-05-06 03:55:23 -04:00
foreman 6a217d1ea0 P4 to Git Change 1778428 by chui@ocl-promo-incrementor on 2019/05/05 17:08:51
SWDEV-2 - Change OpenCL version number from 2889 to 2890.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2637 edit
2019-05-05 17:17:25 -04:00
Michael LIAO 32f69c8bc4 [test] Add device variant of std::declval.
- Current clang disallows any invocation of wrong-side functions even
  under context with type-inspection only. Work around that by adding a
  variant of `std::decl` with `__device__` attribute.
2019-05-03 15:58:31 -04:00
Michael LIAO a27877794f [test] Use explicit cast for address space cast. 2019-05-03 14:56:00 -04:00
Maneesh Gupta 2eafa5dcf9 Merge pull request #1062 from mhbliao/hliao/master/icmp
[hip] Re-implement ballot using AMDGCN builtins
2019-05-03 17:48:19 +05:30
Maneesh Gupta ad070d4da5 Merge pull request #1058 from mhbliao/hliao/master/devfunc
[Device Function] Fix implementation
2019-05-03 17:47:51 +05:30
Konstantin Pyzhov e04e408a37 hipMultiThreadDevice test: Reduced maximum number of created HIP streams on Windows. 2019-05-03 05:43:30 -04:00
Konstantin Pyzhov 29fd3812e5 Refined hipSetDevice test. 2019-05-03 05:39:45 -04:00
foreman 0f72983a61 P4 to Git Change 1777875 by chui@ocl-promo-incrementor on 2019/05/03 03:00:03
SWDEV-2 - Change OpenCL version number from 2888 to 2889.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2636 edit
2019-05-03 03:09:51 -04:00
foreman 441d322dc8 P4 to Git Change 1777625 by asalmanp@asalmanp-ocl-stg on 2019/05/02 14:31:30
SWDEV-132899 - [OCL][GFX10] Add support for Navi12Lite

	ReviewBaordURL = http://ocltc.amd.com/reviews/r/17281/

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palbedefs#37 edit
... //depot/stg/opencl/drivers/opencl/runtime/device/pal/palsettings.cpp#78 edit
2019-05-02 15:20:45 -04:00
Michael LIAO aad19f6171 [test] Remove unused common routines.
- Remove used common routines, which variadic functions, not supported
  feature, are used.
2019-05-02 12:34:07 -04:00
foreman b6712eb2ed P4 to Git Change 1777295 by chui@ocl-promo-incrementor on 2019/05/02 03:00:03
SWDEV-2 - Change OpenCL version number from 2887 to 2888.

Affected files ...

... //depot/stg/opencl/drivers/opencl/runtime/utils/versions.hpp#2635 edit
2019-05-02 03:13:01 -04:00
Michael LIAO a9f90713f3 [devfunc] Add necessary __device__ and __host__ attributes.
- Minor clean up to keep consistent function declaration.
2019-05-01 22:26:35 -04:00