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

6132 Коммитов

Автор SHA1 Сообщение Дата
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
Julia Jiang d407cc46ee SWDEV-288929 - update hipamd document
Change-Id: I638afb4c7f0b96df3f0c1cc0b3bf04ab57692d27


[ROCm/clr commit: 70e18827a6]
2021-07-19 17:21:39 -04:00
kjayapra-amd d579eb9104 SWDEV-282289 - Use preprocessor directive for atomicAdd to support backward compatibility.
Change-Id: I73f058040afaa782bf6a491b8761a040fbd5b571


[ROCm/clr commit: a8e0ab621e]
2021-07-19 10:46:01 -04:00
David Salinas 340ed39723 SWDEV-287640 - rename llvm-amdgpu pkg to rocm-llvm
package llvm-amdgpu is being renamed to rocm-llvm

Change-Id: Ifc0a4deef981b3cced6225b5d1ba1a07d34f0e8b


[ROCm/clr commit: 11c28b9fe3]
2021-07-16 14:44:01 -04:00
Vladislav Sytchenko e89543a8bb SWDEV-240807 - Fix Windows builds
Unimplemented APIs should not be in the linker export script.

Change-Id: Ieabfc829bf950bc49e79f2851fb247a4c95b9427


[ROCm/clr commit: f7f418c101]
2021-07-15 11:34:49 -04:00
Tao Sang 2fe45ab575 SWDEV-294588 - Enable NV printf DTests
Add hipLimitPrintfFifoSize.
Add hipDeviceSetLimit(hipLimit_t limit, size_t value) for NV.

Change-Id: Ife884e0c3081b317bdadc8bec7814d1d7c60153a


[ROCm/clr commit: e0ae326f4a]
2021-07-15 11:02:13 -04:00
Aaron Enye Shi a620f5b973 SWDEV-283267 - HIPRTC Pass COMGR correct msvc flags
On Windows, to enable comgr and hiprtc to enable compilation,
provide the correct target flags. Otherwise comgr cannot
figure out which platform to compile for.

Change-Id: I6426e518c8d695342cb49df0ebdeac0437da83df


[ROCm/clr commit: 58246c78d7]
2021-07-15 08:34:47 -04:00
Jatin Chaudhary ac37a1a3ca SWDEV-283267 - Deprecate -use-pch option and add hiprtc builtin header for all hiprtc programs
Change-Id: I2ed98c65fb310d89a787510c6a362ee0929b83d9


[ROCm/clr commit: 7b8b7a9ba1]
2021-07-15 08:34:24 -04:00
Aaron Enye Shi 20f48d91aa SWDEV-294395 - HIPRTC add definitions for amd_hip_vector_types.h
Add typedefs for int32 and int64. Add templates provided in
system headers such as type_traits used in our HIP header
amd_hip_vector_types.h. Make replacements for clang builtin,
__is_convertible_to.

Change-Id: I4129b3f4f37238e2dda5b64d55e5cffe4d4480c6


[ROCm/clr commit: ff8c20c092]
2021-07-15 05:41:51 -04:00
Anusha GodavarthySurya 5464d40940 SWDEV-240807 - Added Implementation for few more graph APIs
Change-Id: I76336a22233a208a3f54ff9e90f0c5bf4a1bddb4


[ROCm/clr commit: e5cbfa8ca9]
2021-07-14 20:56:36 -07:00
kjayapra-amd 2b5806542f SWDEV-278500 - Implement missing atomic APIs and types to match CUDA.
Change-Id: I5f5bd94af9b68853bf354c8f90da217434934ddd


[ROCm/clr commit: 4aab5c29ff]
2021-07-13 22:15:57 -04:00
Vladislav Sytchenko 51ea4ac113 SWDEV-281658 - Disable HIP profiling for Windows
Currently generating profiling header is not supported on Windows,
hence why the feature is being disabled.

Change-Id: I1f6d70ec3d68356799c5ecc89469eb007ae894f8


[ROCm/clr commit: 08ecf21ddf]
2021-07-12 19:45:09 -04:00