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

78 Commits

Author SHA1 Message Date
Saleel Kudchadker 086aee0fcb SWDEV-301667 - Fix build warnings 
Change-Id: Ice23b3d1a19a7958ca5c3caff34db2934b361a98
 2022-03-02 20:49:18 -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
ajay bafc5bb30f SWDEV-314307 - hipStreamWaitEvent to wait on remote IPC events 
Change-Id: Id97524ae9bc86d38376af2b0240f10d0dd5cc584
 2022-01-19 20:10:02 +00:00
Sarbojit Sarkar 017603703b SWDEV-313905 - Fix segfault 
Change-Id: I7b7bbe80a169014b5d4a8de134351b9f8bf11735
 2022-01-11 23:40:25 -05: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
Sarbojit Sarkar 9a51909058 SWDEV-313905 - Fix for hipLaunchCooperativeKernel crash 
Change-Id: I41205171a9607962ab6b66f2ebc6f8dc9db7f158
 2021-12-05 23:15:06 -05:00
Sarbojit Sarkar 9e4766d990 SWDEV-292547 - Fix for hipStreamPerThread 
Change-Id: I9328c7ec92d954433f8e69732d91e65fa6fe013a
 2021-10-19 23:26:48 -04: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
Sarbojit Sarkar 930807fd20 SWDEV-292547 - To match cuda behavior 
Change-Id: I3577609fcc5443949f73644196e8310fc49d887f
 2021-10-05 00:31:05 -04:00
Laurent Morichetti 3911184607 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
 2021-09-09 12:19:41 -07: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
Saleel Kudchadker 6f71170772 SWDEV-295275 - Check HW event 
Change-Id: I23dfe5626f38b13fbdb6478ab12a0122b03e4a98
 2021-08-30 15:55:58 -04:00
Julia Jiang 8835b897d5 SWDEV-286322 - Remove execution permission 
Change-Id: I96e603fc8d407c3a76fa1053bad81e45744b59ad
 2021-08-05 14:04:06 -04:00
Anusha GodavarthySurya a71f54d9e9 SWDEV-240806 - Added API hipGraphAddMemcpyNode1D, hipGraphAddEmptyNode, hipGraphExecKernelNodeSetParams 
Change-Id: I0d7ec8c0ea1abc3fc0f1e10fa7865f355d9cf2ad
 2021-07-28 00:09:16 -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
Christophe Paquot bea4fa8700 SWDEV-276396 - Implement hipDeviceReset 
Add a hip::Stream::destroyAllStreams static function to destroy all streams
Also call MemObjMap::Purge

Change-Id: I6ee7e3f26ab1f1870a9271c65e99fb818134482b
 2021-06-15 13:13:09 -04:00
German Andryeyev dd8265fc87 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
 2021-06-11 16:40:00 -04:00
Rahul Garg 19c84bc604 ROCMOPS-1956 - Push restructured code to hipamd 
hipamd will have AMD's ROCCLR based HIP backend implementation

Change-Id: Id7de9634519b4ce46fca71a1b61f3d5b1e3fc459
 2021-06-07 21:42:44 +00:00
Tao Sang 1cba7ec965 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
 2020-12-09 15:49:47 -05:00
Jeff Daily e943144b31 add IPC event support (#1996) 2020-04-17 10:31:22 +05:30
Jeff Daily 1444f850ac fix hipStreamAddCallback, block future work on stream (#1934) 2020-03-19 16:16:04 +05:30
Evgeny Mankov 4aaa2336a8 [HIP] Clean-up deprecated HIP error codes 
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle
 2019-12-23 17:01:35 +03:00
satyanveshd d4dde7a27d 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.
 2019-11-20 21:37:52 +05:30
Sarbojit2019 8a3c36a424 Revert [HIP] Fixed hipStreamAddCallback (#1674) 
This reverts commit 97fca3439d.
Addresses SWDEV#212675.
 2019-11-20 11:55:46 +05:30
Sarbojit2019 97fca3439d [HIP] Fixed hipStreamAddCallback [SWDEV#165185] (#1425) 
Fixed hipStreamAddCallback() as requested in SWDEV#165185
Added unit test to test the behavior
 2019-11-07 13:18:12 +05:30
Jeff Daily f337ae1edb 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
 2019-08-05 09:51:02 +00:00
Jeff Daily 734c4b92c3 remove stream locks where it is safe to do so 2019-07-22 17:38:51 +00:00
Aryan Salmanpour 7e48231252 [hip] Move _criticalData of ihipStream_t class to private section and use criticalData() to access it (#1177) 2019-07-04 00:42:19 +00:00
Anusha Godavarthy Surya 4989452413 Added missing NULL checks and corrected API return values as per validation 2019-06-27 00:19:05 +05:30
Rahul Garg 263e82a67a Add extension for kernel concurrency on same stream 2019-03-06 12:55:39 +05:30
root 0774b275c8 rebase to master, tracer related changes 2018-11-13 15:50:34 +00:00
Evgeny e362688adf renaming HIP_INIT_CB_API to HIP_INIT_API 2018-11-13 15:33:26 +00:00
Evgeny 084a68be63 adding activity prof layer 2018-11-13 15:33:26 +00:00
Maneesh Gupta b01ac26948 Make HIP functional again with HCC from ROCm 1.9.x 
Change-Id: I214acdfd0b79dcf783993e44fe31baee64fd4dc3
 2018-10-24 10:41:56 +05:30
Maneesh Gupta 07ee1f07d8 Implementation for stream priority 
- Requires ROCm 1.9.x or higher
- Requires HCC with PR#886 merged

Change-Id: Id7c95ea091ee610e80c9ad815f1cb989cba570ca
 2018-10-05 16:27:46 +05:30
Siu Chi Chan e21e6ed3a0 callback handler: don't need to wait for the thread to become ready 2018-06-02 17:55:37 -04:00
Maneesh Gupta 9e47fccc89 Apply .clangformat to all repo source files 
Change-Id: I7e79c6058f0303f9a98911e3b7dd2e8596079344
 2018-03-12 11:29:03 +05:30
Maneesh Gupta cd9ba0d1e1 Implement hipStreamAddCallback 
Change-Id: Ib851e4d86ba9c8406ca37b88162ea483ccbc9d36
 2017-12-19 16:06:14 +05:30
Ben Sander b5911acce2 hipStreamWaitEvent returns success if event created but not recorded 2017-11-06 23:49:31 +00:00
Ben Sander 955cfbfdc7 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.
 2017-11-06 23:49:25 +00:00
Ben Sander 1c65bb1684 Set event state AFTER it is recorded. 2017-11-05 10:33:18 -06:00
Ben Sander dc7d993a02 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.
 2017-10-30 20:20:51 +00:00
Ben Sander fff74eee21 hipStreamQuery uses av::is_empty. Add HIP_FORCE_NULL_STREAM. 2017-08-31 03:00:14 +00:00
Ben Sander ed8c3ba7e7 Refactor hipStreamWaitEvent 
- Null streams use same flow as non-null.
- Add HIP_SYNC_STREAM_WAIT
- Resolve null stream.
 2017-08-31 03:00:14 +00:00
Ben Sander bc9ba7cd81 Lock streams when waiting on event completion or querying event safety. 2017-08-28 18:40:16 -05:00
Ben Sander d6aee9ad8f Add some new HIP_TRACE_API options. 2017-08-16 04:00:33 +00:00
Ben Sander 823281dcba Fix HIP_SYNC_NULL_STREAM=0 mode. 
- Fix null-stream sync
- hipStreamDestroy of null stream returns hipErrorInvalidResourceHandle
- Update documentation.
- Add tests for null stream sync, hipEventElapsedTime.
- Rename internal enum hipEventStatusRecorded to hipEventStatusComplete
- refactor hipStreamWaitEvent to streamline control-flow
 2017-06-05 08:50:22 -05:00