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

5142 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
foreman 09deb3b408 P4 to Git Change 1780704 by yaxunl@yaxunl-lc10 on 2019/05/09 13:26:13 
SWDEV-145570 - Fix device name mismatch for gfx906.

	For now hip-clang can only emits gfx906 ISA with conservative configurations, i.e. with ecc on and xnack on, therefore it is always gfx906. It is still under discussion how to encode the target id for xnack off or ecc off.

	Therefore, the reasonable solution for now is just allow code object marked as gfx906 to be loaded on any device name that starts with gfx906. We will have more detailed control once hip-clang is able to emit code object for gfx906 with ecc off or xnack off.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_platform.cpp#30 edit


[ROCm/hip commit: 1d60371d01]
 2019-05-09 14:19:54 -04:00
Maneesh Gupta 1f94348f2e Merge pull request #1084 from mhbliao/hliao/master/api_ext 
[hip] Add API `hipExtModuleLaunchKernel` in HIP runtime

[ROCm/hip commit: 5b607e14a6]
 2019-05-09 18:26:31 +05:30
Maneesh Gupta 242aeaf133 [dtests] Fix hipModule test for nvcc path 
Change-Id: If918b87b848a825242e06b0d552a7be188a1c4b6


[ROCm/hip commit: 88abfde2f8]
 2019-05-09 18:17:19 +05:30
Maneesh Gupta 8dd98b8c82 [dtests] Add complex_loading_behavior test 
Change-Id: Iadf135cb727a1a3761abef20336d652b159c7dcd


[ROCm/hip commit: eb637766b9]
 2019-05-09 18:03:42 +05:30
Maneesh Gupta 09f8c228cf [dtests] Add hipModule test to unit tests 
Change-Id: I1dac38f8580265e2e9c82d88e4f070a2ff87f60b


[ROCm/hip commit: 79843f3b12]
 2019-05-09 11:36:46 +05:30
Maneesh Gupta ba620dfbe4 [hit] Add support for BUILD_CMD 
[ROCm/hip commit: 49a2d785d0]
 2019-05-09 11:36:26 +05:30
Maneesh Gupta 4b274cc6f8 [hit] Remove CUSTOM_CMD 
Change-Id: Ia156fe6aab9cfcc11284823ea5131e33eaf962bc


[ROCm/hip commit: 622ea32964]
 2019-05-09 09:59:18 +05:30
Maneesh Gupta fa07d40cdd [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED 
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074


[ROCm/hip commit: 9f2d1453fb]
 2019-05-09 09:59:18 +05:30
Evgeny Mankov 9ccffdd48b Merge pull request #1090 from emankov/master 
[HIPIFY][python] Initial support of hipify-python generation from hipify-clang

[ROCm/hip commit: bfb0524e13]
 2019-05-08 19:12:08 +03:00
Evgeny Mankov cabe0bb799 [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.


[ROCm/hip commit: 6b370e7743]
 2019-05-08 19:08:55 +03:00
Evgeny Mankov 8d702eb417 Merge pull request #1089 from emankov/master 
[HIPIFY][perl] Support of hipify-perl generation from hipify-clang: n…

[ROCm/hip commit: 86fe1d3f1a]
 2019-05-08 15:59:45 +03:00
Evgeny Mankov aea6e34875 [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.


[ROCm/hip commit: 9ddc316fa7]
 2019-05-08 15:25:06 +03:00
Maneesh Gupta 8af2fbb2fa Merge pull request #1088 from ROCm-Developer-Tools/mangupta-patch-1 
[ci] Enable tests on ROCm 2.4

[ROCm/hip commit: 450c7ab295]
 2019-05-08 12:44:02 +05:30
Maneesh Gupta 816e86fc24 [ci] Enable tests on ROCm 2.4 
[ROCm/hip commit: 07bd3ecfad]
 2019-05-08 12:07:33 +05:30
Jenkins 62abc6d805 Merge 'master' into 'amd-master' 
Change-Id: I0b8ccb710d733f41d62227750daf4adc38f401da


[ROCm/hip commit: 2b8431f59b]
 2019-05-07 12:15:02 -07:00
Evgeny Mankov ef268f7268 Merge pull request #1085 from emankov/master 
[HIPIFY][perl] Initial support of hipify-perl generation from hipify-clang

[ROCm/hip commit: 26d4677091]
 2019-05-07 17:30:39 +03:00
Evgeny Mankov b66ecc6596 [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.


[ROCm/hip commit: 5a3d33a338]
 2019-05-07 17:27:34 +03:00
Maneesh Gupta 049c0d84bb Merge pull request #1082 from gargrahul/fix_hipmemcpy_symbol_nvcc 
Fix symbol address issue on NVCC path

[ROCm/hip commit: 7264f6b64e]
 2019-05-07 16:17:01 +05:30
Maneesh Gupta 36d37296d5 Merge pull request #1081 from mangupta/swdev-181624 
Implement hipExtGetLinkTypeAndHopCount for ROCm devices

[ROCm/hip commit: d5abe65668]
 2019-05-07 16:15:41 +05:30
Maneesh Gupta 5f54b7f9a6 Merge pull request #1075 from mhbliao/hliao/master/test_fix2 
[test] Add device variant of `std::declval`.

[ROCm/hip commit: f931152280]
 2019-05-07 16:15:01 +05:30
Maneesh Gupta 13d2c76d3d Merge pull request #1074 from mhbliao/hliao/master/test_fix 
[test] Use explicit cast for address space cast.

[ROCm/hip commit: 1d4941e487]
 2019-05-07 16:09:15 +05:30
Maneesh Gupta fb8d225e25 Merge pull request #1073 from kpyzhov/multi-thread-device-test 
hipMultiThreadDevice test: Reduced maximum number of created HIP stre…

[ROCm/hip commit: 98ab402fcb]
 2019-05-07 16:08:37 +05:30
Maneesh Gupta d6e2d71d99 Merge pull request #1072 from kpyzhov/master 
Refined hipSetDevice test.

[ROCm/hip commit: fea21dc6d5]
 2019-05-07 16:07:36 +05:30
Maneesh Gupta b6393eb059 Merge pull request #1069 from mhbliao/hliao/master/test_cleanup 
[test] Remove unused common routines.

[ROCm/hip commit: 730763c817]
 2019-05-07 16:02:57 +05:30
Maneesh Gupta 0527ac9038 Merge pull request #1068 from mhbliao/hliao/master/dev_vec_func 
[devfunc] Add necessary `__device__` and `__host__` attributes.

[ROCm/hip commit: d82d6b499e]
 2019-05-07 16:01:48 +05:30
Yaxun (Sam) Liu 6f69a5d16e Add documentation for supported clang options (#1065) 
* Add documentation for supported clang options

* Fix typo


[ROCm/hip commit: 669d177079]
 2019-05-07 15:59:40 +05:30
wkwchau 236834c679 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


[ROCm/hip commit: 29b3b46b42]
 2019-05-07 15:58:25 +05:30
Maneesh Gupta 1690053091 Merge pull request #1061 from mhbliao/hliao/master/hipcc 
[hip] Repace `--rpath` with `--rpath-link`

[ROCm/hip commit: 7eff09edad]
 2019-05-07 15:57:57 +05:30
Maneesh Gupta 892d8f8feb Merge pull request #1054 from ssahasra/dry 
minor cleanup: eliminate repetition

[ROCm/hip commit: 927fd0a4bc]
 2019-05-07 15:57:46 +05:30
Michael LIAO 0c41f2298d [hip] Add API hipExtModuleLaunchKernel in HIP runtime 
[ROCm/hip commit: 5150f1297a]
 2019-05-06 21:20:28 -04:00
Rahul Garg f8386e274a Maintain HIP_VISIBLE_DEVICES for kernel launch 
[ROCm/hip commit: 620a07102d]
 2019-05-07 05:09:02 +05:30
Rahul Garg d700f67b79 Fix symbol address issue on NVCC path 
[ROCm/hip commit: e906bd69ce]
 2019-05-07 03:59:43 +05:30
foreman e94aa7fb8c 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


[ROCm/hip commit: 1e856beba9]
 2019-05-06 18:02:54 -04:00
foreman dcc5c0c214 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


[ROCm/hip commit: d41643c39f]
 2019-05-06 17:43:06 -04:00
foreman cf855653b9 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


[ROCm/hip commit: 09920e6024]
 2019-05-06 17:20:00 -04:00
Maneesh Gupta f7eaff474b Implement hipExtGetLinkTypeAndHopCount for ROCm devices 
Change-Id: Ie5bb4f640ac6d189c7fceeab22627a7494fd10bd


[ROCm/hip commit: 035ef04e1f]
 2019-05-06 15:54:31 +05:30
Michael LIAO d71327882c [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.


[ROCm/hip commit: 4fbfb646f6]
 2019-05-03 15:58:31 -04:00
Michael LIAO cb55dc384a [test] Use explicit cast for address space cast. 
[ROCm/hip commit: 2746d95906]
 2019-05-03 14:56:00 -04:00
Maneesh Gupta f49a4c6d89 Merge pull request #1062 from mhbliao/hliao/master/icmp 
[hip] Re-implement ballot using AMDGCN builtins

[ROCm/hip commit: 117bdd8774]
 2019-05-03 17:48:19 +05:30
Maneesh Gupta f42dc08384 Merge pull request #1058 from mhbliao/hliao/master/devfunc 
[Device Function] Fix implementation

[ROCm/hip commit: 37d01a7da9]
 2019-05-03 17:47:51 +05:30
Konstantin Pyzhov ae391b3211 hipMultiThreadDevice test: Reduced maximum number of created HIP streams on Windows. 
[ROCm/hip commit: e29c9d50a6]
 2019-05-03 05:43:30 -04:00
Konstantin Pyzhov 45eb04ea5c Refined hipSetDevice test. 
[ROCm/hip commit: 069fb7e486]
 2019-05-03 05:39:45 -04:00
Michael LIAO b7ae0b6442 [test] Remove unused common routines. 
- Remove used common routines, which variadic functions, not supported
  feature, are used.


[ROCm/hip commit: 16a27e06ee]
 2019-05-02 12:34:07 -04:00
Michael LIAO 2c2b897902 [devfunc] Add necessary __device__ and __host__ attributes. 
- Minor clean up to keep consistent function declaration.


[ROCm/hip commit: 44692978fe]
 2019-05-01 22:26:35 -04:00
foreman 8c0263f6c5 P4 to Git Change 1777225 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 18:47:25 
SWDEV-188233 - [HIP] Implemented hipGetChannelDesc.

Affected files ...

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


[ROCm/hip commit: 3ad9c3f984]
 2019-05-01 19:53:29 -04:00
foreman 486506f113 P4 to Git Change 1777158 by cpaquot@cpaquot-ocl-lc-lnx on 2019/05/01 17:12:01 
SWDEV-188219 - [HIP] Add hipStreamCreateWithPriority. NOP right now.

Affected files ...

... //depot/stg/opencl/drivers/opencl/api/hip/hip_device_runtime.cpp#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.def.in#13 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_hcc.map.in#14 edit
... //depot/stg/opencl/drivers/opencl/api/hip/hip_stream.cpp#17 edit
... //depot/stg/opencl/drivers/opencl/runtime/platform/commandqueue.hpp#21 edit


[ROCm/hip commit: ba93e1ae21]
 2019-05-01 18:43:47 -04:00
Evgeny Mankov 12d4111e16 Merge pull request #1063 from emankov/master 
[HIPIFY][tests] Add cuSPARSE CSR-BCSR-SPMV-conversions example

[ROCm/hip commit: 4e09081554]
 2019-04-30 17:40:05 +03:00
emankov 1f57ee6125 [HIPIFY][tests] Add cuSPARSE CSR-BCSR-SPMV-conversions example 
[ROCm/hip commit: e3082f5142]
 2019-04-30 17:37:34 +03:00
Michael LIAO e637e72364 [Device Function] Fix implementation of __bitinsert_u64 
- It's a common mistake by assuming 1 << shamt would be promoted to
  64-bit, if shamt is a 64-bit integer. That's not the case. Replace
  that left shift to a 64-bit one to ensure it won't fall into undefined
  behavior.
- Fix the host-side implementation as well for device function testing.


[ROCm/hip commit: 9bd2d5746d]
 2019-04-30 08:59:13 -04:00
Michael LIAO cc4de2bc28 [devfunc] Re-implement ballot using AMDGCN builtins 
- As the signature of `amdgcn.icmp` is changed for next-gen chip, using
  clang builtins is portable way to hide that details.


[ROCm/hip commit: a64637da2c]
 2019-04-29 17:21:25 -04:00