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

5942 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
foreman e5eb4fe5a9 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/clr commit: ed092053e1]
 2019-05-09 14:19:54 -04:00
Maneesh Gupta 54f932e569 Merge pull request #1084 from mhbliao/hliao/master/api_ext 
[hip] Add API `hipExtModuleLaunchKernel` in HIP runtime

[ROCm/clr commit: e78a09c041]
 2019-05-09 18:26:31 +05:30
Maneesh Gupta 3d098c6a1c [dtests] Fix hipModule test for nvcc path 
Change-Id: If918b87b848a825242e06b0d552a7be188a1c4b6


[ROCm/clr commit: 6e573ba430]
 2019-05-09 18:17:19 +05:30
Maneesh Gupta 3b75006961 [dtests] Add complex_loading_behavior test 
Change-Id: Iadf135cb727a1a3761abef20336d652b159c7dcd


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


[ROCm/clr commit: 4b38188e1e]
 2019-05-09 11:36:46 +05:30
Maneesh Gupta 1b896685a3 [hit] Add support for BUILD_CMD 
[ROCm/clr commit: dac20b7736]
 2019-05-09 11:36:26 +05:30
Maneesh Gupta 68cf672441 [hit] Remove CUSTOM_CMD 
Change-Id: Ia156fe6aab9cfcc11284823ea5131e33eaf962bc


[ROCm/clr commit: db52b0f60f]
 2019-05-09 09:59:18 +05:30
Maneesh Gupta 74110bbd43 [hit] Rename RUN -> TEST & RUN_NAMED -> TEST_NAMED 
Change-Id: I75e24f15129973cee15fc9dac65d678bd2172074


[ROCm/clr commit: 53dd1df3fa]
 2019-05-09 09:59:18 +05:30
Evgeny Mankov 3e3140c9f7 Merge pull request #1090 from emankov/master 
[HIPIFY][python] Initial support of hipify-python generation from hipify-clang

[ROCm/clr commit: b6ff82a2e6]
 2019-05-08 19:12:08 +03:00
Evgeny Mankov 197affbe2a [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/clr commit: 0f4affde9c]
 2019-05-08 19:08:55 +03:00
Evgeny Mankov d1661fa10d Merge pull request #1089 from emankov/master 
[HIPIFY][perl] Support of hipify-perl generation from hipify-clang: n…

[ROCm/clr commit: c7243ebdae]
 2019-05-08 15:59:45 +03:00
Evgeny Mankov 51fe4163c0 [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/clr commit: 82efa64f55]
 2019-05-08 15:25:06 +03:00
Maneesh Gupta d5f6a19543 Merge pull request #1088 from ROCm-Developer-Tools/mangupta-patch-1 
[ci] Enable tests on ROCm 2.4

[ROCm/clr commit: b3c159344e]
 2019-05-08 12:44:02 +05:30
Maneesh Gupta 63e2d774a0 [ci] Enable tests on ROCm 2.4 
[ROCm/clr commit: a78e719835]
 2019-05-08 12:07:33 +05:30
Jenkins 0c723af675 Merge 'master' into 'amd-master' 
Change-Id: I0b8ccb710d733f41d62227750daf4adc38f401da


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

[ROCm/clr commit: df8909d73d]
 2019-05-07 17:30:39 +03:00
Evgeny Mankov 413e0f97fb [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/clr commit: 849155d865]
 2019-05-07 17:27:34 +03:00
Maneesh Gupta 301a9292ff Merge pull request #1082 from gargrahul/fix_hipmemcpy_symbol_nvcc 
Fix symbol address issue on NVCC path

[ROCm/clr commit: c6cf2a9e26]
 2019-05-07 16:17:01 +05:30
Maneesh Gupta 30c7ed3e28 Merge pull request #1081 from mangupta/swdev-181624 
Implement hipExtGetLinkTypeAndHopCount for ROCm devices

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

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

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

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

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

[ROCm/clr commit: 0fffbbe67a]
 2019-05-07 16:02:57 +05:30
Maneesh Gupta 46d0385435 Merge pull request #1068 from mhbliao/hliao/master/dev_vec_func 
[devfunc] Add necessary `__device__` and `__host__` attributes.

[ROCm/clr commit: 11972049c6]
 2019-05-07 16:01:48 +05:30
Yaxun (Sam) Liu 01ef00b568 Add documentation for supported clang options (#1065) 
* Add documentation for supported clang options

* Fix typo


[ROCm/clr commit: 0b43b24d3f]
 2019-05-07 15:59:40 +05:30
wkwchau 7eaaf6f1ae 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/clr commit: ebf986dcee]
 2019-05-07 15:58:25 +05:30
Maneesh Gupta c6e14467f7 Merge pull request #1061 from mhbliao/hliao/master/hipcc 
[hip] Repace `--rpath` with `--rpath-link`

[ROCm/clr commit: 46ac83a429]
 2019-05-07 15:57:57 +05:30
Maneesh Gupta 0364d5c710 Merge pull request #1054 from ssahasra/dry 
minor cleanup: eliminate repetition

[ROCm/clr commit: 1a1feb600f]
 2019-05-07 15:57:46 +05:30
Michael LIAO d94d566410 [hip] Add API hipExtModuleLaunchKernel in HIP runtime 
[ROCm/clr commit: de768c22ae]
 2019-05-06 21:20:28 -04:00
Rahul Garg 3f65bec096 Maintain HIP_VISIBLE_DEVICES for kernel launch 
[ROCm/clr commit: 3be54a903c]
 2019-05-07 05:09:02 +05:30
Rahul Garg bf3bafb9f5 Fix symbol address issue on NVCC path 
[ROCm/clr commit: 6cbc70d238]
 2019-05-07 03:59:43 +05:30
foreman 0e562f5290 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/clr commit: 9aecfde4a5]
 2019-05-06 18:02:54 -04:00
foreman 4f37e552ad 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/clr commit: 84d257cf3b]
 2019-05-06 17:43:06 -04:00
foreman be2ca7d2ef 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/clr commit: 0da954f20e]
 2019-05-06 17:20:00 -04:00
Maneesh Gupta f657eba4a5 Implement hipExtGetLinkTypeAndHopCount for ROCm devices 
Change-Id: Ie5bb4f640ac6d189c7fceeab22627a7494fd10bd


[ROCm/clr commit: 2f43f110d9]
 2019-05-06 15:54:31 +05:30
Michael LIAO f644d4daaa [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/clr commit: 32f69c8bc4]
 2019-05-03 15:58:31 -04:00
Michael LIAO fa74e75fc1 [test] Use explicit cast for address space cast. 
[ROCm/clr commit: a27877794f]
 2019-05-03 14:56:00 -04:00
Maneesh Gupta 13b13c3493 Merge pull request #1062 from mhbliao/hliao/master/icmp 
[hip] Re-implement ballot using AMDGCN builtins

[ROCm/clr commit: 2eafa5dcf9]
 2019-05-03 17:48:19 +05:30
Maneesh Gupta c73c864fdf Merge pull request #1058 from mhbliao/hliao/master/devfunc 
[Device Function] Fix implementation

[ROCm/clr commit: ad070d4da5]
 2019-05-03 17:47:51 +05:30
Konstantin Pyzhov 1be1dd207a hipMultiThreadDevice test: Reduced maximum number of created HIP streams on Windows. 
[ROCm/clr commit: e04e408a37]
 2019-05-03 05:43:30 -04:00
Konstantin Pyzhov b2e3880696 Refined hipSetDevice test. 
[ROCm/clr commit: 29fd3812e5]
 2019-05-03 05:39:45 -04:00
Michael LIAO 9823184397 [test] Remove unused common routines. 
- Remove used common routines, which variadic functions, not supported
  feature, are used.


[ROCm/clr commit: aad19f6171]
 2019-05-02 12:34:07 -04:00
Michael LIAO 08fa23f774 [devfunc] Add necessary __device__ and __host__ attributes. 
- Minor clean up to keep consistent function declaration.


[ROCm/clr commit: a9f90713f3]
 2019-05-01 22:26:35 -04:00
foreman f567589672 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/clr commit: b39d02b166]
 2019-05-01 19:53:29 -04:00
foreman 2d2e37205f 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/clr commit: ef45e9ab42]
 2019-05-01 18:43:47 -04:00
Evgeny Mankov 86c59f7bc9 Merge pull request #1063 from emankov/master 
[HIPIFY][tests] Add cuSPARSE CSR-BCSR-SPMV-conversions example

[ROCm/clr commit: be1e22ffe3]
 2019-04-30 17:40:05 +03:00
emankov c27f0b952e [HIPIFY][tests] Add cuSPARSE CSR-BCSR-SPMV-conversions example 
[ROCm/clr commit: d5c3e5ea71]
 2019-04-30 17:37:34 +03:00
Michael LIAO eb43303d0b [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/clr commit: 2380eb8ecc]
 2019-04-30 08:59:13 -04:00
Michael LIAO e8de293fc5 [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/clr commit: a7a4d80f54]
 2019-04-29 17:21:25 -04:00