Maneesh Gupta
2ff0c7c7bf
Revert "SWDEV-252801 - Fix hipGetLastError/hipPeekAtLastError"
...
Temporarily reverting to resolve promotion issues.
This reverts commit b36803746b .
Change-Id: I578d1d627e4b9779b146bf2827894522d6673d13
[ROCm/clr commit: ce0995e799 ]
2021-10-04 05:15:43 -04:00
Maneesh Gupta
a4daa31a89
SWDEV-305592 - roc-obj missing execute permissions
...
Change-Id: I8d418c62805d5080c5054f815b4287cb1bcfa8fe
[ROCm/clr commit: dd4e3c9903 ]
2021-10-04 05:15:28 -04:00
Maneesh Gupta
f98233ab6a
SWDEV-305219 - SWDEV-305226 - Fix debian package name to hip-dev
...
Change-Id: Ic19b0edde812747ff7fd8daacd16b4dabe937ed7
[ROCm/clr commit: c4287c6650 ]
2021-09-29 03:34:21 -07:00
Sarbojit Sarkar
8923e6d97d
SWDEV-301823 - Optimized hipMemset2D/3D
...
Change-Id: I1e817ab135bfdf9b8f9af18c1bf2cd2e926db729
[ROCm/clr commit: 98c172c2e4 ]
2021-09-28 00:05:33 -04:00
Sarbojit Sarkar
2e1449e9af
SWDEV-304076 - Fix for Cuda build error
...
Change-Id: Ibca63a08b8d6d1235b51a06c0bc024cd284cee97
[ROCm/clr commit: 70e1fb6a5b ]
2021-09-27 23:55:52 -04:00
Sourabh
f1486e33e4
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
[ROCm/clr commit: 4177d20877 ]
2021-09-27 13:59:21 -04:00
Payam
ab21349df9
SWDEV-245531 - GLInterop: linux - Buffer Interop
...
adding back two missed changes back to cmakelists and amdhip.def
Change-Id: Ibe0ed655d3590f0add13c20b160078ae005feaaf
[ROCm/clr commit: b075718a0f ]
2021-09-23 17:10:37 -04:00
Jatin Chaudhary
1843c58544
SWDEV-297217 - Append user options after default options
...
Change-Id: I1bdd309f98997f805357baa5d3ff36063797460c
[ROCm/clr commit: c250a13849 ]
2021-09-21 15:12:36 -04:00
Sarbojit Sarkar
b97595d514
SWDEV-298667 - fix stream operation for Cuda
...
Change-Id: Ida91712e678e324b54293ba48dfca442be390783
[ROCm/clr commit: 7aaad05910 ]
2021-09-21 15:07:15 -04:00
Ajay
918575f762
SWDEV-301069 - null ptr check before calling getUserData
...
Change-Id: Iaff3acd44d89a9629efe0672cb45138942d7fa28
[ROCm/clr commit: 198530143c ]
2021-09-17 19:25:24 -04:00
agunashe
0cf25d1fd3
SWDEV-301069 - current device id saved while allocating memory
...
Change-Id: I57045119e7adf915074c547cbe76349a4cfd72d9
[ROCm/clr commit: 29adfcd3c0 ]
2021-09-14 12:19:44 -04:00
Satyanvesh Dittakavi
e7a40bf6f6
SWDEV-302147 - fix __hip_ds_permutef device function to return float
...
Change-Id: Ie452e90a7f7410401df4a66de468ad850403953c
[ROCm/clr commit: 673c2deed1 ]
2021-09-14 02:15:53 -04:00
Laurent Morichetti
b36803746b
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
[ROCm/clr commit: 3dc47bc839 ]
2021-09-09 12:29:05 -07:00
Laurent Morichetti
cb2eaff241
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
[ROCm/clr commit: 3911184607 ]
2021-09-09 12:19:41 -07:00
Jason Tang
0f5020cfb5
SWDEV-1 - switch to C++17
...
Change-Id: Ifdb1ecbf175949462c29035c007acb3e82fe8322
[ROCm/clr commit: 4d06d64939 ]
2021-09-09 10:16:43 -04:00
Sarbojit Sarkar
87862528be
SWDEV-276319 - Added missing null check
...
Change-Id: I0fcaa55b9a793cbb6c1d2f3022edf288dabea757
[ROCm/clr commit: 88186db4cd ]
2021-09-08 06:53:02 -04:00
Jatin Chaudhary
3231b56cbc
SWDEV-299162 - Use new comgr API to demangle names
...
Change-Id: I9e34518de94db30c345cd03c92801b8424b4e446
[ROCm/clr commit: 0faf1244b5 ]
2021-09-08 02:32:41 -04:00
Sarbojit Sarkar
0c08bbf838
SWDEV-300655 - HIP trace cleanup
...
Change-Id: Iebc1eefe8d81d2f1f8adbab47e1351f03635868f
[ROCm/clr commit: c8983ead49 ]
2021-09-08 00:32:47 -04:00
Satyanvesh Dittakavi
5bfa893ac8
SWDEV-301330 - Remove the hard coded driver version on HIP CUDA platform
...
Change-Id: I0eb10781acc7524174c7ae6fc552c824b7c94b0a
[ROCm/clr commit: b25e6d3716 ]
2021-09-02 09:03:04 +00:00
David Salinas
c6063fe27b
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
[ROCm/clr commit: 64cbd7951d ]
2021-09-02 01:12:38 -04:00
anusha GodavarthySurya
c0a835a9b9
SWDEV-296918 - Bring clang-format in sync with hip & rocclr
...
Change-Id: I905943b5040c3108741db6f2a00b20fb72043666
[ROCm/clr commit: d30f9335fc ]
2021-09-02 00:45:50 -04:00
anusha GodavarthySurya
64799f183f
SWDEV-300471 - updated hipFree to wait for all streams to finish
...
Change-Id: I4983ef48a9e720ed03128d83a8d23ad11024fd8f
[ROCm/clr commit: c9d9fd992a ]
2021-09-02 00:45:24 -04:00
jujiang
00bce2cfc2
SWDEV-286322 - clean up trailing white space
...
Change-Id: If2e3f72ff4901f20dc91539c7d3c290ebb2a2531
[ROCm/clr commit: e1cd8c5ae2 ]
2021-09-01 14:44:16 -04:00
Satyanvesh Dittakavi
1a9391cdb9
SWDEV-300584 - Update memory validation checks in hipMemPrefetchAsync
...
Change-Id: Ie3f07781da58a5d909b8e6d0284387493a97e488
[ROCm/clr commit: 9adc14a0f5 ]
2021-09-01 13:19:04 -04:00
Satyanvesh Dittakavi
1652a70d4a
SWDEV-300934 - Check if the stream is valid
...
Change-Id: I41797dc3e726c7eea6a405f20deebd6f59381b5e
[ROCm/clr commit: dda2613525 ]
2021-09-01 13:16:36 -04:00
Rahul Garg
f55e3f39d4
SWDEV-295859 Update HIP_VERSION
...
Change-Id: Ibc4ce0d87360b3a25f7a313fc4dcc05e57b4f5f4
[ROCm/clr commit: dab4457c14 ]
2021-08-31 05:25:43 +00:00
Saleel Kudchadker
73004099f7
SWDEV-295275 - Check HW event
...
Change-Id: I23dfe5626f38b13fbdb6478ab12a0122b03e4a98
[ROCm/clr commit: 6f71170772 ]
2021-08-30 15:55:58 -04:00
Tao Sang
c641ec60de
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
[ROCm/clr commit: 3f1cb97306 ]
2021-08-30 10:30:52 -04:00
Satyanvesh Dittakavi
7c92e51d68
SWDEV-298985 - Fix hipMemPrefetchAsync
...
Use the dst device specified to prefetch the data
Change-Id: Id3d2295e0ae500ba03031ef43473a2c29852e45f
[ROCm/clr commit: 037f161f2e ]
2021-08-27 06:53:09 -04:00
anusha GodavarthySurya
43b3e7d573
SWDEV-287869 - [HIP] Fix Centos/SLES builds
...
Change-Id: I20ce625263e04224a85d39df9cc5417f8af6d9ec
[ROCm/clr commit: 4d47bd64be ]
2021-08-27 05:17:38 -04:00
anusha GodavarthySurya
fb441e0062
SWDEV-297541 - Fix static lib package generation
...
Change-Id: Ie39cbe6d8a2cda659902f878ff69b45b93f41981
[ROCm/clr commit: b43badaba7 ]
2021-08-25 00:51:32 -04:00
Icarus Sparry
87c636e1e7
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
[ROCm/clr commit: aa52c5079f ]
2021-08-24 12:46:21 -04:00
Jatin Chaudhary
7b095ace14
SWDEV-293749 - Add cast before calling the builtin
...
Change-Id: I6224a3693f91a5b4e040bd76918ab04a56a6454b
[ROCm/clr commit: feed2de479 ]
2021-08-24 10:35:52 -04:00
Jatin Chaudhary
db604128a0
SWDEV-294764 - Trim spaces from demangled name before comparision
...
Change-Id: I6359c5c01f68be1bbe98d2f2e079ae9cb06709b0
[ROCm/clr commit: 221cf39d65 ]
2021-08-23 08:36:40 -04:00
anusha GodavarthySurya
6ee2e39b4b
SWDEV-287884 - [HIP] Package Versioning
...
Change-Id: I4a4d96f947a67713036437ed525359fd422fefe2
[ROCm/clr commit: 4bcca82634 ]
2021-08-19 06:15:44 -04:00
Payam
b3ead327cd
SWDEV-245531 - GLInterop - merging changes from opencl
...
Change-Id: I3e21ff89b64afaa406bf46221c0f82045e905b1f
[ROCm/clr commit: 710bedf5da ]
2021-08-16 19:22:46 -04:00
Satyanvesh Dittakavi
a49ebc4612
SWDEV-298982 - hipMemPrefetchAsync should not allow more bytes than the actual size allocated
...
Change-Id: If8df97a79a16d39c66c508a8927ae1b4c276663e
[ROCm/clr commit: a984cbf90c ]
2021-08-16 13:19:04 -04:00
Julia Jiang
291f3b02b3
SWDEV-291894 - update readme for branch info
...
Change-Id: Ib8e9462e4f67a5d51f75544a5034ef4427aea421
[ROCm/clr commit: a41c5c783b ]
2021-08-16 11:01:58 -04:00
cjatin
d898f71794
SWDEV-296918 - Adding unsafe atomic add operation for float and double type
...
Change-Id: I98eabb7412f604733a999bf5e89c2c80b91cfbb1
[ROCm/clr commit: 06e1e4f0de ]
2021-08-14 12:22:53 +05:30
Laurent Morichetti
ae091a2320
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
[ROCm/clr commit: 73ee1afb17 ]
2021-08-11 21:25:49 -07:00
Ammar ELWazir
efc02f62d0
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
[ROCm/clr commit: 0670e49806 ]
2021-08-11 11:06:10 -04:00
Vladislav Sytchenko
0bda91b6ba
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
[ROCm/clr commit: 88f6f3d581 ]
2021-08-10 11:37:49 -04:00
Vladislav Sytchenko
8dc0bb325a
SWDEV-297808 - Free sampler when destroying textures
...
Change-Id: Idaab76392d18c7f5fedc89497e93f0d17835001a
[ROCm/clr commit: b41d5d73d4 ]
2021-08-09 21:49:36 -04:00
Julia Jiang
6883ccde42
SWDEV-286322 - Remove execution permission
...
Change-Id: I96e603fc8d407c3a76fa1053bad81e45744b59ad
[ROCm/clr commit: 8835b897d5 ]
2021-08-05 14:04:06 -04:00
Sourabh Betigeri
1cbb056f4c
SWDEV-297689 - Moving the vendor specific builtin function calls to hip_cooperative_helper.h header file
...
Change-Id: I797bdde8fbb01285dfda0eac0f960ded260beb8e
[ROCm/clr commit: 8a4ca88477 ]
2021-08-02 19:14:42 -04:00
Rahul Garg
ab2cc17a2e
SWDEV-297563 - Move surface types
...
Change-Id: Ie2393fb32a30a76c39c81ce17497fa3b131a85b1
[ROCm/clr commit: ec39f62ee1 ]
2021-08-02 18:48:15 +00:00
Rahul Garg
62a018191f
SWDEV-297563 - Move declarations to hip
...
Change-Id: Ifdab79945ea2e625e8cef5cd71d638552e9a740b
[ROCm/clr commit: 3dd9dbb359 ]
2021-08-02 11:56:08 -04:00
pghafari
6a49667ae6
SWDEV-245531 - GLInterop: linux - Buffer Interop
...
in progress...
Change-Id: I6f2cd8ee19ffef93e4f2aa6a08e002a13722d78a
[ROCm/clr commit: 65fcb6a0aa ]
2021-07-30 02:43:41 -04:00
Rahul Garg
b5ae4cf403
Revert "SWDEV-293742 - script to update the copyrights end year"
...
This reverts commit de94f93e57 .
Reason for revert: Copyright year to be updated only when a file is getting modified in that year.
Change-Id: Id1ece634dce7e67da9f3f6e10103ef6214e72dab
[ROCm/clr commit: 91df8fc0e9 ]
2021-07-29 19:06:52 -04:00
kjayapra-amd
31213b7ea5
SWDEV-282289 - Do not compare Pre-processor directive with string.
...
Change-Id: I9cd76c57a5cdea8059f69cc56ba9dca278b4d04c
[ROCm/clr commit: bf677f91af ]
2021-07-29 06:55:42 -04:00