AI/rocm-systems
2
0
Форкнуть 0
Код Задачи Запросы на слияние Действия Пакеты Проекты Релизы Вики Активность
6 828 коммитов 3 Ветки 0 Теги
23aa33200cd03b4caed7806fc5575a91ef8459be
Граф коммитов

55 Коммитов

Автор SHA1 Сообщение Дата
Sourabh Betigeri 02a3fcff26 SWDEV-326798 - Revert "SWDEV-326798 - Changes in stream sync behavior" 
This reverts commit 1932e88970.

Reason for revert: HIP tests on windows fails

Change-Id: I795ed19d76a41e2fd9971414cefa5bd3be45d4bc


[ROCm/clr commit: 08c8972d97]
 2023-02-28 02:28:12 -05:00
Sourabh Betigeri 1932e88970 SWDEV-326798 - Changes in stream sync behavior 
Change-Id: If6d0b3876a9bf197c7e49273eaa5ca5bfae46d0b


[ROCm/clr commit: 51adec2730]
 2023-02-27 16:48:14 -05:00
Ioannis Assiouras ea7d5037b9 SWDEV-381402 - Remove unused getNullStream() from device. Make stream destructor private. 
Change-Id: Idde30a8bfe97a525bd9f9fb50698a5cb14b798fc


[ROCm/clr commit: 06927fd3c1]
 2023-02-24 10:42:46 +00:00
German Andryeyev 2e0fd95d74 SWDEV-353281 - Add support for MemPool in graphs 
Implement hipDeviceGetGraphMemAttribute, hipDeviceSetGraphMemAttribute
and hipDeviceGraphMemTrim

Change-Id: I4f8fc1250ce1e8b7636d43d59ba7343158e45088


[ROCm/clr commit: 314bdba632]
 2023-02-23 12:49:53 -05:00
Ioannis Assiouras 2633e62801 SWDEV-381402 - Derive hip::Stream from amd::HostQueue 
Change-Id: I6c1aca5eb350c32d974ae4ffcc725705355956d8


[ROCm/clr commit: e3633dc8f4]
 2023-02-21 18:12:03 -05:00
Ioannis Assiouras 5007a5f15d SWDEV-381402 - convert host_device to host_context of type amd::Context* 
Change-Id: Ic1cb9a3fa64e16699fad7e9ec6679f1d34b14bef


[ROCm/clr commit: 8b87ccb8cc]
 2023-02-16 17:49:12 -05:00
pghafari 24b7348137 SWDEV-377571 - adding scopelock for hipDeviceReset 
Change-Id: I3dd95a40d6abff721a4774f26e99d1162bafdfa1


[ROCm/clr commit: 03f62b90ef]
 2023-02-07 11:29:20 -05:00
Ajay GunaShekar 01fe2ea09e SWDEV-372757 - Don't destroy null queue in MT 
This reverts commit 3afbe3a155.

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

Change-Id: I332d1ea29c23747b46b7667fe3e34e0ceefd2b23


[ROCm/clr commit: 1f4176062b]
 2023-01-25 23:41:16 -05:00
Anusha GodavarthySurya f681854310 SWDEV-376407 - Track manual nodes added during capture 
Change-Id: Ic44f842c303eed0eff08b6ee5922976d96a52c71


[ROCm/clr commit: d422ad0ec1]
 2023-01-18 03:27:41 -05:00
sdashmiz 42a08627ef 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


[ROCm/clr commit: be966acb0c]
 2023-01-16 13:09:24 -05:00
Ajay 433f99686b SWDEV-369556 - Unit_hipMemGetAddressRange_Negative cases 
- return value for invalid device ptr
- offset greater than size

Change-Id: I8bcf878c3c1c0a29836ea664bfb9048e1114b74e


[ROCm/clr commit: c6a7ce66bb]
 2023-01-10 06:57:54 -05:00
German 3afbe3a155 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


[ROCm/clr commit: f39655c0c8]
 2023-01-09 00:03:09 -05:00
German Andryeyev d8f1606489 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


[ROCm/clr commit: 38ad6234f9]
 2023-01-03 13:34:07 -05:00
pghafari b0bc6d6c7e SWDEV-356549 - del Null strm in destroyAllStreams 
Change-Id: Ie04172ee39e6333247d07791dffda753a8b9ef41


[ROCm/clr commit: a643c199de]
 2022-12-29 15:45:54 -05:00
Ioannis Assiouras be16c31b60 SWDEV-374402 - Added check for invalid events in hipExtLaunchKernel 
Change-Id: I8dfd69aa1ef38971a72b98c723d2099347a66d11


[ROCm/clr commit: b83271b4ca]
 2022-12-21 12:37:12 -05:00
Ioannis Assiouras f3c412b183 SWDEV-369548 - Disallow opening an ipc mem handle in the originating process. 
Change-Id: Icce5e41a220566141bd7d92b7199d477f60bed8e


[ROCm/clr commit: 30e740023b]
 2022-12-14 04:52:21 -05:00
sdashmiz bafdaa4f31 SWDEV-365587 - reuse the id from capturing stream 
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: I65f5be3fcc4cffcf3eb5762fd0b43fd051c145c2


[ROCm/clr commit: b665b9a6e8]
 2022-11-24 10:35:14 -05:00
sdashmiz dc97f3719e 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


[ROCm/clr commit: c5e7b56463]
 2022-11-21 10:39:21 -05:00
Rakesh Roy f149b21399 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


[ROCm/clr commit: 8b391ef18c]
 2022-10-09 22:08:14 -04:00
Saleel Kudchadker 79e1355f3a SWDEV-301667 - Pretty print logs 
Change-Id: Ide95a5f8d35d81d4a9eb658f40ae2e82ffa3d97f


[ROCm/clr commit: 1ea4d588ef]
 2022-08-30 12:32:11 -04:00
Anusha Godavarthy Surya 020a8dcede SWDEV-344166 - Updated HIP APIs to return hipErrorNoDevice when there are no devices in the system 
Change-Id: I636828ff39d3b404f89bcc6e2cb7348d92c897ff


[ROCm/clr commit: 0e2b348ef4]
 2022-07-22 06:59:19 -04:00
Sarbojit Sarkar 86481e460d SWDEV-333073 - HIP_INIT_API to handle no return case 
Change-Id: I78d43e88cc196047a4cb5d6fcf756339c0e46e80


[ROCm/clr commit: 1074b22c48]
 2022-06-24 12:53:18 -04:00
Jaydeep 147485a9aa SWDEV-336548 - Check for valid hipArray pointer in hipFreeArray 
Change-Id: Icf0d47eeca7b5dd390a6a9c53b622b3680688ca4


[ROCm/clr commit: 1032581ded]
 2022-06-18 00:56:33 -04:00
Ajay 12df44b4fc 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


[ROCm/clr commit: 1abd0d6ecf]
 2022-04-26 11:59:01 -04:00
German Andryeyev ecb4165943 SWDEV-333607 - Avoid synchronization of all GPU(s) 
Use the original device from creation to sync before host memory
free.

Change-Id: I510e34afa7accf69e3d01338587bbc817b981cec


[ROCm/clr commit: b4c5a01fbc]
 2022-04-21 15:36:04 -04:00
Sarbojit Sarkar a687844e68 SWDEV-332809 - Fix for OpenMp crash 
Change-Id: I70445edf76261ab8ecf174614f23bd9fb8d60881


[ROCm/clr commit: 71b5235c64]
 2022-04-19 11:29:19 -04:00
Sarbojit Sarkar e22f2e1714 SWDEV-323441 - support for default stream per thread 
Change-Id: I0032da0357f5cffbf5e4ec4a02435d2a128a262b


[ROCm/clr commit: fc1f02bbed]
 2022-04-18 23:19:55 -04:00
German Andryeyev 3de1a9e36c 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


[ROCm/clr commit: 5957ff9f7b]
 2022-04-18 10:34:21 -04:00
German Andryeyev 593844fdd6 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


[ROCm/clr commit: fb835c6f3e]
 2022-04-01 11:18:55 -04:00
German Andryeyev e7d2493402 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


[ROCm/clr commit: 539d264eb0]
 2022-03-31 09:21:37 -04:00
Sourabh Betigeri 3bd5aa1b47 SWDEV-328295 - Returns a vector of graphNodes with reference to retain scope 
Change-Id: Ib51c9bdbcb5e5cea76f111cb54bde724053073ff


[ROCm/clr commit: c47a55f371]
 2022-03-18 12:28:57 -04:00
Christophe Paquot 0c90a8cda6 SWDEV-323472 - Fix hipThreadExchangeStreamCaptureMode 
Matching CUDA's described behavior: Threads have their own mode.

Change-Id: I3ea15826305a607bff73eb317c4ef62728ed5dc8


[ROCm/clr commit: 925c742d42]
 2022-03-15 10:53:02 -04:00
Ajay 687298ba1c SWDEV-314982 - hipStreamGetCaptureInfo negative cases 
Change-Id: I98a65fc60610f89184b54152c8e33f59d74e3850


[ROCm/clr commit: 0e94178c03]
 2022-02-16 18:06:12 -05:00
Satyanvesh Dittakavi 51f8fc06e1 SWDEV-306940 - Fix hipamd errors/warnings found by CppCheck 
Change-Id: Ia93d4f5262ea4269d8031edbfd27033b887e5300


[ROCm/clr commit: 6e562f4d83]
 2022-02-05 08:42:47 -05:00
Sarbojit Sarkar 2d5abacc5e SWDEV-320901 - Added HIP_INIT_API_NO_RETURN 
Change-Id: Ic79acc21f6a92fcb24527d4f121ae96b13192f75


[ROCm/clr commit: 3e2cc04da5]
 2022-01-31 23:29:29 -05:00
haoyuan2 0dc8886919 SWDEV-318872 - workaround explicit loading functional issue in Blender 
Change-Id: I6857a8724f164641bc8d656367736e0fa16a158e


[ROCm/clr commit: 167810d6c8]
 2022-01-24 14:55:08 -05:00
anusha GodavarthySurya a6227d8d87 SWDEV-313856, SWDEV-313907, SWDEV-313915 - Export StreamCapture APIs, handle few graph negitive senarios, set event, parallelstreams for endcapture 
Change-Id: I3c6008e1a1195cd2e1a14ef24c943ef6b54033ab


[ROCm/clr commit: e3585209d7]
 2021-12-14 05:54:13 -05:00
haoyuan2 86520ebd83 SWDEV-311585 - workaround dynamic loading functional issue in Blender 
Change-Id: I815724c0bdcb712e40ec1ed11b9632fab7243f69


[ROCm/clr commit: d1a491b30b]
 2021-12-10 11:52:15 -08:00
haoyuan2 9735c1b617 SWDEV-290298 - add a flag to indicate the primary context active status 
Change-Id: Id13d132923fcef697b689e75b6aa04060923a2ad


[ROCm/clr commit: 981ef060fb]
 2021-12-09 23:32:16 -05:00
pghafari 26ddbfd8ec SWDEV-310292 - checking hip initialization 
Change-Id: I83c9a0d511699c150abe61c3053cc4de2f7f1205


[ROCm/clr commit: 24e984fd57]
 2021-11-29 14:59:19 -05:00
Saleel Kudchadker dd76f98009 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


[ROCm/clr commit: 0d5bc833c3]
 2021-11-21 01:13:36 -05:00
anusha GodavarthySurya 71215f1231 SWDEV-240806 - hip stream capture handling for memory APIs 
Change-Id: Ie29493cd09421175c3ce5a198f8c2c299739f997


[ROCm/clr commit: 3e2c2dfb71]
 2021-11-17 00:15:13 -08:00
kjayapra-amd e9238ae2f1 SWDEV-298434 - Delete texture references resources before deleting the ptr. 
Change-Id: Ib616aadd45eced1b10891c908e986bbeddc08288


[ROCm/clr commit: 7145c500b3]
 2021-11-12 11:20:47 -05: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 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
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
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
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
Julia Jiang 6883ccde42 SWDEV-286322 - Remove execution permission 
Change-Id: I96e603fc8d407c3a76fa1053bad81e45744b59ad


[ROCm/clr commit: 8835b897d5]
 2021-08-05 14:04:06 -04:00