Commit Graph

5429 Commits

Author SHA1 Message Date
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
Anusha GodavarthySurya 4c1f84b6ec SWDEV-287869 - [HIP] Package rename
Change-Id: Ic4ddece01bfc34d586cfaba3193c56ce0540626d


[ROCm/clr commit: 50e57158eb]
2021-07-29 05:55:44 -04:00
Tao Sang eac431380a SWDEV-294591 - Fix hipEventIpc failure on NV
make hipIpcOpenEventHandle has the same behavour of cudaIpcOpenEventHandle.

Change-Id: I3fe6dbc35a7b14ba9119df297b7885df83d28149


[ROCm/clr commit: c87a352288]
2021-07-28 20:34:11 -04:00
Vladislav Sytchenko 9b27759df1 SWDEV-240806 - Fix Windows build
Fixes error "All control paths should return a value".

Change-Id: I4178ee4b644cd54629bd2a2f4c57eb58d2709ab8


[ROCm/clr commit: 578b6d32f4]
2021-07-28 19:18:04 -04:00
Tao Sang 17a02d1ad5 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


[ROCm/clr commit: 3452a09975]
2021-07-28 11:34:38 -04:00
Anusha GodavarthySurya f25a9e8217 SWDEV-240806 - Added API hipGraphAddMemcpyNode1D, hipGraphAddEmptyNode, hipGraphExecKernelNodeSetParams
Change-Id: I0d7ec8c0ea1abc3fc0f1e10fa7865f355d9cf2ad


[ROCm/clr commit: a71f54d9e9]
2021-07-28 00:09:16 -04:00
Vladislav Sytchenko 8f197606a2 SWDEV-292547 - Fix Windows build
This addresses the warning `not all control paths return a value`.

Change-Id: Ibbb5eda9758dca5cc94c8efba9bbc6910362d6ba


[ROCm/clr commit: a89d34d0c9]
2021-07-27 10:52:28 -04:00
German Andryeyev 9db25e5985 SWDEV-290384 - Add compilation option for direct disaptch
DISABLE_DIRECT_DISPATCH flag will control compilation.
Default is OFF.

Change-Id: I7d4207b8a79f5e3eb61440c5fbe5034c6ce75cce


[ROCm/clr commit: a852370a25]
2021-07-27 00:07:27 -04:00
Sarbojit Sarkar 597831dd66 SWDEV-292547 - hipStreamPerThread support
Change-Id: Id621ce073b0fee9eac03c59ffb78b197fda4ddb5


[ROCm/clr commit: c3ca1faee7]
2021-07-26 20:51:51 -04:00
Tao Sang f97143a0d9 SWDEV-294594 - Fix hipPointerGetAttributes test on NV
Replace return value of hipPointerGetAttributes() on NV from
hipErrorUnknown to hipErrorInvalidValue if memory has been freed.

Change-Id: I3fe6dbc35a7a14aa9109df297b7885df83d28149


[ROCm/clr commit: 203c4b9b35]
2021-07-26 11:30:22 -04:00
Tao Sang 46737b278a SWDEV-294596 - Make hipModuleGetGlobal match cuda
Make hipModuleGetGlobal match cuModuleGetGlobal behavour.
That is, if one of the first two parameters is nullptr, ignore it.

Change-Id: I3fe6dbc35a7b14aa9119df297b7885df83d28048


[ROCm/clr commit: b58355b065]
2021-07-23 23:06:56 -04:00
Rahul Garg 969db71ffa SWDEV-288929 - Fix typo
Change-Id: I56acb7ce3021304b2cd2c8bc2b840cbdcdefd072


[ROCm/clr commit: ba0220578e]
2021-07-23 07:10:31 -04:00
Sourabh Betigeri c396ebad94 SWDEV-292523 - [hipamd]Change in the signature of streamOperations APIs, particularly 'value' arg to unsigned 'value'
Change-Id: I7e31508622865b9986c886c4218ba394ffe9cf9e


[ROCm/clr commit: cbbf627662]
2021-07-22 16:24:27 -04:00
Vladislav Sytchenko aec5e9325c SWDEV-240807 - Fix Windows build
These are defined as structs in HIP headers, not as classes.

Change-Id: Ie53424a026424c71fd45db3a60e5be906d472c5d


[ROCm/clr commit: d3062d3bc2]
2021-07-21 20:40:16 -04:00
Vladislav Sytchenko b80bd6e21c SWDEV-286884 - Correct hiprtc installation on Windows
Generated .lib binary should go into the lib/ folder.

Change-Id: I552552745457368dc48f3a4b727a731a6bea822b


[ROCm/clr commit: f9732d7f20]
2021-07-21 09:29:17 -04:00
Christophe Paquot f9116b4328 SWDEV-281658 - Preserve the callback IDs enum ordering
Use continue instead of break to make sure we process the
whole hip_runtime_api.h file.

Change-Id: Ied2a8df69ed9eb1dc04d6b2d0d7b117ce2a2b6b3


[ROCm/clr commit: 9a510f1cf1]
2021-07-20 20:12:21 -07:00
Christophe Paquot 9488cd1194 SWDEV-240807 - Fix header file
Remove class useage from header file

Change-Id: Ibe1a59241f000cc162dd865484c313e56c4db95f


[ROCm/clr commit: 223c0364f8]
2021-07-20 20:32:55 -04:00