AI/rocm-systems
2
0
Förgrening 0
Kod Ärenden Pull-förfrågningar Actions Packages Projekt Släpp Wiki Aktiviteter
6 821 Incheckningar 3 Grenar 0 Taggar
314bdba632dc8e5f3b020c062b74af1c96a89612
Commit-Graf

52 Incheckningar

Upphovsman SHA1 Meddelande Datum
German Andryeyev 314bdba632 SWDEV-353281 - Add support for MemPool in graphs 
Implement hipDeviceGetGraphMemAttribute, hipDeviceSetGraphMemAttribute
and hipDeviceGraphMemTrim

Change-Id: I4f8fc1250ce1e8b7636d43d59ba7343158e45088
 2023-02-23 12:49:53 -05:00
Ioannis Assiouras e3633dc8f4 SWDEV-381402 - Derive hip::Stream from amd::HostQueue 
Change-Id: I6c1aca5eb350c32d974ae4ffcc725705355956d8
 2023-02-21 18:12:03 -05:00
Ioannis Assiouras 8b87ccb8cc SWDEV-381402 - convert host_device to host_context of type amd::Context* 
Change-Id: Ic1cb9a3fa64e16699fad7e9ec6679f1d34b14bef
 2023-02-16 17:49:12 -05:00
pghafari 03f62b90ef SWDEV-377571 - adding scopelock for hipDeviceReset 
Change-Id: I3dd95a40d6abff721a4774f26e99d1162bafdfa1
 2023-02-07 11:29:20 -05:00
Ajay GunaShekar 1f4176062b SWDEV-372757 - Don't destroy null queue in MT 
This reverts commit f39655c0c8.

Reason for revert: patch does not fix all stream hangs. So another patch was merged which fixes all issues.

Change-Id: I332d1ea29c23747b46b7667fe3e34e0ceefd2b23
 2023-01-25 23:41:16 -05:00
Anusha GodavarthySurya d422ad0ec1 SWDEV-376407 - Track manual nodes added during capture 
Change-Id: Ic44f842c303eed0eff08b6ee5922976d96a52c71
 2023-01-18 03:27:41 -05:00
sdashmiz be966acb0c SWDEV-360031 - check for stream capture finish. 
- stream capture should be done before any sync APIs.

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: I3d65f67ee68777be71f97f48d460ccaefdd4e1af
 2023-01-16 13:09:24 -05:00
Ajay c6a7ce66bb SWDEV-369556 - Unit_hipMemGetAddressRange_Negative cases 
- return value for invalid device ptr
- offset greater than size

Change-Id: I8bcf878c3c1c0a29836ea664bfb9048e1114b74e
 2023-01-10 06:57:54 -05:00
German f39655c0c8 SWDEV-372757 - Don't destroy null queue in MT 
Skip destruction of the null queue for MT. Windows can destroy worker
thread on exit during the stream destruction, causing a race condition.

Change-Id: I3e4bc3ab2b477d38c0aec1fc59e6f1af0f8f6b0f
 2023-01-09 00:03:09 -05:00
German Andryeyev 38ad6234f9 SWDEV-360031 - Erase destroyed stream from capture 
Parallel streams can be destroyed during capture. Make sure runtime
removes the destoryed streams from the list of parallel captured streams

Change-Id: I46b6cbb951e8711f0bf02f2826c3b890b2541ffe
 2023-01-03 13:34:07 -05:00
pghafari a643c199de SWDEV-356549 - del Null strm in destroyAllStreams 
Change-Id: Ie04172ee39e6333247d07791dffda753a8b9ef41
 2022-12-29 15:45:54 -05:00
Ioannis Assiouras b83271b4ca SWDEV-374402 - Added check for invalid events in hipExtLaunchKernel 
Change-Id: I8dfd69aa1ef38971a72b98c723d2099347a66d11
 2022-12-21 12:37:12 -05:00
Ioannis Assiouras 30e740023b SWDEV-369548 - Disallow opening an ipc mem handle in the originating process. 
Change-Id: Icce5e41a220566141bd7d92b7199d477f60bed8e
 2022-12-14 04:52:21 -05:00
sdashmiz b665b9a6e8 SWDEV-365587 - reuse the id from capturing stream 
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: I65f5be3fcc4cffcf3eb5762fd0b43fd051c145c2
 2022-11-24 10:35:14 -05:00
sdashmiz c5e7b56463 SWDEV-366974 - add proper error 
- Null stream correct error when blocing stream is being captured

Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: I0d902a4f4ef02736a6db60ba7bffa7c20011bc84
 2022-11-21 10:39:21 -05:00
Rakesh Roy 8b391ef18c SWDEV-351969 - TLS Optimization 
- Aggregate all TLS(Thread Local Storage) variables into a single class
- This is to improve cache accesses per thread

Change-Id: Ic8361eaeae290fff00254684e309471958365eb9
 2022-10-09 22:08:14 -04:00
Saleel Kudchadker 1ea4d588ef SWDEV-301667 - Pretty print logs 
Change-Id: Ide95a5f8d35d81d4a9eb658f40ae2e82ffa3d97f
 2022-08-30 12:32:11 -04:00
Anusha Godavarthy Surya 0e2b348ef4 SWDEV-344166 - Updated HIP APIs to return hipErrorNoDevice when there are no devices in the system 
Change-Id: I636828ff39d3b404f89bcc6e2cb7348d92c897ff
 2022-07-22 06:59:19 -04:00
Sarbojit Sarkar 1074b22c48 SWDEV-333073 - HIP_INIT_API to handle no return case 
Change-Id: I78d43e88cc196047a4cb5d6fcf756339c0e46e80
 2022-06-24 12:53:18 -04:00
Jaydeep 1032581ded SWDEV-336548 - Check for valid hipArray pointer in hipFreeArray 
Change-Id: Icf0d47eeca7b5dd390a6a9c53b622b3680688ca4
 2022-06-18 00:56:33 -04:00
Ajay 1abd0d6ecf SWDEV-332522 - ipcEvents Avoid deadlock b/w streamWait & Event 
Using device write to set 0 to signal while streamWaitEvent is checking
the signal.
Use app in SWDEV-314307 to verify this fix
Requires vdi #668012 change to work

Change-Id: Ie329a29cfaeb5d144b92cda36773646f913ca73d
 2022-04-26 11:59:01 -04:00
German Andryeyev b4c5a01fbc SWDEV-333607 - Avoid synchronization of all GPU(s) 
Use the original device from creation to sync before host memory
free.

Change-Id: I510e34afa7accf69e3d01338587bbc817b981cec
 2022-04-21 15:36:04 -04:00
Sarbojit Sarkar 71b5235c64 SWDEV-332809 - Fix for OpenMp crash 
Change-Id: I70445edf76261ab8ecf174614f23bd9fb8d60881
 2022-04-19 11:29:19 -04:00
Sarbojit Sarkar fc1f02bbed SWDEV-323441 - support for default stream per thread 
Change-Id: I0032da0357f5cffbf5e4ec4a02435d2a128a262b
 2022-04-18 23:19:55 -04:00
German Andryeyev 5957ff9f7b SWDEV-311271 - Make sure memory pool can accept default stream 
Add lock protection for access to the pool list.
Remove destroyed stream from the list of the safe streams

Change-Id: I1863b89bd3f5e188c161227cc790c3adaf72cc58
 2022-04-18 10:34:21 -04:00
German Andryeyev fb835c6f3e SWDEV-328670 - Pass the size of allocation 
The actual size of allocation can be different from the original
request due to alignments. Pass the size of the original request
for validation during the arena object look-up

Change-Id: I30000046b1ec56abe743e43113046144fd3edbc6
 2022-04-01 11:18:55 -04:00
German Andryeyev 539d264eb0 SWDEV-311271 - Initial mempool implementation 
HIP_MEM_POOL_SUPPORT controls memory pool support in runtime.
Currently it's disabled by default. The initial change doesn't
include: IPC, MGPU, virtual memory alloc, suballoc, defragmentation,
internal dependencies.

Change-Id: Ibed8528ebec698b045ebb247e49c0ecd6e587ed7
 2022-03-31 09:21:37 -04:00
Sourabh Betigeri c47a55f371 SWDEV-328295 - Returns a vector of graphNodes with reference to retain scope 
Change-Id: Ib51c9bdbcb5e5cea76f111cb54bde724053073ff
 2022-03-18 12:28:57 -04:00
Christophe Paquot 925c742d42 SWDEV-323472 - Fix hipThreadExchangeStreamCaptureMode 
Matching CUDA's described behavior: Threads have their own mode.

Change-Id: I3ea15826305a607bff73eb317c4ef62728ed5dc8
 2022-03-15 10:53:02 -04:00
Ajay 0e94178c03 SWDEV-314982 - hipStreamGetCaptureInfo negative cases 
Change-Id: I98a65fc60610f89184b54152c8e33f59d74e3850
 2022-02-16 18:06:12 -05:00
Satyanvesh Dittakavi 6e562f4d83 SWDEV-306940 - Fix hipamd errors/warnings found by CppCheck 
Change-Id: Ia93d4f5262ea4269d8031edbfd27033b887e5300
 2022-02-05 08:42:47 -05:00
Sarbojit Sarkar 3e2cc04da5 SWDEV-320901 - Added HIP_INIT_API_NO_RETURN 
Change-Id: Ic79acc21f6a92fcb24527d4f121ae96b13192f75
 2022-01-31 23:29:29 -05:00
haoyuan2 167810d6c8 SWDEV-318872 - workaround explicit loading functional issue in Blender 
Change-Id: I6857a8724f164641bc8d656367736e0fa16a158e
 2022-01-24 14:55:08 -05:00
anusha GodavarthySurya e3585209d7 SWDEV-313856, SWDEV-313907, SWDEV-313915 - Export StreamCapture APIs, handle few graph negitive senarios, set event, parallelstreams for endcapture 
Change-Id: I3c6008e1a1195cd2e1a14ef24c943ef6b54033ab
 2021-12-14 05:54:13 -05:00
haoyuan2 d1a491b30b SWDEV-311585 - workaround dynamic loading functional issue in Blender 
Change-Id: I815724c0bdcb712e40ec1ed11b9632fab7243f69
 2021-12-10 11:52:15 -08:00
haoyuan2 981ef060fb SWDEV-290298 - add a flag to indicate the primary context active status 
Change-Id: Id13d132923fcef697b689e75b6aa04060923a2ad
 2021-12-09 23:32:16 -05:00
pghafari 24e984fd57 SWDEV-310292 - checking hip initialization 
Change-Id: I83c9a0d511699c150abe61c3053cc4de2f7f1205
 2021-11-29 14:59:19 -05:00
Saleel Kudchadker 0d5bc833c3 SWDEV-299893 - Set preferred node affinity 
Set affinity to the node nearest to default GPU at init. Afterthat
set it to NUMA node thats nearest to whatever GPU is set with
hipSetDevice
Change-Id: I85749258ea7c25385096ffe4089a70c948f332c7

Change-Id: I99a92c922655e22955bee512073b6ac8e6ced3a2
 2021-11-21 01:13:36 -05:00
anusha GodavarthySurya 3e2c2dfb71 SWDEV-240806 - hip stream capture handling for memory APIs 
Change-Id: Ie29493cd09421175c3ce5a198f8c2c299739f997
 2021-11-17 00:15:13 -08:00
kjayapra-amd 7145c500b3 SWDEV-298434 - Delete texture references resources before deleting the ptr. 
Change-Id: Ib616aadd45eced1b10891c908e986bbeddc08288
 2021-11-12 11:20:47 -05:00
anusha GodavarthySurya f6456c5e27 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
 2021-10-06 00:31:42 -07:00
anusha GodavarthySurya 1c51d82dd5 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
 2021-10-05 07:44:54 -07:00
Maneesh Gupta ce0995e799 Revert "SWDEV-252801 - Fix hipGetLastError/hipPeekAtLastError" 
Temporarily reverting to resolve promotion issues.

This reverts commit 3dc47bc839.

Change-Id: I578d1d627e4b9779b146bf2827894522d6673d13
 2021-10-04 05:15:43 -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
Sarbojit Sarkar c8983ead49 SWDEV-300655 - HIP trace cleanup 
Change-Id: Iebc1eefe8d81d2f1f8adbab47e1351f03635868f
 2021-09-08 00:32:47 -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
Julia Jiang 8835b897d5 SWDEV-286322 - Remove execution permission 
Change-Id: I96e603fc8d407c3a76fa1053bad81e45744b59ad
 2021-08-05 14:04:06 -04:00
Vladislav Sytchenko a89d34d0c9 SWDEV-292547 - Fix Windows build 
This addresses the warning `not all control paths return a value`.

Change-Id: Ibbb5eda9758dca5cc94c8efba9bbc6910362d6ba
 2021-07-27 10:52:28 -04:00
Sarbojit Sarkar c3ca1faee7 SWDEV-292547 - hipStreamPerThread support 
Change-Id: Id621ce073b0fee9eac03c59ffb78b197fda4ddb5
 2021-07-26 20:51:51 -04:00
agunashe d9d9e81acb SWDEV-293742 - Update copyrights end year for hipamd 
Change-Id: I08f620f84563a9214b59f1b943ed091b67229eab
 2021-07-09 12:08:39 -04:00