AI/rocm-systems
2
0
Bifurcation 0
Code Tickets Demandes d'ajout Actions Paquets Projets Publications Wiki Activité
6 369 Révisions 3 Branches 0 Étiquette
fe505c36ede7f9e4ca6b68dccb7de10fa98d0940
Graphe des révisions

81 Révisions

Auteur SHA1 Message Date
Satyanvesh Dittakavi 6a849eb690 SWDEV-327967 - Fix Segmentation fault in hipFree 
Queue creation and release fails during hipFree causing seg fault
if the null queue was not created until then and there is no
device memory left.

Change-Id: I118b86b58e777dac5415bc9ba0c4e23c986efa7d


[ROCm/clr commit: 4a90c3ccaf]
 2022-03-22 00:34:40 -04:00
Satyanvesh Dittakavi 4e2e28b23c SWDEV-326800 - hipStreamWaitEvent shouldnt accept flags other than 0 
Change-Id: Ic9e2e8e7ac5d34d4286356534810c8e7aa0ee5ad


[ROCm/clr commit: 796b8c2b62]
 2022-03-18 03:34:53 -04:00
Ajay 739e1dc4c4 SWDEV-313350 - hipStreamDestroy to remove the stream added to capturing list 
Change-Id: I0979766da7f1cf6082835d46701009902f55139e


[ROCm/clr commit: 782c411d1a]
 2022-03-17 17:22:51 +00:00
Saleel Kudchadker 8139cc4683 SWDEV-301667 - Fix build warnings 
Change-Id: Ice23b3d1a19a7958ca5c3caff34db2934b361a98


[ROCm/clr commit: 086aee0fcb]
 2022-03-02 20:49:18 -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
ajay a4e46d09e2 SWDEV-314307 - hipStreamWaitEvent to wait on remote IPC events 
Change-Id: Id97524ae9bc86d38376af2b0240f10d0dd5cc584


[ROCm/clr commit: bafc5bb30f]
 2022-01-19 20:10:02 +00:00
Sarbojit Sarkar 8f0c0822ad SWDEV-313905 - Fix segfault 
Change-Id: I7b7bbe80a169014b5d4a8de134351b9f8bf11735


[ROCm/clr commit: 017603703b]
 2022-01-11 23:40:25 -05: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
Sarbojit Sarkar c6afc74798 SWDEV-313905 - Fix for hipLaunchCooperativeKernel crash 
Change-Id: I41205171a9607962ab6b66f2ebc6f8dc9db7f158


[ROCm/clr commit: 9a51909058]
 2021-12-05 23:15:06 -05:00
Sarbojit Sarkar ecde1f5b96 SWDEV-292547 - Fix for hipStreamPerThread 
Change-Id: I9328c7ec92d954433f8e69732d91e65fa6fe013a


[ROCm/clr commit: 9e4766d990]
 2021-10-19 23:26:48 -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 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
Sarbojit Sarkar 96e7dcecd1 SWDEV-292547 - To match cuda behavior 
Change-Id: I3577609fcc5443949f73644196e8310fc49d887f


[ROCm/clr commit: 930807fd20]
 2021-10-05 00:31:05 -04: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
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
Saleel Kudchadker 73004099f7 SWDEV-295275 - Check HW event 
Change-Id: I23dfe5626f38b13fbdb6478ab12a0122b03e4a98


[ROCm/clr commit: 6f71170772]
 2021-08-30 15:55:58 -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
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
Sarbojit Sarkar 597831dd66 SWDEV-292547 - hipStreamPerThread support 
Change-Id: Id621ce073b0fee9eac03c59ffb78b197fda4ddb5


[ROCm/clr commit: c3ca1faee7]
 2021-07-26 20:51:51 -04:00
agunashe fae697b4d6 SWDEV-293742 - Update copyrights end year for hipamd 
Change-Id: I08f620f84563a9214b59f1b943ed091b67229eab


[ROCm/clr commit: d9d9e81acb]
 2021-07-09 12:08:39 -04:00
Christophe Paquot 96f580a267 SWDEV-276396 - Implement hipDeviceReset 
Add a hip::Stream::destroyAllStreams static function to destroy all streams
Also call MemObjMap::Purge

Change-Id: I6ee7e3f26ab1f1870a9271c65e99fb818134482b


[ROCm/clr commit: bea4fa8700]
 2021-06-15 13:13:09 -04:00
German Andryeyev 08611a1fe4 SWDEV-290367 - Make sure HIP checks for GPU signal 
Check GPU signal status for event before falling into CPU command
status validation

Change-Id: I66f15752d7dca550c0fa1a2252ec5a63817391c3


[ROCm/clr commit: dd8265fc87]
 2021-06-11 16:40:00 -04:00
Rahul Garg dd95d3d23c ROCMOPS-1956 - Push restructured code to hipamd 
hipamd will have AMD's ROCCLR based HIP backend implementation

Change-Id: Id7de9634519b4ce46fca71a1b61f3d5b1e3fc459


[ROCm/clr commit: 19c84bc604]
 2021-06-07 21:42:44 +00:00
Tao Sang 6227f3fae2 Remove hip-hcc codes: Part one 
Remove hip-hcc codes from hip code base
Simplify hip CMakeLists.txt to exclude hip-hcc
Simplify cmake cmd for hip-rocclr building
Some minor fixes

Change-Id: I1ae357ecfd638d6c25bca293c1724b026be21ecd


[ROCm/clr commit: 1cba7ec965]
 2020-12-09 15:49:47 -05:00
Jeff Daily 8b0a909b2b add IPC event support (#1996) 
[ROCm/clr commit: e943144b31]
 2020-04-17 10:31:22 +05:30
Jeff Daily 1a434dccd3 fix hipStreamAddCallback, block future work on stream (#1934) 
[ROCm/clr commit: 1444f850ac]
 2020-03-19 16:16:04 +05:30
Evgeny Mankov d191980c6a [HIP] Clean-up deprecated HIP error codes 
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle


[ROCm/clr commit: 4aaa2336a8]
 2019-12-23 17:01:35 +03:00
satyanveshd e2a0a547ff fixed directed tests fail when hcc bumped to 3.0 (#1678) 
Handled the HCC version check appropriately as few of the directed tests (SWDEV-212161) were failing when hcc was bumped to 3.0.

[ROCm/clr commit: d4dde7a27d]
 2019-11-20 21:37:52 +05:30
Sarbojit2019 2c00d66995 Revert [HIP] Fixed hipStreamAddCallback (#1674) 
This reverts commit 4d0b7e65bb.
Addresses SWDEV#212675.

[ROCm/clr commit: 8a3c36a424]
 2019-11-20 11:55:46 +05:30
Sarbojit2019 4d0b7e65bb [HIP] Fixed hipStreamAddCallback [SWDEV#165185] (#1425) 
Fixed hipStreamAddCallback() as requested in SWDEV#165185
Added unit test to test the behavior


[ROCm/clr commit: 97fca3439d]
 2019-11-07 13:18:12 +05:30
Jeff Daily 68f674205e consolidate thread local storage (#915) 
* all thread local access now through single struct

* clean up old commented-out code, more use of GET_TLS()

* fewer calls to GET_TLS by passing tls as a funtion argument

* revert unnecessary change to printf

* fix failing tests due to TLS change

* fix merge conflicts in ihipOccupancyMaxActiveBlocksPerMultiprocessor


[ROCm/clr commit: f337ae1edb]
 2019-08-05 09:51:02 +00:00
Jeff Daily df457ce2bd remove stream locks where it is safe to do so 
[ROCm/clr commit: 734c4b92c3]
 2019-07-22 17:38:51 +00:00
Aryan Salmanpour 4b06a21504 [hip] Move _criticalData of ihipStream_t class to private section and use criticalData() to access it (#1177) 
[ROCm/clr commit: 7e48231252]
 2019-07-04 00:42:19 +00:00
Anusha Godavarthy Surya e643bae27d Added missing NULL checks and corrected API return values as per validation 
[ROCm/clr commit: 4989452413]
 2019-06-27 00:19:05 +05:30
Rahul Garg f364b32e29 Add extension for kernel concurrency on same stream 
[ROCm/clr commit: 263e82a67a]
 2019-03-06 12:55:39 +05:30
root 873c51bdf5 rebase to master, tracer related changes 
[ROCm/clr commit: 0774b275c8]
 2018-11-13 15:50:34 +00:00
Evgeny 96b7f0404e renaming HIP_INIT_CB_API to HIP_INIT_API 
[ROCm/clr commit: e362688adf]
 2018-11-13 15:33:26 +00:00
Evgeny 7519b3f75e adding activity prof layer 
[ROCm/clr commit: 084a68be63]
 2018-11-13 15:33:26 +00:00
Maneesh Gupta 127f7d0320 Make HIP functional again with HCC from ROCm 1.9.x 
Change-Id: I214acdfd0b79dcf783993e44fe31baee64fd4dc3


[ROCm/clr commit: b01ac26948]
 2018-10-24 10:41:56 +05:30
Maneesh Gupta c4ed6b18fb Implementation for stream priority 
- Requires ROCm 1.9.x or higher
- Requires HCC with PR#886 merged

Change-Id: Id7c95ea091ee610e80c9ad815f1cb989cba570ca


[ROCm/clr commit: 07ee1f07d8]
 2018-10-05 16:27:46 +05:30
Siu Chi Chan 07d06ef156 callback handler: don't need to wait for the thread to become ready 
[ROCm/clr commit: e21e6ed3a0]
 2018-06-02 17:55:37 -04:00
Maneesh Gupta 46ddefedee Apply .clangformat to all repo source files 
Change-Id: I7e79c6058f0303f9a98911e3b7dd2e8596079344


[ROCm/clr commit: 9e47fccc89]
 2018-03-12 11:29:03 +05:30
Maneesh Gupta 290b5f1738 Implement hipStreamAddCallback 
Change-Id: Ib851e4d86ba9c8406ca37b88162ea483ccbc9d36


[ROCm/clr commit: cd9ba0d1e1]
 2017-12-19 16:06:14 +05:30
Ben Sander f761859993 hipStreamWaitEvent returns success if event created but not recorded 
[ROCm/clr commit: b5911acce2]
 2017-11-06 23:49:31 +00:00
Ben Sander 379b3fc7a0 Make hipEvent_t thread safe. 
Support re-recording of same event by different threads.

- Add criticalData structure to hipEvent_t, similar to mechanism used
  for streams, contexts, device.  Events are always locked
  after streams to avoid deadlock.
- ihipEvent_t::locked_copyCrit can be used to copy critical state
  including marker.  The critical state in the event can then
  be re-recorded.
- refactor hipEventElapsedTime.  Remmove stale debug code, native signal
  refs.


[ROCm/clr commit: 955cfbfdc7]
 2017-11-06 23:49:25 +00:00
Ben Sander 0c5ce41d7c Set event state AFTER it is recorded. 
[ROCm/clr commit: 1c65bb1684]
 2017-11-05 10:33:18 -06:00
Ben Sander 4df6b371ab Add ns-level timer for HIP API routines 
Refactor some miuses of ihipLogStatus, these should only be in top-level
HIP APIs and should be paired with HIP_API_INIT calls.


[ROCm/clr commit: dc7d993a02]
 2017-10-30 20:20:51 +00:00
Ben Sander 5134d6a2e9 hipStreamQuery uses av::is_empty. Add HIP_FORCE_NULL_STREAM. 
[ROCm/clr commit: fff74eee21]
 2017-08-31 03:00:14 +00:00
Ben Sander b45217fef0 Refactor hipStreamWaitEvent 
- Null streams use same flow as non-null.
- Add HIP_SYNC_STREAM_WAIT
- Resolve null stream.


[ROCm/clr commit: ed8c3ba7e7]
 2017-08-31 03:00:14 +00:00