Commit graph

5166 Commits

Autor SHA1 Nachricht Datum
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
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
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
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 aadb232c20 Fix MIOpen build failure
This is charrypick of 9ead991784
and https://github.com/ROCm-Developer-Tools/HIP/pull/2009

Fix cmake config file

Removed cmake target files under packaging directory.

Merged cmake config .in files for HIP-Clang and HCC as one.

Use cmake generated target files in both install and packaging.

This makes cmake config file consistent for make install and
make package.

Let device side malloc/free return nullptr and trap

Change-Id: I448f3ea2d4934648089bad371debc203f895cba6


[ROCm/clr commit: 4e1d05c4be]
2020-04-13 23:01:31 -04:00
kjayapra-amd e780909a6d SWDEV-227602 - Adding support for hipFuncGetAttribute
Change-Id: I16511274653c8c5521447eb2ed0fc5331dae8cba


[ROCm/clr commit: fc720c6287]
2020-04-13 21:23:04 -04:00
Vlad Sytchenko ba0c6101b0 Default stream needs to be initialized
Change-Id: I5cbf9076bffb51c0e99601393645f443c1658e13


[ROCm/clr commit: a9513154c7]
2020-04-13 15:32:35 -04:00
Vlad Sytchenko 60ec8d6047 Fix Windows build
Change-Id: I8c46c8ee82a6e47483d4c0430b483eead3772e5b


[ROCm/clr commit: ff3c449514]
2020-04-10 22:25:04 -04:00
Evgeny Shcherbakov 9b65761bdd Merge "fxing C compatibility (amd-master-next)" into amd-master-next
[ROCm/clr commit: 76363d90b8]
2020-04-10 13:41:47 -04:00
Maneesh Gupta 997cab12d3 Merge "Merge branch 'amd-master' into amd-master-next" into amd-master-next
[ROCm/clr commit: d02eb22c63]
2020-04-10 01:11:03 -04:00
Evgeny 8e6c6bc844 fxing C compatibility (amd-master-next)
Change-Id: Ib95b953bb49e0edbe044789b6ff81aaccb87f85f


[ROCm/clr commit: 8e2138b23b]
2020-04-10 00:08:09 -05:00
Vladislav Sytchenko 7779046de8 Correctly check max 1D image buffer size
VDI reports the limits in pixels, but user provides the size in bytes.

Make sure both values are in pixels before doing comparisons.

Change-Id: I082c7175c9fa4383e0b0ee38ff8c047c26ff20b4


[ROCm/clr commit: 28da0b89ea]
2020-04-09 21:37:43 -04:00
Vladislav Sytchenko 5ae3b3ac31 Fix Windows build
Change-Id: I8e219f8200875e3c46c1f54348317ba7ad8ae8ba


[ROCm/clr commit: 73751496e1]
2020-04-09 20:00:29 -04:00
Christophe Paquot 3b73ee5350 Merge "Remove a map lookup whenever we were getting the default stream" into amd-master-next
[ROCm/clr commit: 396e6a87ba]
2020-04-09 18:35:46 -04:00
Vladislav Sytchenko 3da0c744e1 Fix warnings when compiling with clang
The following warnings are addressed:

comparison of different enumeration types in switch statement

Change-Id: I6cb3948aeab7287851c57ecc1d4b3a439ab14ec6


[ROCm/clr commit: 524a81fcf5]
2020-04-09 17:07:48 -04:00
Christophe Paquot a7005281e8 Remove a map lookup whenever we were getting the default stream
Change-Id: I64b6d1deea41d81e94a58a83de287e78923656b3


[ROCm/clr commit: 137150f694]
2020-04-09 12:44:21 -07:00
Aakash Sudhanwa 50e6094f4f Merge "enabling hipPrintString (to master-next)" into amd-master-next
[ROCm/clr commit: 0f9266e3f1]
2020-04-09 15:08:35 -04:00
Vladislav Sytchenko de96ecc441 Disable all texture tests for VDI
Latest llvm already includes the texture/surface rework, but appropriate runtime changes have not been submitted.

Disable all texture related tests until http://gerrit-git.amd.com/c/compute/ec/hip/+/342147 is submitted.

Change-Id: I359c2eac6becdd3ca5110f2140679bd29d8ae54b


[ROCm/clr commit: b291104e7d]
2020-04-09 14:02:40 -04:00
Evgeny 68d860d006 enabling hipPrintString (to master-next)
Change-Id: I28859f3dbe5b867a858ca1d76c93e6fab6a68d1f


[ROCm/clr commit: cc60da5da1]
2020-04-09 09:57:27 -05:00
Maneesh Gupta e5ee180568 Merge branch 'amd-master' into amd-master-next
Change-Id: I3094c15008093f2072bcd38aca4ea90aeae2d97b


[ROCm/clr commit: 0ea6697192]
2020-04-09 06:31:00 -04:00
Sameer Sahasrabuddhe e2b46225c7 printf test: loop with divergent exit condition
Change-Id: I1071e4a240a280332bde669701c72228b9dea2df


[ROCm/clr commit: 7a51f9c5e8]
2020-04-09 10:20:11 +05:30
Michael LIAO 4fba98c2cf [hip] Fix volatile-qualified member function declartion.
- It should be a volatile-qualified member function instead of returning
  volatile type.

Change-Id: Id7aaa1953d56151b59e469ef22b9f4280f63bebb


[ROCm/clr commit: 35b001b33a]
2020-04-07 12:49:26 -04:00
Saleel Kudchadker 83e6fd2996 Merge "Revert "Wake up commandQueue before returning"" into amd-master-next
[ROCm/clr commit: f3e31ad00e]
2020-04-06 18:52:29 -04:00
Saleel Kudchadker fefdc97c2a Revert "Wake up commandQueue before returning"
This reverts commit 67c6b46cf0.

Reason for revert: German advised againt this change.

Change-Id: Ia1b1b9db60c965b2d9c006bd7d20012a9d7697e1


[ROCm/clr commit: 1b46f2622b]
2020-04-06 16:46:50 -05:00
Payam 3dbdfd27b7 updated LOG_LEVEL prints to print pid and tid
Change-Id: I8a9212b26bb7e312408a222823efcfd00344094b


[ROCm/clr commit: 14010cb705]
2020-04-06 16:58:25 -04:00