Grafik Komit

6155 Melakukan

Penulis SHA1 Pesan Tanggal
Sarbojit Sarkar 70e1fb6a5b SWDEV-304076 - Fix for Cuda build error
Change-Id: Ibca63a08b8d6d1235b51a06c0bc024cd284cee97
2021-09-27 23:55:52 -04:00
Sourabh 4177d20877 SWDEV-292525 - [hipamd] Use a blit to streamWait
Implementation to use a blit kernel to perform
a hipStreamWait instead of an AQL packet.

Change-Id: I9d9bc1dd793c1454e91e68afb793460749e10d2e
2021-09-27 13:59:21 -04:00
Payam b075718a0f SWDEV-245531 - GLInterop: linux - Buffer Interop
adding back two missed changes back to cmakelists and amdhip.def

Change-Id: Ibe0ed655d3590f0add13c20b160078ae005feaaf
2021-09-23 17:10:37 -04:00
Jatin Chaudhary c250a13849 SWDEV-297217 - Append user options after default options
Change-Id: I1bdd309f98997f805357baa5d3ff36063797460c
2021-09-21 15:12:36 -04:00
Sarbojit Sarkar 7aaad05910 SWDEV-298667 - fix stream operation for Cuda
Change-Id: Ida91712e678e324b54293ba48dfca442be390783
2021-09-21 15:07:15 -04:00
Ajay 198530143c SWDEV-301069 - null ptr check before calling getUserData
Change-Id: Iaff3acd44d89a9629efe0672cb45138942d7fa28
2021-09-17 19:25:24 -04:00
agunashe 29adfcd3c0 SWDEV-301069 - current device id saved while allocating memory
Change-Id: I57045119e7adf915074c547cbe76349a4cfd72d9
2021-09-14 12:19:44 -04:00
Satyanvesh Dittakavi 673c2deed1 SWDEV-302147 - fix __hip_ds_permutef device function to return float
Change-Id: Ie452e90a7f7410401df4a66de468ad850403953c
2021-09-14 02:15:53 -04:00
Laurent Morichetti 3dc47bc839 SWDEV-252801 - Fix hipGetLastError/hipPeekAtLastError
hipGetLastError/hipPeekAtLastError should really return the last error
produced by any of the runtime calls that did not successfuly complete,
not just the error code of the last runtime call.

For example, in this snippet of code:

   1: hipLaunchKernelGGL(MyKernel, dim3(2), dim3(128), 0, 0, 10000,x);
   2: hipDeviceSynchronize();
   3: hipError_t error = hipGetLastError();

If the call to hipLaunchKernelGGL fails, hipDeviceSynchronize (which
succeeds) should not reset the last error to hipSuccess. hipGetLastError
should still return the non-success error code returned by
hipLaunchKernelGGL.

The last error is reset to hipSuccess after calling hipGetLastError.

Change-Id: Ib7c039067c53c94c99c8ecd83f54212bcef06f81
2021-09-09 12:29:05 -07:00
Laurent Morichetti 3911184607 SWDEV-252801 - Fix return HIP_RETURN(x)
HIP_RETURN(x) is not a value, it is a statement ending with a return,
this commit replaces all instances of "return HIP_RETURN(x)" with simply
"HIP_RETURN(x)"

Change-Id: I03293b2684a65367ff55e02b3a71ea49ec7a517a
2021-09-09 12:19:41 -07:00
Jason Tang 4d06d64939 SWDEV-1 - switch to C++17
Change-Id: Ifdb1ecbf175949462c29035c007acb3e82fe8322
2021-09-09 10:16:43 -04:00
Sarbojit Sarkar 88186db4cd SWDEV-276319 - Added missing null check
Change-Id: I0fcaa55b9a793cbb6c1d2f3022edf288dabea757
2021-09-08 06:53:02 -04:00
Jatin Chaudhary 0faf1244b5 SWDEV-299162 - Use new comgr API to demangle names
Change-Id: I9e34518de94db30c345cd03c92801b8424b4e446
2021-09-08 02:32:41 -04:00
Sarbojit Sarkar c8983ead49 SWDEV-300655 - HIP trace cleanup
Change-Id: Iebc1eefe8d81d2f1f8adbab47e1351f03635868f
2021-09-08 00:32:47 -04:00
Satyanvesh Dittakavi b25e6d3716 SWDEV-301330 - Remove the hard coded driver version on HIP CUDA platform
Change-Id: I0eb10781acc7524174c7ae6fc552c824b7c94b0a
2021-09-02 09:03:04 +00:00
David Salinas 64cbd7951d SWDEV-294828 - Move roc-obj binaries from hip to hipamd
SWDEV-280149 - roc-obj-ls/roc-obj-extract don't extract all kernel code

Change-Id: Ibe8aff5ff02fced4d9034740da72d3aa8d67c6ae
2021-09-02 01:12:38 -04:00
anusha GodavarthySurya d30f9335fc SWDEV-296918 - Bring clang-format in sync with hip & rocclr
Change-Id: I905943b5040c3108741db6f2a00b20fb72043666
2021-09-02 00:45:50 -04:00
anusha GodavarthySurya c9d9fd992a SWDEV-300471 - updated hipFree to wait for all streams to finish
Change-Id: I4983ef48a9e720ed03128d83a8d23ad11024fd8f
2021-09-02 00:45:24 -04:00
jujiang e1cd8c5ae2 SWDEV-286322 - clean up trailing white space
Change-Id: If2e3f72ff4901f20dc91539c7d3c290ebb2a2531
2021-09-01 14:44:16 -04:00
Satyanvesh Dittakavi 9adc14a0f5 SWDEV-300584 - Update memory validation checks in hipMemPrefetchAsync
Change-Id: Ie3f07781da58a5d909b8e6d0284387493a97e488
2021-09-01 13:19:04 -04:00
Satyanvesh Dittakavi dda2613525 SWDEV-300934 - Check if the stream is valid
Change-Id: I41797dc3e726c7eea6a405f20deebd6f59381b5e
2021-09-01 13:16:36 -04:00
Rahul Garg dab4457c14 SWDEV-295859 Update HIP_VERSION
Change-Id: Ibc4ce0d87360b3a25f7a313fc4dcc05e57b4f5f4
2021-08-31 05:25:43 +00:00
Saleel Kudchadker 6f71170772 SWDEV-295275 - Check HW event
Change-Id: I23dfe5626f38b13fbdb6478ab12a0122b03e4a98
2021-08-30 15:55:58 -04:00
Tao Sang 3f1cb97306 SWDEV-299966 - Fix hipModuleGetTexRef
hipModuleGetTexRef() returns success for any global device
variable name even if it's not a texture.
This is wrong thus will fail "hipModuleTexture2dDrv --tests 0x14"
This patch will compare the size to overcome this issue somehow.

Change-Id: I4a4d96f947a68713036437ee525359ff412fefe2
2021-08-30 10:30:52 -04:00
Satyanvesh Dittakavi 037f161f2e SWDEV-298985 - Fix hipMemPrefetchAsync
Use the dst device specified to prefetch the data

Change-Id: Id3d2295e0ae500ba03031ef43473a2c29852e45f
2021-08-27 06:53:09 -04:00
anusha GodavarthySurya 4d47bd64be SWDEV-287869 - [HIP] Fix Centos/SLES builds
Change-Id: I20ce625263e04224a85d39df9cc5417f8af6d9ec
2021-08-27 05:17:38 -04:00
anusha GodavarthySurya b43badaba7 SWDEV-297541 - Fix static lib package generation
Change-Id: Ie39cbe6d8a2cda659902f878ff69b45b93f41981
2021-08-25 00:51:32 -04:00
Icarus Sparry aa52c5079f Add dependency on rocm-core
The intention is to make all rocm-packages depend on a tiny rocm-core
package so that all of rocm can be removed by removing
rocm-core. Obviously it is less than ideal that you install by using
some variant of "apt install rocm" and remove everything by "apt
remove rocm-core", but this is easy to document. The alternative "apt
autoremove rocm" may remove unrelated packages.

Signed-off-by: Icarus Sparry <icarus.sparry@amd.com>
Change-Id: I95cf65550a33b8852ad3da15bbb5c1ac4a88bf46
2021-08-24 12:46:21 -04:00
Jatin Chaudhary feed2de479 SWDEV-293749 - Add cast before calling the builtin
Change-Id: I6224a3693f91a5b4e040bd76918ab04a56a6454b
2021-08-24 10:35:52 -04:00
Jatin Chaudhary 221cf39d65 SWDEV-294764 - Trim spaces from demangled name before comparision
Change-Id: I6359c5c01f68be1bbe98d2f2e079ae9cb06709b0
2021-08-23 08:36:40 -04:00
anusha GodavarthySurya 4bcca82634 SWDEV-287884 - [HIP] Package Versioning
Change-Id: I4a4d96f947a67713036437ed525359fd422fefe2
2021-08-19 06:15:44 -04:00
Payam 710bedf5da SWDEV-245531 - GLInterop - merging changes from opencl
Change-Id: I3e21ff89b64afaa406bf46221c0f82045e905b1f
2021-08-16 19:22:46 -04:00
Satyanvesh Dittakavi a984cbf90c SWDEV-298982 - hipMemPrefetchAsync should not allow more bytes than the actual size allocated
Change-Id: If8df97a79a16d39c66c508a8927ae1b4c276663e
2021-08-16 13:19:04 -04:00
Julia Jiang a41c5c783b SWDEV-291894 - update readme for branch info
Change-Id: Ib8e9462e4f67a5d51f75544a5034ef4427aea421
2021-08-16 11:01:58 -04:00
cjatin 06e1e4f0de SWDEV-296918 - Adding unsafe atomic add operation for float and double type
Change-Id: I98eabb7412f604733a999bf5e89c2c80b91cfbb1
2021-08-14 12:22:53 +05:30
Laurent Morichetti 73ee1afb17 Fix a build failure on Windows
Terse static_assert is only available starting with c++17. Add the
message argument since HIP is not compiled using c++17.

Change-Id: I77bc7ddb635e50ac3e6744d73c8751dc8299087e
2021-08-11 21:25:49 -07:00
Ammar ELWazir 0670e49806 SWDEV-294248 (Fixing Race Conditions):
Fixing race conditions that happened when enabling trace-period feature on the following code:
#include <hip/hip_runtime.h>
__global__ void
kernel ()
{
}
int
main (int argc, char **argv)
{
  for (size_t i = 0; i < 10000; ++i) {
    hipLaunchKernelGGL (kernel, 1, 1, 0, 0);
    hipDeviceSynchronize ();
  }
  return 0;
}

Change-Id: I6d2407ad06ecd602b93f53970859e1f4b67072e8
2021-08-11 11:06:10 -04:00
Vladislav Sytchenko 88f6f3d581 SWDEV-297808 - Correct sampler destruction logic
If the texture object was created from an array, then the array owns
the image SRD. Otherwise, if the texture object is a view, or was
created from a buffer, then it owns the image SRD.

The texture object always owns the sampler SRD.

Change-Id: Id88360c23b2b82418c8c3ae2dd569f427574d420
2021-08-10 11:37:49 -04:00
Vladislav Sytchenko b41d5d73d4 SWDEV-297808 - Free sampler when destroying textures
Change-Id: Idaab76392d18c7f5fedc89497e93f0d17835001a
2021-08-09 21:49:36 -04:00
Julia Jiang 8835b897d5 SWDEV-286322 - Remove execution permission
Change-Id: I96e603fc8d407c3a76fa1053bad81e45744b59ad
2021-08-05 14:04:06 -04:00
Sourabh Betigeri 8a4ca88477 SWDEV-297689 - Moving the vendor specific builtin function calls to hip_cooperative_helper.h header file
Change-Id: I797bdde8fbb01285dfda0eac0f960ded260beb8e
2021-08-02 19:14:42 -04:00
Rahul Garg ec39f62ee1 SWDEV-297563 - Move surface types
Change-Id: Ie2393fb32a30a76c39c81ce17497fa3b131a85b1
2021-08-02 18:48:15 +00:00
Rahul Garg 3dd9dbb359 SWDEV-297563 - Move declarations to hip
Change-Id: Ifdab79945ea2e625e8cef5cd71d638552e9a740b
2021-08-02 11:56:08 -04:00
pghafari 65fcb6a0aa SWDEV-245531 - GLInterop: linux - Buffer Interop
in progress...

Change-Id: I6f2cd8ee19ffef93e4f2aa6a08e002a13722d78a
2021-07-30 02:43:41 -04:00
Rahul Garg 91df8fc0e9 Revert "SWDEV-293742 - script to update the copyrights end year"
This reverts commit 5b5f934d58.

Reason for revert: Copyright year to be updated only when a file is getting modified in that year. 

Change-Id: Id1ece634dce7e67da9f3f6e10103ef6214e72dab
2021-07-29 19:06:52 -04:00
kjayapra-amd bf677f91af SWDEV-282289 - Do not compare Pre-processor directive with string.
Change-Id: I9cd76c57a5cdea8059f69cc56ba9dca278b4d04c
2021-07-29 06:55:42 -04:00
Anusha GodavarthySurya 50e57158eb SWDEV-287869 - [HIP] Package rename
Change-Id: Ic4ddece01bfc34d586cfaba3193c56ce0540626d
2021-07-29 05:55:44 -04:00
Tao Sang c87a352288 SWDEV-294591 - Fix hipEventIpc failure on NV
make hipIpcOpenEventHandle has the same behavour of cudaIpcOpenEventHandle.

Change-Id: I3fe6dbc35a7b14ba9119df297b7885df83d28149
2021-07-28 20:34:11 -04:00
Vladislav Sytchenko 578b6d32f4 SWDEV-240806 - Fix Windows build
Fixes error "All control paths should return a value".

Change-Id: I4178ee4b644cd54629bd2a2f4c57eb58d2709ab8
2021-07-28 19:18:04 -04:00
Tao Sang 3452a09975 SWDEV-296812 - Fix LINK_LANGUAGE issue
LINK_LANGUAGE support has some issue in CMake versions from 3.18.0 to
3.19.8 when complex libs' dependence exists. Jump to a known CMake
version 3.20.0 where the issue is fixed.

Change-Id: I3fe6dbc35a7b14baa210df297b7885df83d28178
2021-07-28 11:34:38 -04:00