Commit Graph

3610 Commits

Author SHA1 Message Date
Siu Chi Chan 2bc9455928 fix breakage due to compiling in C++17 2019-05-24 17:27:58 -04:00
Siu Chi Chan 1fb9ab2d44 replace std::vector for kernarg 2019-05-24 17:27:43 -04:00
Siu Chi Chan 1a2d332e76 move executable_cache into program_state.cpp 2019-05-24 17:27:25 -04:00
Siu Chi Chan e2c0122892 remove executables() from program_state 2019-05-24 17:27:01 -04:00
Siu Chi Chan 6852be819f moving agent_globals_impl into hip_module 2019-05-24 16:43:38 -04:00
Evgeny Mankov 9fc9a6c7ab Merge pull request #1137 from emankov/LLVM
[HIPIFY][LLVMCompat] Support of upcoming LLVM 9.0.0
2019-05-24 15:16:27 +03:00
Evgeny Mankov c1ac414f14 [HIPIFY][LLVMCompat] Support of upcoming LLVM 9.0.0 2019-05-24 15:14:14 +03:00
Maneesh Gupta 68d30cd7e4 Merge pull request #1136 from yxsamliu/fix-rdc
Fix device lib path for hip-clang.
2019-05-24 14:16:30 +05:30
Maneesh Gupta 98d93eef6b Merge pull request #1129 from b-sumner/master
Update kernel language documentation
2019-05-24 14:16:21 +05:30
Maneesh Gupta f03a8cc1b0 Merge pull request #1128 from aaronenyeshi/fix-smid-func
Fix bug in __smid not setting correct size
2019-05-24 14:16:12 +05:30
Maneesh Gupta f30446c4bc Merge pull request #1124 from kpyzhov/hipModule-test
Updated kernel binary file for hipModule test.
2019-05-24 14:16:03 +05:30
Maneesh Gupta c289973030 Merge pull request #1121 from kpyzhov/hipStreamSync2-test
Disable hipStreamSync2 test for hip-clang.
2019-05-24 14:15:54 +05:30
Maneesh Gupta 30ccb66949 Merge pull request #1117 from aaronenyeshi/fix-exit-code-hipcc
Fix hipcc exit code when failing
2019-05-24 14:15:44 +05:30
Yaxun Sam Liu 6360570532 Fix device lib path for hip-clang.
We now always need device lib path when compiling and not need it at linking.
2019-05-23 15:11:02 -04:00
Evgeny Mankov acaea5d7b2 Merge pull request #1132 from emankov/master
[HIPIFY] Add device texture fetch functions support
2019-05-23 12:48:53 +03:00
Evgeny Mankov 7db992cf44 [HIPIFY] Add device texture fetch functions support
+ Add a corresponding reverse engineered sample tex2dKernel with texture template
2019-05-23 12:47:08 +03:00
Evgeny Mankov c3606891a9 Merge pull request #1127 from emankov/master
[HIP][HIPIFY] Make hipMemcpyParam2D coherent with cuMemcpy2D
2019-05-23 10:45:14 +03:00
Brian Sumner e481012f43 Update kernel language documentation 2019-05-22 12:30:00 -07:00
Aaron Enye Shi 2b11a8bf0c Fix bug in __smid not setting correct size
The SZ field should minus by 1 since SIZE range is 1..32. Also add comments that results may vary.
2019-05-22 19:20:09 +00:00
Evgeny Mankov 49b9df7a9e [HIP] fix typo in #1127 2019-05-22 20:48:18 +03:00
Evgeny Mankov 6806ab6745 [HIP] fix nvcc path break in #1127 2019-05-22 20:04:45 +03:00
Evgeny Mankov 9cb3e9aa5e [HIP][HIPIFY] Make hipMemcpyParam2D coherent with cuMemcpy2D
+ Makes hip_Memcpy2D struct compatible with CUDA_MEMCPY2D struct
+ Add hipMemcpyParam2D support in nvcc fallback path
+ Update hipify-clang, tests and docs accordingly
2019-05-22 18:31:39 +03:00
Konstantin Pyzhov d2125f0325 Updated kernel binary file for hipModule test. 2019-05-21 13:21:48 -04:00
Maneesh Gupta 7068859ff4 Merge pull request #1123 from emankov/master
[HIP][tests] Copyright notice update
2019-05-21 09:35:13 +05:30
Evgeny Mankov 7664560f14 [HIP][tests] Copyright notice update 2019-05-20 18:46:23 +03:00
Evgeny Mankov be09662009 Merge pull request #1122 from emankov/master
[HIPIFY][tests] Add reverse engineered HIP sample "peer2peer"
2019-05-20 17:17:56 +03:00
Evgeny Mankov 5c205b75f5 [HIPIFY][tests] Add reverse engineered HIP sample "peer2peer"
+ Fix typo in sample "stream"
2019-05-20 17:16:11 +03:00
Evgeny Mankov 44f1be5a28 Merge pull request #1120 from emankov/master
[HIPIFY][doc] Update README.md
2019-05-20 13:09:50 +03:00
Evgeny Mankov c3c42834ab [HIPIFY][doc] Update README.md
+ Populate supported CUDA and LLVM releases with hyperlinks
2019-05-20 13:03:26 +03:00
Konstantin Pyzhov adf3b8774e Disable hipStreamSync2 test for hip-clang. 2019-05-20 02:13:30 -04:00
Maneesh Gupta 71143b426e Merge pull request #1118 from yxsamliu/fix-build-hiprtc
Fix build failure due to hiprtc for HIP-Clang
2019-05-17 21:38:22 +05:30
Yaxun Sam Liu d088a8c23b Fix build failure due to hiprtc for HIP-Clang 2019-05-17 09:52:43 -04:00
Aaron Enye Shi 303ba600d6 Fix hipcc exit code when failing 2019-05-16 20:36:58 +00:00
Evgeny Mankov 633323c981 Update README.md 2019-05-16 18:16:17 +03:00
Evgeny Mankov ab865dbf0e Merge pull request #1116 from emankov/master
[HIPIFY][doc] Update README.md
2019-05-16 18:10:09 +03:00
Evgeny Mankov df2a64cf0d [HIPIFY][doc] Update README.md
+ Update logs
+ Formatting
2019-05-16 18:07:11 +03:00
Evgeny Mankov 21518887bc Merge pull request #1115 from emankov/master
[HIPIFY][cuDNN] Add cudnnGetFilter4dDescriptor support
2019-05-16 16:39:34 +03:00
Evgeny Mankov 02f8dfe7d8 [HIPIFY][cuDNN] Add cudnnGetFilter4dDescriptor support
+ Update cudnn_convolution_forward test accordingly
2019-05-16 16:36:23 +03:00
Alex Voicu a538eb705a Add HIPRTC, glorious ersatz for NVRTC (#1097)
* Add ersatz for NVRTC.

* Fix extraneous paren and use correct namespace.

* Use lowerCamelCase (yuck, yuck) consistently.

* Link against FS when building hiprtc lib.

* Correctly mark Manipulators. Fix dual compile.

* Add unit tests. Extend HIT to accept linker options.

* Make sure the HIPRTC library is installed.

* Better logging. Try to auto-detect the target.

* Stop specifying the target explicitly.

* Add missing flavour of `hipModuleLaunchKernel`.

* Program was already destroyed.

* Don't use `--genco`. Fix mangled name trimming.

* Fix HIPRTC breakage due to upstream noise.

* [dtests] Replace RUN -> TEST in hiprtc tests

Change-Id: Ie499e92dfe4e5c94634b1c2b76cf52d241bcfea3

* [hit] Set HIP_PATH to HIP_ROOT_DIR for all tests

Change-Id: Ib0ad1f99bc71c03e363e055dd508a7a4a210680a
2019-05-16 18:28:54 +05:30
Maneesh Gupta 3178ae2f92 Merge pull request #1113 from wenkaidu/hop_count
Use NUMA distance for hop count calculation
2019-05-16 14:16:29 +05:30
Maneesh Gupta 8e9bc62f6e Merge pull request #1112 from kpyzhov/hipModule-test
Upload pre-built kernel binary for hipModule test.
2019-05-16 14:16:18 +05:30
Wenkai Du 56d2dc0022 Use NUMA distance for hop count calculation 2019-05-15 21:50:35 +00:00
Evgeny Mankov 43ad335d3c Merge pull request #1111 from emankov/master
[HIPIFY][tests] Add reverse engineered HIP sample "stream"
2019-05-15 20:18:51 +03:00
Evgeny Mankov 7cc12df514 [HIPIFY][tests] Add reverse engineered HIP sample "stream"
+ Add additional checks for extern __shared__ due to [#1109]
2019-05-15 20:17:03 +03:00
Evgeny Mankov de57a5ba62 Merge pull request #1110 from emankov/master
[HIPIFY][fix][#1109] Do not preserve extern __shared__ for IncompleteArrayType
2019-05-15 20:09:00 +03:00
Evgeny Mankov bf65120156 [HIPIFY][fix][#1109] Do not preserve extern __shared__ for IncompleteArrayType
+ Update tests accordingly
2019-05-15 20:05:56 +03:00
Konstantin Pyzhov 6242377a5c Upload pre-built kernel binary for hipModule test. 2019-05-15 07:19:40 -04:00
Evgeny Mankov a0f10ebaa2 Merge pull request #1104 from emankov/master
[HIPIFY][tests] Add reverse engineered HIP sample Profiler
2019-05-14 16:59:36 +03:00
Evgeny Mankov 5e49c25faa [HIPIFY][tests] Add reverse engineered HIP sample Profiler
+ Add missing cuda_profiler_api.h to hip/hip_profile.h transformation.
NOTE: HIP Profiler API is under development. This is NOT WORKING example.
TODO: Find out a way to generate HIP_SCOPED_MARKER, HIP_BEGIN_MARKER, HIP_END_MARKER, declared in hip/hip_profile.h in particular place (signatures are to obtain).
2019-05-14 16:43:44 +03:00
Evgeny Mankov 5da723222e Merge pull request #1102 from emankov/master
[HIPIFY][tests] Add reverse engineered HIP sample hipEvent
2019-05-13 22:14:41 +03:00