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
c9d9fd992a
SWDEV-300471 - updated hipFree to wait for all streams to finish
...
Change-Id: I4983ef48a9e720ed03128d83a8d23ad11024fd8f
2021-09-02 00:45:24 -04:00
6f71170772
SWDEV-295275 - Check HW event
...
Change-Id: I23dfe5626f38b13fbdb6478ab12a0122b03e4a98
2021-08-30 15:55:58 -04:00
8835b897d5
SWDEV-286322 - Remove execution permission
...
Change-Id: I96e603fc8d407c3a76fa1053bad81e45744b59ad
2021-08-05 14:04:06 -04:00
a71f54d9e9
SWDEV-240806 - Added API hipGraphAddMemcpyNode1D, hipGraphAddEmptyNode, hipGraphExecKernelNodeSetParams
...
Change-Id: I0d7ec8c0ea1abc3fc0f1e10fa7865f355d9cf2ad
2021-07-28 00:09:16 -04:00
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
c3ca1faee7
SWDEV-292547 - hipStreamPerThread support
...
Change-Id: Id621ce073b0fee9eac03c59ffb78b197fda4ddb5
2021-07-26 20:51:51 -04:00
d9d9e81acb
SWDEV-293742 - Update copyrights end year for hipamd
...
Change-Id: I08f620f84563a9214b59f1b943ed091b67229eab
2021-07-09 12:08:39 -04:00
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
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
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
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
e943144b31
add IPC event support ( #1996 )
2020-04-17 10:31:22 +05:30
1444f850ac
fix hipStreamAddCallback, block future work on stream ( #1934 )
2020-03-19 16:16:04 +05:30
4aaa2336a8
[HIP] Clean-up deprecated HIP error codes
...
hipErrorMemoryAllocation -> hipErrorOutOfMemory
hipErrorInitializationError -> hipErrorNotInitialized
hipErrorMapBufferObjectFailed -> hipErrorMapFailed
hipErrorInvalidResourceHandle -> hipErrorInvalidHandle
2019-12-23 17:01:35 +03:00
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
8a3c36a424
Revert [HIP] Fixed hipStreamAddCallback ( #1674 )
...
This reverts commit 97fca3439d
2019-11-20 11:55:46 +05:30
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
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
734c4b92c3
remove stream locks where it is safe to do so
2019-07-22 17:38:51 +00:00
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
4989452413
Added missing NULL checks and corrected API return values as per validation
2019-06-27 00:19:05 +05:30
263e82a67a
Add extension for kernel concurrency on same stream
2019-03-06 12:55:39 +05:30
0774b275c8
rebase to master, tracer related changes
2018-11-13 15:50:34 +00:00
e362688adf
renaming HIP_INIT_CB_API to HIP_INIT_API
2018-11-13 15:33:26 +00:00
084a68be63
adding activity prof layer
2018-11-13 15:33:26 +00:00
b01ac26948
Make HIP functional again with HCC from ROCm 1.9.x
...
Change-Id: I214acdfd0b79dcf783993e44fe31baee64fd4dc3
2018-10-24 10:41:56 +05:30
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
e21e6ed3a0
callback handler: don't need to wait for the thread to become ready
2018-06-02 17:55:37 -04:00
9e47fccc89
Apply .clangformat to all repo source files
...
Change-Id: I7e79c6058f0303f9a98911e3b7dd2e8596079344
2018-03-12 11:29:03 +05:30
cd9ba0d1e1
Implement hipStreamAddCallback
...
Change-Id: Ib851e4d86ba9c8406ca37b88162ea483ccbc9d36
2017-12-19 16:06:14 +05:30
b5911acce2
hipStreamWaitEvent returns success if event created but not recorded
2017-11-06 23:49:31 +00:00
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
1c65bb1684
Set event state AFTER it is recorded.
2017-11-05 10:33:18 -06:00
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
fff74eee21
hipStreamQuery uses av::is_empty. Add HIP_FORCE_NULL_STREAM.
2017-08-31 03:00:14 +00:00
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
bc9ba7cd81
Lock streams when waiting on event completion or querying event safety.
2017-08-28 18:40:16 -05:00
d6aee9ad8f
Add some new HIP_TRACE_API options.
2017-08-16 04:00:33 +00:00
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
b2b620c12b
Add isDefaultStream() accessor.
...
Fix code that checked for stream==nullptr after stream had been
resolved to a "true stream".
2017-05-26 13:46:48 -05:00
d43d57d39c
Remove HIP_MAX_QUEUES (replaced with HCC_MAX_QUEUES)
2017-05-23 23:48:01 -05:00
8bc6ee5932
Add initial HIP_SYNC_NULL_STREAM=0 mode.
...
This eliminates host-synchronization for null stream. Instead, the
null-stream uses GPU-side events to wait for other streams.
Default is OFF pending additional testing.
Add enhanced null-stream test.
Also refine HIP_TRACE_API.
2017-05-16 19:04:25 -05:00
1cead6a4cd
added new api hipHccModuleLaunchKernel
...
1. hipHccModuleLaunchKernel is same as hipModuleLaunchKernel with OpenCL workitem model
2. Added copy right
3. Fixed header naming
Change-Id: I6a7c35a3566e2f8d3f5056613e34193775d4b236
2017-03-31 12:11:34 -05:00
e9ff23e5f9
changed copyright year from 2016 to 2017 in src directory
...
Change-Id: Idb97db509b2b4b1656b2df7a14a62ade38c9d574
2017-01-11 18:05:41 -06:00
b29fbf736d
Add HIP_MAX_QUEUES feature.
...
Includes some tricky manipulation of the locks for contexts and streams.
issue is that stealing a stream requires we lock the context to
walk the streams to find a victim. To avoid deadlock, we can't
have a stream locked when we lock the context. This implementation
releases the stream lock, then acquires the context and selects the
victim.
A more stable implemenation might be to copy the stream list
from a context so that a lock is not required to walk all streams.
Smart shared_ptr could be used to prevent the streams from being
deallocated during the walk.
2017-01-09 21:02:56 -06:00
c9f5fe34e6
First pass at virtualized queue support.
...
Also updated stream debug messages to consistently use trace_helper.
2017-01-09 21:02:53 -06:00
49d1477b9d
tolerate spaces in hip args
2017-01-09 20:57:13 -06:00
7a0375854a
Add workaround for hipStreamAddCallback function: call stream synchronize on host and then add execute the call back function
...
Change-Id: If361f8e053949904b19b9e09245d267f05e29f7b
2016-10-22 23:59:39 -05:00
403cdf93c3
Move some internal headers from "include/hip/" to src.
...
Change-Id: I7041bd5c803d9318979f4a7c1d658445c614691e
2016-10-18 22:27:16 -05:00
Laurent Morichetti
anusha GodavarthySurya
Saleel Kudchadker
Julia Jiang
Vladislav Sytchenko
Sarbojit Sarkar
agunashe
Christophe Paquot
German Andryeyev
Rahul Garg
Tao Sang
Jeff Daily
Evgeny Mankov
satyanveshd
Sarbojit2019
Aryan Salmanpour
Anusha Godavarthy Surya
root
Evgeny
Maneesh Gupta
Siu Chi Chan
Ben Sander
Aditya Atluri
pensun