Commit Graph

3743 Commits

Author SHA1 Message Date
Jenkins 94f17d0953 Merge 'master' into 'amd-master'
Change-Id: I2c8409732f0c2397d6c65f1c39c0fb847bd1bcd8


[ROCm/clr commit: 1e526ae7c5]
2019-05-22 07:30:16 -04:00
Maneesh Gupta e02fc91feb Merge pull request #1123 from emankov/master
[HIP][tests] Copyright notice update

[ROCm/clr commit: 7068859ff4]
2019-05-21 09:35:13 +05:30
Evgeny Mankov fef3e849eb [HIP][tests] Copyright notice update
[ROCm/clr commit: 7664560f14]
2019-05-20 18:46:23 +03:00
Evgeny Mankov 0c34f69f2f Merge pull request #1122 from emankov/master
[HIPIFY][tests] Add reverse engineered HIP sample "peer2peer"

[ROCm/clr commit: be09662009]
2019-05-20 17:17:56 +03:00
Evgeny Mankov 3e0fa665f7 [HIPIFY][tests] Add reverse engineered HIP sample "peer2peer"
+ Fix typo in sample "stream"


[ROCm/clr commit: 5c205b75f5]
2019-05-20 17:16:11 +03:00
Evgeny Mankov 947555c6fe Merge pull request #1120 from emankov/master
[HIPIFY][doc] Update README.md

[ROCm/clr commit: 44f1be5a28]
2019-05-20 13:09:50 +03:00
Evgeny Mankov 45fd88e251 [HIPIFY][doc] Update README.md
+ Populate supported CUDA and LLVM releases with hyperlinks


[ROCm/clr commit: c3c42834ab]
2019-05-20 13:03:26 +03:00
Jenkins ad8b2accd1 Merge 'master' into 'amd-master'
Change-Id: Ic1757967f5f1d7982fa304c84f8a4c923dd606c4


[ROCm/clr commit: 96f4b022ab]
2019-05-18 19:59:41 -07:00
Maneesh Gupta 713ff86eb0 Merge pull request #1118 from yxsamliu/fix-build-hiprtc
Fix build failure due to hiprtc for HIP-Clang

[ROCm/clr commit: 71143b426e]
2019-05-17 21:38:22 +05:30
Jenkins b9cb2ec991 Merge 'master' into 'amd-master'
Change-Id: I4189feaa83580761c6fb2d0b636040a40964cbeb


[ROCm/clr commit: 0d805b92be]
2019-05-17 10:50:29 -04:00
Yaxun Sam Liu c0a754b148 Fix build failure due to hiprtc for HIP-Clang
[ROCm/clr commit: d088a8c23b]
2019-05-17 09:52:43 -04:00
Evgeny Mankov 824d5d8792 Update README.md
[ROCm/clr commit: 633323c981]
2019-05-16 18:16:17 +03:00
Evgeny Mankov df5dbdd6a6 Merge pull request #1116 from emankov/master
[HIPIFY][doc] Update README.md

[ROCm/clr commit: ab865dbf0e]
2019-05-16 18:10:09 +03:00
Evgeny Mankov 71647e33bf [HIPIFY][doc] Update README.md
+ Update logs
+ Formatting


[ROCm/clr commit: df2a64cf0d]
2019-05-16 18:07:11 +03:00
Evgeny Mankov 9d0ac6be5e Merge pull request #1115 from emankov/master
[HIPIFY][cuDNN] Add cudnnGetFilter4dDescriptor support

[ROCm/clr commit: 21518887bc]
2019-05-16 16:39:34 +03:00
Evgeny Mankov 76c52aa429 [HIPIFY][cuDNN] Add cudnnGetFilter4dDescriptor support
+ Update cudnn_convolution_forward test accordingly


[ROCm/clr commit: 02f8dfe7d8]
2019-05-16 16:36:23 +03:00
Alex Voicu a4a3132c64 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


[ROCm/clr commit: a538eb705a]
2019-05-16 18:28:54 +05:30
Maneesh Gupta ef71f962f9 Merge pull request #1113 from wenkaidu/hop_count
Use NUMA distance for hop count calculation

[ROCm/clr commit: 3178ae2f92]
2019-05-16 14:16:29 +05:30
Maneesh Gupta 13f8cc0139 Merge pull request #1112 from kpyzhov/hipModule-test
Upload pre-built kernel binary for hipModule test.

[ROCm/clr commit: 8e9bc62f6e]
2019-05-16 14:16:18 +05:30
Wenkai Du 3d75b10e0b Use NUMA distance for hop count calculation
[ROCm/clr commit: 56d2dc0022]
2019-05-15 21:50:35 +00:00
Evgeny Mankov 6ce0a62bb5 Merge pull request #1111 from emankov/master
[HIPIFY][tests] Add reverse engineered HIP sample "stream"

[ROCm/clr commit: 43ad335d3c]
2019-05-15 20:18:51 +03:00
Evgeny Mankov 355f49a850 [HIPIFY][tests] Add reverse engineered HIP sample "stream"
+ Add additional checks for extern __shared__ due to [#1109]


[ROCm/clr commit: 7cc12df514]
2019-05-15 20:17:03 +03:00
Evgeny Mankov 2addee852a Merge pull request #1110 from emankov/master
[HIPIFY][fix][#1109] Do not preserve extern __shared__ for IncompleteArrayType

[ROCm/clr commit: de57a5ba62]
2019-05-15 20:09:00 +03:00
Evgeny Mankov bbe9275e38 [HIPIFY][fix][#1109] Do not preserve extern __shared__ for IncompleteArrayType
+ Update tests accordingly


[ROCm/clr commit: bf65120156]
2019-05-15 20:05:56 +03:00
Konstantin Pyzhov 5bb9455f51 Upload pre-built kernel binary for hipModule test.
[ROCm/clr commit: 6242377a5c]
2019-05-15 07:19:40 -04:00
Jenkins dc634cc586 Merge 'master' into 'amd-master'
Change-Id: I15e04f87004767e238af9aa1ab9567921594d07f


[ROCm/clr commit: 6ffc5cb48f]
2019-05-15 05:45:15 -04:00
Evgeny Mankov b866a2e1d1 Merge pull request #1104 from emankov/master
[HIPIFY][tests] Add reverse engineered HIP sample Profiler

[ROCm/clr commit: a0f10ebaa2]
2019-05-14 16:59:36 +03:00
Evgeny Mankov 7a5a838e80 [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).


[ROCm/clr commit: 5e49c25faa]
2019-05-14 16:43:44 +03:00
Jenkins a84793b372 Merge 'master' into 'amd-master'
Change-Id: I476b12c4e051b47fb2e62dbea709d268d9a2f630


[ROCm/clr commit: b32578d5b9]
2019-05-14 02:12:10 -07:00
Evgeny Mankov a973fba09f Merge pull request #1102 from emankov/master
[HIPIFY][tests] Add reverse engineered HIP sample hipEvent

[ROCm/clr commit: 5da723222e]
2019-05-13 22:14:41 +03:00
Evgeny Mankov 8c12edcf65 [HIPIFY][tests] Add reverse engineered HIP sample hipEvent
[ROCm/clr commit: 9860dac7fa]
2019-05-13 22:12:43 +03:00
Evgeny Mankov 612afc5fed Merge pull request #1101 from emankov/master
[HIPIFY][tests] Add reverse engineered HIP sample MatrixTranspose

[ROCm/clr commit: 4cf53fb09c]
2019-05-13 19:39:16 +03:00
emankov 39b28d7623 [HIPIFY][tests] Add reverse engineered HIP sample MatrixTranspose
[ROCm/clr commit: cdc76af186]
2019-05-13 19:37:18 +03:00
Jenkins 2ce81d2cb4 Merge 'master' into 'amd-master'
Change-Id: Ibca6232ef00edf0c11a5db5f6f10a5bcbb963625


[ROCm/clr commit: b54dddb6e2]
2019-05-13 05:46:17 -04:00
Wen-Heng (Jack) Chung e92ffd2261 Revert "HACK for SWDEV-173477" (#1004)
* Revert "HACK for SWDEV-173477"

This reverts commit 86379d694f.

[ROCm/clr commit: a4db991cbf]
2019-05-13 14:42:05 +05:30
Maneesh Gupta e0e30536e6 Merge pull request #1083 from gargrahul/fix_hip_impl_visible_agents
Maintain HIP_VISIBLE_DEVICES for kernel launch

[ROCm/clr commit: c9fdb42b91]
2019-05-13 14:20:18 +05:30
Rahul Garg d44e800a17 Add fine grained host memory lock support (#1095)
* Add fine grained host memory lock support

* Fix default flag check


[ROCm/clr commit: e1f3dc0c80]
2019-05-13 11:48:26 +05:30
Nick Curtis 3b6b356d23 Markdown fixes & Whitespace cleanup for samples (#1096)
* Fix multiline code blocks in README's

* Whitespace cleanup


[ROCm/clr commit: fb92feae0e]
2019-05-12 19:27:44 +05:30
Maneesh Gupta 89da742110 Merge pull request #1094 from mangupta/hit_improvements
[dtests] Add new tests to directed tests

[ROCm/clr commit: 0cc7fe8a9f]
2019-05-12 19:25:21 +05:30
Siu Chi Chan 76f535b4ce migrate program_state logic from header into shared library (phase I) (#1077)
* Revert "Revert "Use COMgr to read Kernel Args Metadata (#1006)""

This reverts commit f8d108a815.

* Revert "Use COMgr to read Kernel Args Metadata (#1006)"

This reverts commit 10048a5631.

* Revert "improve program state commentary"

This reverts commit 5233d41c6c.

* Revert "load program state once per agent"

This reverts commit 9cee2c5311.

* start moving function_names() into the hip shared lib

* start moving code_object_blobs to a new "state" object

* Consolidate various program state related static objects into a
single program_state object

* minor clean up

* move more stuffs from functional_grid_launch into program_state

* debug make_kernarg

* moving lookup for kernargs size_align into program_state

* clean up old code for kernarg size and alignment

* update hip_module to use newer api in program_state

* Create public member functions for program_state

* move most program state functions into shared library

* Pass the data buffer size to load_executable
Otherwise, it can't figure what the data size is
just from the char* (since the data is not really a string)

* turning free functions in program state into members of program_state_impl

* change the free function globals() into a member of program_state_impl

* replace the static mutex used for populating globals

* moving associate_code_object_symbols_with_host_allocation into
program_state_impl

* move load_code_object_and_freeze_executable into program_state_impl

* moving executables and functions_names into program_state_impl

* moving kernels() into program_state_impl

* moving functions() into program_state_impl

* move get_kernargs into program_state_impl

* moving kernel_descriptor into program_state_impl

* moving kernargs_size_align calculation into program_state_impl

* Changing the handle to program_state_impl to a pointer

* moving program_state_impl into a separate inline source file

* fixing/cleaning up some header file includes

* moving member function for kernargs_size_align into program_state.cpp

* moving Kernel_descriptor into program_state.inl

* add a new class to manage agent globals

* moving all agent globals processing functions into agent_globals_impl

* load program state once per agent

re-merging PR991 against other program state changes

* fix per-agent program state member initialization

* cache executables based on elf name, isa, and agent.

This avoids program state reloading executables after a shared library is dlopened.

re-merging PR1057 against other program state changes

* protect executables cache by a global mutex

* return ref to executables cache

* adapt PR#981 Make hipModuleGetGlobal be in HIP runtime


[ROCm/clr commit: 05a1b696da]
2019-05-12 19:24:03 +05:30
Jenkins 46d808af51 Merge 'master' into 'amd-master'
Change-Id: I390e88de292d69072474b3ed1e5537d2477e9a0f


[ROCm/clr commit: f80450c366]
2019-05-10 11:30:25 -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