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

4565 Коммитов

Автор SHA1 Сообщение Дата
Aaron Enye Shi b1904716e1 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/clr commit: 2df5d92240]
2020-04-27 11:44:53 -04:00
Yaxun (Sam) Liu 6b0c1024c2 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/clr commit: 4e7b1cdbd2]
2020-04-27 11:43:05 -04:00
kjayapra-amd 8070085d1c SWDEV-232008 - Handle cases where Memcpy size is less than Symbol Size.
Change-Id: I046bc70445dfd4f6fdfd06415f53d1fc06f425b4


[ROCm/clr commit: 19c654e794]
2020-04-27 10:47:28 -04:00
root 6a7aa0c1c6 Merge master into amd-master-next
Change-Id: I3fc1dc0c860d627053537581e75561e8a7efe327


[ROCm/clr commit: b5031f39b1]
2020-04-26 22:19:37 +00:00
Michael LIAO 134b33e4e0 [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/clr commit: f8062c6fbd]
2020-04-24 22:28:31 -04:00
Yaxun (Sam) Liu c13a63bcff 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/clr commit: 29549ce4dc]
2020-04-24 12:30:28 -07:00
German Andryeyev 6aa9951a42 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/clr commit: 5a7c094729]
2020-04-24 14:40:43 -04:00
Christophe Paquot 6a64edc032 Merge "cherrypick from master branch" into amd-master-next
[ROCm/clr commit: cf6df62b3a]
2020-04-24 11:48:18 -04:00
Yaxun Liu 80edc2b562 Merge "Enable template max and min for HIP-Clang" into amd-master-next
[ROCm/clr commit: 040ca11925]
2020-04-24 11:44:49 -04:00
Tao Sang 8d2cbef722 Merge "Add Performance/memory/hipPerfMemMallocCpyFree" into amd-master-next
[ROCm/clr commit: cf6345d7c7]
2020-04-24 11:32:47 -04:00
Michael Hong Bin Liao 72b42ff530 Merge "[vdi] Fix texture reference sample." into amd-master-next
[ROCm/clr commit: 17e9c63708]
2020-04-24 10:30:38 -04:00
Michael Hong Bin Liao 07bde00301 Merge "[vdi] Fix hang due to recursive locking." into amd-master-next
[ROCm/clr commit: 2e61683b33]
2020-04-24 10:30:26 -04:00
Yaxun (Sam) Liu 066b79be84 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/clr commit: 1013e4eca8]
2020-04-24 09:51:17 -04:00
Paul Fultz II b42e1216d9 cherrypick from master branch
75a5088446
727c9f77d8

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/clr commit: 9227b08458]
2020-04-24 09:32:02 -04:00
Tao Sang b0f72224a1 Add Performance/memory/hipPerfMemMallocCpyFree
Change-Id: Id1ac415f85028da3e9517c2226764bcb4acec1b1


[ROCm/clr commit: 33d7005b10]
2020-04-23 23:49:56 -04:00
Michael LIAO 5147a686ff [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/clr commit: b469e5c573]
2020-04-23 23:41:56 -04:00
Michael LIAO 310a0d2640 [vdi] Fix hang due to recursive locking.
- Declare recursive lock for global function map.

Change-Id: I3e792e21688c980343c4fd1c61dcad97f7a890cd


[ROCm/clr commit: c56a3ca63e]
2020-04-23 23:32:56 -04:00
kjayapra-amd 3077742b22 SWDEV - 231874 - Do Dword aligned memset if the total size aligns.
Change-Id: Id05db4cfd9c43b2cffa3cec8b02f1cd07f340dd6


[ROCm/clr commit: 92c63384cb]
2020-04-23 21:08:50 -04:00
Vlad Sytchenko 9fb3564410 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/clr commit: bfa363d00c]
2020-04-23 16:38:52 -04:00
Michael Hong Bin Liao e4aef105f3 Merge "[hip] Fix typos." into amd-master-next
[ROCm/clr commit: b70dac2557]
2020-04-23 13:32:09 -04:00
eshcherb 3a519a8f0d fix pointers format (#2037)
* fix pointers format

* fix pointers format - cleanup

* fix pointers format - fix

[ROCm/clr commit: 6cb57ee64a]
2020-04-23 21:54:51 +05:30
Yaxun (Sam) Liu 9c9ed1cab0 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/clr commit: 5abcda3ab7]
2020-04-23 21:51:54 +05:30
Aaron Enye Shi 7c6aa863d6 extractkernel obj dump args to use double dashes (#2034)
More recent llvm-objdump has changed disassemble and mcpu arguments to require double dashes.

[ROCm/clr commit: 17e439e572]
2020-04-23 21:51:33 +05:30
Paul Fultz II a7d56e7159 Add __HIP_PLATFORM_HCC__ to hip::host target (#2029)
[ROCm/clr commit: 445953aa94]
2020-04-23 21:51:02 +05:30
Maneesh Gupta 11fe5b06de Merge in the rocclr based hip runtime (#2032)
* Merge master-next changes in master (include vdi development in master branch)



[ROCm/clr commit: f2e1118d7a]
2020-04-23 09:12:06 -07:00
Evgeny Shcherbakov be4f312ee4 Merge "cleanup" into amd-master-next
[ROCm/clr commit: e8d64b509e]
2020-04-22 23:28:22 -04:00
Michael LIAO 4e3c8a5ff4 [hip] Fix typos.
Change-Id: I9d85d0e70033d144dbd4d61cb434ffbe023af8c0


[ROCm/clr commit: a353df6b36]
2020-04-22 16:44:54 -04:00
Tao Sang 9d88e0ff89 Fix hip_get_devices failure in lammps
Support hipDeviceAttributeIntegrated in hipDeviceGetAttribute() with hip-vdi rt

Change-Id: Ie5ba81222af3554a843c184ae75af7f369a3c24b


[ROCm/clr commit: 85abd8f028]
2020-04-22 15:16:59 -04:00
Evgeny c4c08791e2 cleanup
Change-Id: Ia0ee0e4cab2ee8eaa9931024681d0db5b2802594


[ROCm/clr commit: b05e54bf84]
2020-04-22 13:42:45 -05:00
Michael LIAO 07f08b78c1 [hip] Generate assertion message in assertion.
Change-Id: Ie66f6563e8728fd0e21cf22dcc6619e4a0e5c28d


[ROCm/clr commit: 2c1933e0f3]
2020-04-21 16:44:40 -04:00
Tao Sang 98a2707931 Merge "support hipLaunchParm test with static lib of hip-vdi rt" into amd-master-next
[ROCm/clr commit: 8d63204887]
2020-04-21 15:54:46 -04:00
Tao Sang 672f243a42 Add perfDispatch tests into hip direct_tests
Port perfDispatch tests from OpenCL into hip direct_tests

Change-Id: I9f8362636e329d2d0a434c4f012ccc46a524c746


[ROCm/clr commit: b52873ff98]
2020-04-21 14:00:27 -04:00
Tao Sang 876c5c568e 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/clr commit: d27880ac39]
2020-04-21 13:55:42 -04:00
Michael LIAO f0df4418a0 [vdi] Refactor texture/surface reference support.
Change-Id: I8014d82aae7139ef5f95e4b50c4fc6da200dbc9d


[ROCm/clr commit: 441284841d]
2020-04-21 11:56:48 -04:00
German Andryeyev 2266bc700b 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/clr commit: 21840ac6a0]
2020-04-21 10:05:26 -04:00
kjayapra-amd a13cab17d4 SWDEV-229480 - Improve error messages in HIP Layer.
Change-Id: I054b979d3aa6cf6ed4ca14a9393bdcba757772ff


[ROCm/clr commit: b3308f7674]
2020-04-20 21:23:52 -04:00
Tao Sang eb50c7ef38 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/clr commit: 32130f8ec3]
2020-04-20 15:37:02 -04:00
Yaxun Liu 7d1457a58a Merge "Revert "Solve issues with hip-vdi runtime static lib"" into amd-master-next
[ROCm/clr commit: 54e663fb27]
2020-04-18 08:52:26 -04:00
Payam c1aa097920 Adding License file
Change-Id: I9da5c36883a7b167e3bf312c7ed61af207c33c59


[ROCm/clr commit: be45d12c1d]
2020-04-17 13:44:43 -04:00
Tao Sang efe517e4c0 Revert "Solve issues with hip-vdi runtime static lib"
This reverts commit 08d1b39d50.

Reason for revert: It is causing dkms-no-npi-hipclang broken.
It is top priority to maintain dkms-no-npi-hipclang build, otherwise we lose track of regression analysis.
So revert the change for now and recommit it after fixing it.

 

Change-Id: Ia5136e888baecb6148c6c18eedbf37066fcb1eaa


[ROCm/clr commit: a6c6f51926]
2020-04-17 10:13:08 -05:00
Aryan Salmanpour ca51795efd disable printf on hip-clang on Windows (#2021)
[ROCm/clr commit: 08147681d0]
2020-04-17 10:33:24 +05:30
Sarbojit2019 2436c2dd6f [HIPTEST]common changes for unittest (#2017)
[ROCm/clr commit: 7808be893f]
2020-04-17 10:31:47 +05:30
Jeff Daily 8b0a909b2b add IPC event support (#1996)
[ROCm/clr commit: e943144b31]
2020-04-17 10:31:22 +05:30
Siu Chi Chan fee56cb360 moving the extractkernel tool from hcc to hip (#1644)
[ROCm/clr commit: 2634c8fe74]
2020-04-17 10:31:06 +05:30
Tao Sang 08d1b39d50 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: Ia2333622a8d05639b90974c4c5d3d85654ba0138


[ROCm/clr commit: 5210ee6ca5]
2020-04-15 13:46:36 -04:00
Karthik Jayaprakash 18aa2145cd Merge "SWDEV-227602 - Adding support for hipFuncGetAttribute" into amd-master-next
[ROCm/clr commit: d7d49eb8e9]
2020-04-15 12:18:32 -04:00
Christophe Paquot ca7600b808 Merge "Fix build failure of rocPRIM" into amd-master-next
[ROCm/clr commit: b87d9405e6]
2020-04-14 15:02:09 -04:00
Vlad Sytchenko bde6f8b43a Correctly calculate size of the copy region
Since we adjust we adjust the start of the region, amd::BufferRect::end_ is no longer the size, just the offset as to where the region ends.

The actual size of the region is (amd::BufferRect::end_ - amd::BufferRect::start_).

Change-Id: I8425d8bdfb20f485740863813e762e8923d9ee94


[ROCm/clr commit: 4d6e394c73]
2020-04-14 12:25:17 -04:00
Yaxun (Sam) Liu 59b7920748 Fix build failure of rocPRIM
Two issues are fixed:

libamdhip64_static.a is not included in package.

cmake generated target files uses installation path of libraries
which are created when the libraries are built and installed.
The CI uses customized installation directory which is not
the package installation directory, thefore the library location
in cmake generated target files differs from the library location
installed from package. This causes rocPRIM build failure since
rocPRIM uses pkg-config which checks library location.

The fix is to fix the library location before adding cmake
generated target files to package.

Change-Id: I4aa2c6138f58df6d4a86301a5c0436edcb19ab70


[ROCm/clr commit: fa66140ee5]
2020-04-14 09:47:59 -04:00
Yaxun (Sam) Liu 2406fa8a3d Disable device side malloc (#2009)
* Disable device side malloc

Currently device side malloc is not working and takes excessive
device memory.

Disable it for now until a working malloc is implemented.

Change-Id: I1ad908c1c53a83752383b4be96688a848642c699

[ROCm/clr commit: d556c3425b]
2020-04-14 16:07:14 +05:30