Граф коммитов

4578 Коммитов

Автор SHA1 Сообщение Дата
Aaron En Ye Shi cd1c9827e7 Merge "Update hipcc to use HIP_COMPILER variable" into amd-master-next
[ROCm/hip commit: d69ccdee27]
2020-04-30 17:31:33 -04:00
Michael Hong Bin Liao 7540dbc29c Merge "[vdi] Skip null texture object in hipDestroyTextureObject." into amd-master-next
[ROCm/hip commit: 61932e1785]
2020-04-30 16:07:58 -04:00
Aaron Enye Shi 318a527d31 Update hipcc to use HIP_COMPILER variable
This will update the hipcc script so that it will use HIP_PLATFORM, HIP_COMPILER, and HIP_RUNTIME variables correctly based on updated hipconfig file.

Removing HIP_PLATFORM=clang, only use hcc and nvcc for now. HIP_PLATFORM should eventually switch to amd or nvcc.

Change-Id: Ie527d07a1add974cc3aab8e9f61b0518147d7602


[ROCm/hip commit: 2de1129510]
2020-04-30 15:31:20 -04:00
Payam Ghafari 9b2b0f3a86 Merge "renaming vdi to rocclr, part 1" into amd-master-next
[ROCm/hip commit: b24e5fea52]
2020-04-29 19:42:20 -04:00
Laurent Morichetti 1e3a301694 Don't make a copy of the embedded device binaries
Embedded device binaries should not be cloned if we want the ROCR's
code object URI for this binary to point to the container (host
executable or shared library) instead of a memory location.

Depends-On: I7973bb0243f5a2d1b639b8a88445cfe6af919dd7
Change-Id: Id3afc981e027e5371114d011f2caaa6414f5fc58


[ROCm/hip commit: f21fd3e22e]
2020-04-29 18:40:18 -04:00
Payam 72958eaee7 renaming vdi to rocclr, part 1
Change-Id: Idec9be2b6174217abcebaa1776e59168670740b1


[ROCm/hip commit: 4c3f8221e9]
2020-04-29 17:54:37 -04:00
Saleel Kudchadker f634b3681f Fix error code when hipEventRecord is not called
Change-Id: I6672d4320280fd87fd2786bc54214d40944da845


[ROCm/hip commit: 34b32e35c9]
2020-04-29 13:13:52 -04:00
Michael LIAO f34408abb4 [vdi] Skip null texture object in hipDestroyTextureObject.
- To match both CUDA and HCC runtime behavior.

Change-Id: I072b006dd554e17f8341f391d33bf6224a125a7e


[ROCm/hip commit: cbe9023639]
2020-04-29 12:20:42 -04:00
German Andryeyev f814d47640 Clean-up the list of blocking streams
- Insert the stream into the list on the host queue creation,
instead of stream creation

Change-Id: Ib25053019f7df97e5bc786922a6587b9514852d3


[ROCm/hip commit: deb2c399c9]
2020-04-29 11:37:43 -04:00
Vlad Sytchenko 4df7727906 Fix order initialization warning
Change-Id: I77ddf1dbec2d11c273163efae6526d3deca92dbf


[ROCm/hip commit: ded92a5d2a]
2020-04-28 20:07:51 -04:00
Payam 1e81c0ce1f updating package name to hip-rocclr instead of hip-vdi
Change-Id: Ife8810d4dd224ce29c2e2a827b221a618c9f1b3d


[ROCm/hip commit: db3d4bc848]
2020-04-28 13:36:33 -04:00
Vlad Sytchenko 427a814caf Handle copy cases where the uses pases a bad ptr
Change-Id: I4490b8519e4d0dde25b845f9ca7e81c1d80d4f28


[ROCm/hip commit: cf52b5fca4]
2020-04-28 11:04:29 -04:00
Freddy Paul 027752bb3a hip-on-vdi: Enable RUNPATH and versioning
1. Enable versioning for HIP libraries
2. Enable RUNPATH on HIP libraries to find ROCm dependencies
3. Control HIP package install using CPACK_INSTALL_PREFIX

Change-Id: I9096da56592e9c78cdba329011f6e1bae99adaa2


[ROCm/hip commit: b75b602601]
2020-04-27 19:48:44 -04:00
Aaron Enye Shi d9bb1fd770 Update hipconfig to support HIP-Clang
Add support for hipconfig to display details on HIP-Clang compiler and update HIP_COMPILER and HIP_RUNTIME to include clang and rocclr. Also, add hipcc flags --cxxflags and --ldflags to support HCC users who used hccconfig flags.

Change-Id: Ib12d81a4ff59d34fb000626836b1adb10be3ac61


[ROCm/hip commit: afc9b546fb]
2020-04-27 11:44:53 -04:00
Yaxun (Sam) Liu 98032a796a Let hipcc treats .cpp files as C++ files for HIP-Clang
This change is required by rocBLAS and rocFFT for OpenMP issue
since cmake needs to treat .cpp file as C++ program to detect
OpenMP support.

This is to match nvcc behavior, speed up compilation of C++
programs, and fix some compilation issue where C++ programs
are compiled as HIP programs.

Currently it is controlled by an environment variable
HIP_COMPILE_CXX_AS_HIP. By default it is 1, where
hipcc treats .cpp files as HIP programs. If it is
set to 0, hipcc will treat .cpp files as C++ programs.
This is because some math libraries are still not
ready for the change, however rocBLAS and rocFFT
require this feature for OpenMP, therefore put it
under an environment variable so that rocBLAS
and rocFFT can use it.

Change-Id: I56a51e27079df850ee39d4217fb647c22d79f612


[ROCm/hip commit: 9c5a7226b2]
2020-04-27 11:43:05 -04:00
kjayapra-amd 1773f66d6a SWDEV-232008 - Handle cases where Memcpy size is less than Symbol Size.
Change-Id: I046bc70445dfd4f6fdfd06415f53d1fc06f425b4


[ROCm/hip commit: 1f3789d5a2]
2020-04-27 10:47:28 -04:00
root 2061d19165 Merge master into amd-master-next
Change-Id: I3fc1dc0c860d627053537581e75561e8a7efe327


[ROCm/hip commit: 2689246de6]
2020-04-26 22:19:37 +00:00
Michael LIAO 2a95fcf779 [vdi] Revise the symbol management.
- As different modules may have symbols with the same name, each symbol
  needs identifying with a pair of the module handle and the symbol
  name.

Change-Id: I85650a787d9a424545154cc40ebd59e706fa358f


[ROCm/hip commit: a0acf7bdaa]
2020-04-24 22:28:31 -04:00
Yaxun (Sam) Liu f79898e90e Enable template max and min for HIP-Clang (#2028)
It was for HCC only. HIP-Clang also needs it for __fp16 since AMDMIGraphX uses it.

Change-Id: Id49322b7b89ef799accdf6b47627a6fce51d1ab5

[ROCm/hip commit: 808dae6813]
2020-04-24 12:30:28 -07:00
German Andryeyev 0aea572bff SWDEV-232918
hipEventRecord is much slower in hipclang/vdi

- Make sure default streams don't sync each other.
- Add null stream into the list of default streams.
- Code clean-up to simplify queue look-up.

Change-Id: I36e1fc8d86a600e3dce806694d95d146ed8afd03


[ROCm/hip commit: f7f7337bae]
2020-04-24 14:40:43 -04:00
Christophe Paquot c7a4cfc114 Merge "cherrypick from master branch" into amd-master-next
[ROCm/hip commit: 0bec17a266]
2020-04-24 11:48:18 -04:00
Yaxun Liu 10cfc55ed3 Merge "Enable template max and min for HIP-Clang" into amd-master-next
[ROCm/hip commit: 8cb04db89e]
2020-04-24 11:44:49 -04:00
Tao Sang 7de150a1b1 Merge "Add Performance/memory/hipPerfMemMallocCpyFree" into amd-master-next
[ROCm/hip commit: b7a407a61b]
2020-04-24 11:32:47 -04:00
Michael Hong Bin Liao 6c2bf62424 Merge "[vdi] Fix texture reference sample." into amd-master-next
[ROCm/hip commit: 880d2a8b50]
2020-04-24 10:30:38 -04:00
Michael Hong Bin Liao 4764c2f091 Merge "[vdi] Fix hang due to recursive locking." into amd-master-next
[ROCm/hip commit: 7519ba64af]
2020-04-24 10:30:26 -04:00
Yaxun (Sam) Liu 6f1a8d4e77 Enable template max and min for HIP-Clang
This change is required by AMDMIGraphX.

It was for HCC only. HIP-Clang also needs it for __fp16 since AMDMIGraphX uses it.

Change-Id: Id49322b7b89ef799accdf6b47627a6fce51d1ab5


[ROCm/hip commit: 4143d81618]
2020-04-24 09:51:17 -04:00
Paul Fultz II 4da30ef9ae cherrypick from master branch
34d5719edc
4488c9a016

These are needed by MIOpen and rocBLAS.

Add __HIP_PLATFORM_HCC__ to hip::host target (#2029)

Fix hip-config.cmake for CMAKE_CXX_COMPILER=g++ (#2035)

* Fix hip-config.cmake for CMAKE_CXX_COMPILER=g++

* Add inlineall option to hip::device in hip-config.cmake

Change-Id: Ib51f82d0b9e38d2137df65c940592413e22ba07a


[ROCm/hip commit: d568f78bdd]
2020-04-24 09:32:02 -04:00
Tao Sang f94a1bd16d Add Performance/memory/hipPerfMemMallocCpyFree
Change-Id: Id1ac415f85028da3e9517c2226764bcb4acec1b1


[ROCm/hip commit: e130c3ba4f]
2020-04-23 23:49:56 -04:00
Michael LIAO 5a2ad708ea [vdi] Fix texture reference sample.
- The driver code should not re-define `tex` again as it's already
  defined in the kernel code. Eventually, the driver code should be as
  regular C++ code instad of HIP code.

Change-Id: I8c7cab204b98990619d6e7109b990d7089ea9261


[ROCm/hip commit: 74ba25602b]
2020-04-23 23:41:56 -04:00
Michael LIAO b6bb0cc509 [vdi] Fix hang due to recursive locking.
- Declare recursive lock for global function map.

Change-Id: I3e792e21688c980343c4fd1c61dcad97f7a890cd


[ROCm/hip commit: 04794c6359]
2020-04-23 23:32:56 -04:00
kjayapra-amd d16399a853 SWDEV - 231874 - Do Dword aligned memset if the total size aligns.
Change-Id: Id05db4cfd9c43b2cffa3cec8b02f1cd07f340dd6


[ROCm/hip commit: b443172d12]
2020-04-23 21:08:50 -04:00
Vlad Sytchenko 1c3f7234de Make sure to zero out all the unset texture fields
These might contain garbage causing the runtime to incorrectly parse the state of the texture references.

Change-Id: I93c726fa30b580b3e14c50ac939f3c71b0d1c8d9


[ROCm/hip commit: 8d6347c6b8]
2020-04-23 16:38:52 -04:00
Michael Hong Bin Liao 618efb83c1 Merge "[hip] Fix typos." into amd-master-next
[ROCm/hip commit: aa98d636ed]
2020-04-23 13:32:09 -04:00
eshcherb 5b9a4d2a8e fix pointers format (#2037)
* fix pointers format

* fix pointers format - cleanup

* fix pointers format - fix

[ROCm/hip commit: d0511dfb16]
2020-04-23 21:54:51 +05:30
Yaxun (Sam) Liu 34d5719edc Fix hip-config.cmake for CMAKE_CXX_COMPILER=g++ (#2035)
* Fix hip-config.cmake for CMAKE_CXX_COMPILER=g++

Change-Id: I84ae83a5d223853706dd36834b7962ffe9573c1f

* Fix HIP_CXX_COMPILER

Change-Id: I4e2523b560113420af1ab877a0bc48ca2e9e957a

* Fix hip-config.cmake

Change-Id: Ida4ef8f40fed83d5f659a9a9835b1f521cb6a374

* Add inlineall option to hip::device in hip-config.cmake

Change-Id: Ib51f82d0b9e38d2137df65c940592413e22ba07a

[ROCm/hip commit: 75a5088446]
2020-04-23 21:51:54 +05:30
Aaron Enye Shi aaffb776d5 extractkernel obj dump args to use double dashes (#2034)
More recent llvm-objdump has changed disassemble and mcpu arguments to require double dashes.

[ROCm/hip commit: a2768ea554]
2020-04-23 21:51:33 +05:30
Paul Fultz II 4488c9a016 Add __HIP_PLATFORM_HCC__ to hip::host target (#2029)
[ROCm/hip commit: 727c9f77d8]
2020-04-23 21:51:02 +05:30
Maneesh Gupta 8e137a6ec1 Merge in the rocclr based hip runtime (#2032)
* Merge master-next changes in master (include vdi development in master branch)



[ROCm/hip commit: a0b5dfd625]
2020-04-23 09:12:06 -07:00
Evgeny Shcherbakov 63cd0a7ab9 Merge "cleanup" into amd-master-next
[ROCm/hip commit: 7d5cd08796]
2020-04-22 23:28:22 -04:00
Michael LIAO 92e3cff6cb [hip] Fix typos.
Change-Id: I9d85d0e70033d144dbd4d61cb434ffbe023af8c0


[ROCm/hip commit: 218044577e]
2020-04-22 16:44:54 -04:00
Tao Sang 3a3aec1388 Fix hip_get_devices failure in lammps
Support hipDeviceAttributeIntegrated in hipDeviceGetAttribute() with hip-vdi rt

Change-Id: Ie5ba81222af3554a843c184ae75af7f369a3c24b


[ROCm/hip commit: 793dbf5bd5]
2020-04-22 15:16:59 -04:00
Evgeny a9a90c8687 cleanup
Change-Id: Ia0ee0e4cab2ee8eaa9931024681d0db5b2802594


[ROCm/hip commit: 6823232b3a]
2020-04-22 13:42:45 -05:00
Michael LIAO 91329e44a9 [hip] Generate assertion message in assertion.
Change-Id: Ie66f6563e8728fd0e21cf22dcc6619e4a0e5c28d


[ROCm/hip commit: 19f793f1cd]
2020-04-21 16:44:40 -04:00
Tao Sang 7142f1c5c2 Merge "support hipLaunchParm test with static lib of hip-vdi rt" into amd-master-next
[ROCm/hip commit: 5fee28ce03]
2020-04-21 15:54:46 -04:00
Tao Sang 77190ec979 Add perfDispatch tests into hip direct_tests
Port perfDispatch tests from OpenCL into hip direct_tests

Change-Id: I9f8362636e329d2d0a434c4f012ccc46a524c746


[ROCm/hip commit: daf32606db]
2020-04-21 14:00:27 -04:00
Tao Sang 02c3baa938 support hipLaunchParm test with static lib of hip-vdi rt
Let hipMalloc() be called in main() so that global variable can be initialized.

Change-Id: I9aa1f0a0bb4fa0825d10af0b58c843e7b928e9a3


[ROCm/hip commit: de4c173c6e]
2020-04-21 13:55:42 -04:00
Michael LIAO c11c159905 [vdi] Refactor texture/surface reference support.
Change-Id: I8014d82aae7139ef5f95e4b50c4fc6da200dbc9d


[ROCm/hip commit: 16d9fe5e37]
2020-04-21 11:56:48 -04:00
German Andryeyev 45306fcdf6 SWDEV-231579 - [hipclang-vdi-rocm][perf]
- HIPPerfDispatchSpeed disparity between HIP/HCC vs HIP/VDI
Insert a wait marker command in the default stream only when
HIP has pending operations on other async streams

Change-Id: I68660a54867fab7571ba57eb1df5feb1bca1c61a


[ROCm/hip commit: db70fc66b7]
2020-04-21 10:05:26 -04:00
kjayapra-amd 45f8e9444a SWDEV-229480 - Improve error messages in HIP Layer.
Change-Id: I054b979d3aa6cf6ed4ca14a9393bdcba757772ff


[ROCm/hip commit: 2eb8cc8e90]
2020-04-20 21:23:52 -04:00
Tao Sang 6406087713 Solve issues with hip-vdi runtime static lib
1.Combine libamdhip64_static_base.a and libamdvdi_static.a into libamdhip64_static.a.
2.Let hipcc use -use-staticlib to link libamdhip64_static.a.
3.Add some samples for static lib.
4.Fix compiling failure of code object.

Change-Id: Ic8c95228eb139058da8b5d66ba8439486154ca6f


[ROCm/hip commit: da27fd2b09]
2020-04-20 15:37:02 -04:00