AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
6,169 Commits 3 Branches 0 Tags
d0cb0062a058f74d0796c9c01e2f0c067fef8108
Commit Graph

1196 Commits

Author SHA1 Message Date
pghafari d0cb0062a0 SWDEV-245531 - GLInterop: removing GL dependency 
Change-Id: Ie8d794fff9518704d008b71c4d108fb01ea3fcb5


[ROCm/clr commit: c5acbf2685]
 2021-10-06 16:53:49 -04:00
anusha GodavarthySurya 20e5aace05 SWDEV-24806 - Added support for event wait and event record graph APIs 
hip graph implementation for APIs AddEventRecordNode, AddEventWaitNode, EventRecordNodeGetEvent, EventWaitNodeGetEvent, EventRecordNodeSetEvent,EventWaitNodeSetEvent, ExecEventRecordNodeSetEvent, ExecEventWaitNodeSetEvent

Change-Id: Ifde51f4591067795d6cbf5595372cbdbd8a7bc26


[ROCm/clr commit: f6456c5e27]
 2021-10-06 00:31:42 -07:00
anusha GodavarthySurya be487b261b SWDEV-24806 - Added support for memcpy related graph APIs 
hipGraphMemcpyNodeSetParams1D, hipGraphExecMemcpyNodeSetParams1D, hipGraphExecMemcpyNodeSetParams, hipGraphAddMemcpyNodeFromSymbol, hipGraphMemcpyNodeSetParamsFromSymbol, hipGraphExecMemcpyNodeSetParamsFromSymbol, hipGraphAddMemcpyNodeToSymbol, hipGraphMemcpyNodeSetParamsToSymbol, hipGraphExecMemcpyNodeSetParamsToSymbol

Change-Id: I6896144f340867d938aa1777880c78c46ca6f893


[ROCm/clr commit: c4eda85835]
 2021-10-05 22:43:49 -07:00
anusha GodavarthySurya d3424a31ac SWDEV-240806 - Fix windows build remove unused symbols 
Change-Id: I27524f2f0700ed5a9b78d46fbc8a19a516c46ad1


[ROCm/clr commit: a62b6110db]
 2021-10-05 21:10:44 -07:00
anusha GodavarthySurya 78f89618cb SWDEV-240806 - Added few Graph API Implementation 
hipGraph APIs clone, childGraph, RemoveDependencies, GetEdges,GetDependencies, GetDependentNodes, GetType and DestroyNode
hipStream APIs GetCaptureInfo, GetCaptureInfo_v2, UpdateCaptureDependencies.

Change-Id: Ib0f4cb8ea335698eecdd6d744ffab1e954153673


[ROCm/clr commit: 1c51d82dd5]
 2021-10-05 07:44:54 -07:00
anusha GodavarthySurya 4a7b23b848 SWDEV-287830 - Remove hardcoding of /opt/rocm path 
Change-Id: I3b654f46d8867651734804f19a4456e17ada740d


[ROCm/clr commit: 63cd524f1d]
 2021-10-05 07:38:01 -04:00
anusha GodavarthySurya ea786b1810 SWDEV-240806 - Added few more Graph APIs 
Change-Id: I028a1fdf30232b0c47443685e03d7ca410d2a0d0


[ROCm/clr commit: 1111468b49]
 2021-10-05 07:37:11 -04:00
Sarbojit Sarkar 96e7dcecd1 SWDEV-292547 - To match cuda behavior 
Change-Id: I3577609fcc5443949f73644196e8310fc49d887f


[ROCm/clr commit: 930807fd20]
 2021-10-05 00:31:05 -04:00
Ajay 48316f63e9 SWDEV-301069 - save device id during hipHostRegister 
Change-Id: I789b2252fa1a131ed1924b47718e355cb4fc9037


[ROCm/clr commit: 361dec890c]
 2021-10-04 12:07:29 -04:00
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
Sarbojit Sarkar 8923e6d97d SWDEV-301823 - Optimized hipMemset2D/3D 
Change-Id: I1e817ab135bfdf9b8f9af18c1bf2cd2e926db729


[ROCm/clr commit: 98c172c2e4]
 2021-09-28 00:05:33 -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
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
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
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
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 fb441e0062 SWDEV-297541 - Fix static lib package generation 
Change-Id: Ie39cbe6d8a2cda659902f878ff69b45b93f41981


[ROCm/clr commit: b43badaba7]
 2021-08-25 00:51:32 -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
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
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
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
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
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 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
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