نمودار کامیت

3232 کامیت‌ها

مولف SHA1 پیام تاریخ
Maneesh Gupta 384b4554a2 Merge pull request #1083 from gargrahul/fix_hip_impl_visible_agents
Maintain HIP_VISIBLE_DEVICES for kernel launch

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

* Fix default flag check


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

* Whitespace cleanup


[ROCm/hip commit: 5257b54a39]
2019-05-12 19:27:44 +05:30
Maneesh Gupta 2302345dd5 Merge pull request #1094 from mangupta/hit_improvements
[dtests] Add new tests to directed tests

[ROCm/hip commit: 8c4b161a45]
2019-05-12 19:25:21 +05:30
Siu Chi Chan d0252dfa79 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 62e96cb4cf.

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

This reverts commit 882006555b.

* Revert "improve program state commentary"

This reverts commit fb2beb0c88.

* Revert "load program state once per agent"

This reverts commit 21f5e142f5.

* 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/hip commit: f5eb91d53d]
2019-05-12 19:24:03 +05:30
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 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 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 816e86fc24 [ci] Enable tests on ROCm 2.4
[ROCm/hip commit: 07bd3ecfad]
2019-05-08 12:07:33 +05:30
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
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
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
Michael LIAO 448be14118 [hipcc] Repace --rpath with --rpath-link
- With `--rpath`, app's RUNPATH is set to the temporary library path
  during build. Instead, `--rpath-link` should be used to leave RUNPATH
  untouched. User should set LD_LIBRARY_PATH or system ld.so.conf to
  proper setting.


[ROCm/hip commit: 7f8b80103d]
2019-04-29 16:01:16 -04:00
Evgeny Mankov 2b16e01c66 [HIPIFY][doc] Update Readme.md: latest cuDNN 7.5.1.10 is supported
+ tested with CUDA 9.0, 9,2, 10.0 and 10.1


[ROCm/hip commit: c0705f892b]
2019-04-29 15:41:08 +03:00
Aaron Enye Shi 62e96cb4cf Revert "Use COMgr to read Kernel Args Metadata (#1006)"
This reverts commit 882006555b.


[ROCm/hip commit: a3d118eaa8]
2019-04-26 16:04:56 -04:00
Aaron Enye Shi c797e6e27b Revert "Add COMGR relative path for build machines"
This reverts commit 01a11c94f8.


[ROCm/hip commit: 48701ad4ba]
2019-04-26 16:04:56 -04:00
Aaron Enye Shi 3585159140 Revert "Add dependency on amd_comgr in hip-config-*.cmake.in"
This reverts commit b9526364bb.


[ROCm/hip commit: 59a5965fe1]
2019-04-26 16:04:56 -04:00
Maneesh Gupta b9526364bb Add dependency on amd_comgr in hip-config-*.cmake.in
Change-Id: Iac1d851a8cfb99224e9c5926780273d9b9b08426


[ROCm/hip commit: ef99ffd9f4]
2019-04-25 15:26:33 -04:00