eb1089593e
SWDEV-480536 - Disable cpu wait in device synchronize
...
1) currently cpu wait is set to true, which makes the host wait for last
command in queue to finish even if the kernel execution has already
finished causing delay in device sync call.
2) device sync only needs to await completion when hw event
is not ready.
Change-Id: I91e3e89d39a1193ae06abac822cea8ae651493a5
2024-09-13 15:31:32 -04:00
8be00b6602
SWDEV-477218 - Implement hipDeviceGetTexture1DLinearMaxWidth
...
Change-Id: I8103f710abeb869f5f84be61c57a30b24356def6
2024-09-05 15:09:38 -04:00
2aed4cf401
SWDEV-468133 - Fixed hipDeviceGetLimit for hipLimitMallocHeapSize
...
Change-Id: I91bede414ebe46831509cbd24ffb53cf129d6a40
2024-06-20 10:55:15 -04:00
1815fc808d
SWDEV-464927 - Update the Get by PCI BusId logic and Hop count
...
- Update the intra socket weight for partitions within single socket as
it is changed to 13 by the driver.
- Use the PCIe function to distinguish the partitions of the same device
such as TPX mode in gfx942.
Change-Id: I8e64023d44e37c2dbb105cbb343441a48021ba7b
2024-06-10 04:46:50 -04:00
a1e0970d6d
SWDEV-422580 - Adding back the pcie.function to PCI address string in hipGetDevicePCIBusId.
...
Change-Id: I932724cc872d7ae2643ce6ac2924901cb49cd7ad
2024-04-16 07:28:48 -04:00
19b4660cbb
SWDEV-443567 - SWDEV-436126 - Fix Prohibited and Unhandled Operations during capture
...
=> hipDeviceSynchronize is not allowed during capture.
=> hipEventSynchronize during capture should return hipErrorCapturedEvent error
=> hipEventQuery during capture should return hipErrorCapturedEvent error
hipStreamSynchronize, hipEventSynchronize, hipStreamWaitEvent, hipStreamQuery
For Side Stream(Stream that is not currently under capture):
=> If current thread is capturing in relaxed mode, calls are allowed
=> If any stream in current/concurrent thread is capturing in global mode, calls are not allowed
=> If any stream in current thread is capturing in ThreadLocal mode, calls are not allowed
For Stream that is currently under capture
=> calls are not allowed
=> Any call that is not allowed during capture invalidates the capture sequence
=> It is invalid to call synchronous APIs during capture. Synchronous APIs,
such as hipMemcpy(), enqueue work to the legacy stream and synchronize it before returning.
Change-Id: I201c6e63e1a5d93fd416a3b520264c0fdbe31237
2024-03-28 22:10:31 -04:00
be2bdabb76
SWDEV-430437,SWDEV-434702 - Split the streamset per device
...
Change-Id: If1bcca45825c9899462bb95ed6f637f5af806cc8
2024-03-18 19:08:52 -04:00
2c0fa829b4
[SWDEV-448077][SWDEV-448067] - Changes to Kernel Node Attribute related APIs
...
Change-Id: Ibbf773fd5f134a62b7ce04f6956b10c1086b1782
2024-02-28 18:14:41 -05:00
60549b101c
SWDEV-438503 - Always report hipDeviceAttributeUnifiedAddressing as true.
...
Change-Id: I3119bd8f99c079280bde1ba32b3d26b474899e7d
2024-02-05 05:08:11 +00:00
4a7291ded8
SWDEV-436405 - Move hipChooseDevice out of hip namespace
...
Change-Id: I47a3cc5e5409f418b282d1a2e250128c769f4778
2023-12-18 04:37:39 -05:00
3e72b8d1e1
SWDEV-436405 - Add hipGetDevicePropertiesR0000 and hipChooseDeviceR0000 to hip dispatch table
...
Change-Id: I5b373ac030502eb88477d20a1d216bc48369b51d
2023-12-15 06:26:52 -05:00
d5e596c975
SWDEV-434226 - populate correct output in mempool supported handle type query
...
Change-Id: Iabbf9c0b54d9978671e3492f13660917499a03fa
2023-12-13 04:40:41 -05:00
b825decd42
SWDEV-422544 - Use hipDeviceAttributeUnifiedAddressing as APU flag
...
Change-Id: If718a20f62f0ba8d83c01a0b2d16ff3f706f7bd4
2023-12-08 11:40:34 -05:00
afc28b091e
SWDEV-427855 - hipamd change for profiler and TF fix
...
This reverts commit 57cb840058
2023-12-05 20:33:48 -05:00
5e21f0c6bd
SWDEV-351966 - Dispatch table for hip runtime
...
Change-Id: Ie4a44fa8cf1ff9c152146070bbbf6b0636d4e325
2023-11-22 01:11:19 -05:00
57cb840058
SWDEV-427855 - Revert "SWDEV-427855 - hipamd change for profiler and TF fix"
...
This reverts commit 3b9963c499
2023-11-16 00:20:54 -05:00
3b9963c499
SWDEV-427855 - hipamd change for profiler and TF fix
...
Change-Id: If32eb0ee152f3f46741a8277689363181c8753e8
2023-11-15 23:36:52 -05:00
ee00ebc42f
SWDEV-425568 - Do cpu wait for device sync.
...
Change-Id: Ia05e09bd10ab623b36c74037e9988e132120dd9f
2023-10-21 01:16:06 -04:00
2989840511
SWDEV-306642 - [ABI Break] Add texture/surface/device capabilities device struct entries
...
- alias hipGetDeviceProperties to hipGetDevicePropertiesR0600
- alias hipDeviceProp_t to hipDeviceProp_tR0600
- remove gcnArch from new device property struct
- add new requested struct members
Change-Id: If3f5dbef3d608487d9f6f419285f4bf577ea9bf0
2023-10-12 11:16:18 -04:00
9008a53c98
SWDEV-414833 - adding hipDeviceAttributeIsLargeBar
...
to hipDeviceGetAttribute
Change-Id: Icde0ab9326b1759c66f9a3acbadfb9a01cf6a5be
2023-09-25 00:31:30 -04:00
fbea58ba11
SWDEV-423317 - Enable GPU wait for hip sync calls
...
hipStreamSynchronize and hipDeviceSynchronize won't longer wait
for CPU commands in DD mode
Change-Id: I079c8bbfc34ddc6d3e2d74c92a34665877e512a5
2023-09-22 13:04:27 -04:00
8705322f10
SWDEV-330665 - [ABI Break] check for attribute
...
- Add support for DevAttrHostRegisterSupported
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com >
Change-Id: Ica8d323eda97b65ef0088aa99c84dd36cfe4edf3
2023-09-22 04:51:24 -04:00
369fdc4d87
SWDEV-422580 - Adding pcie.function to the PCI address string in hipGetDevicePCIBusId.
...
Change-Id: Iaa73b6028ac7b1d05cc310405d6fe622d764320f
2023-09-21 12:22:05 -04:00
a4cccd3b0e
SWDEV-390597 - NoGpuTst test of Catch2 fails with docker
...
Change-Id: Ibf65e0ec57d47357e0afd119200622e223850b1e
2023-06-26 10:21:57 -04:00
68238c99d2
SWDEV-397358 - Revert "Return hipErrorNotSupported for unsupported APIs"
...
This reverts commit c6647487e0
2023-06-05 04:55:33 -04:00
0064fac887
SWDEV-403762 - Fill pciBusId even if len <=12.
...
Change-Id: Iaf1b3314f4ae5597d42d54eb4c977667ecbb9cfb
2023-06-02 10:47:21 +00:00
3dfe48b582
SWDEV-390597 - Return No Device error for hipSetDevice and hipSetDeviceFlags.
...
Change-Id: I457b1197a8f1b71a8bbbdf09f193f643c61700b6
2023-04-24 03:50:33 -04:00
1e88d2c52f
SWDEV-380703 - sync all streams individually
...
Avoid syncing blocking streams with the default stream,
since that introduces extra command dependencies and
doesn't allow to destroy memory after last submission
Change-Id: I618e9bd2091c4cf9157125612d8c4759030c5a80
2023-04-05 16:37:49 +00:00
4d8fd17985
SWDEV-362365 - Return invalid value if config is not valid.
...
Change-Id: I5f7300060f25536f8d3fd25afc2fe2522b621432
2023-04-05 16:37:28 +00:00
7809d2846b
SWDEV-387810 - Fixes to verify if the current stream matches the capture stream
...
- invalid to synchronize or query the execution status of a capturing stream but non-capturing streams can.
- If any local thread has an ongoing or concurrent capture sequence initiated with hipStreamCaptureModeGlobal, it is prohibited from unsafe calls
Change-Id: Ifa641e807216d3b7c3e8c2fb1be2f7a50bd641df
2023-04-05 10:53:33 +00:00
e3633dc8f4
SWDEV-381402 - Derive hip::Stream from amd::HostQueue
...
Change-Id: I6c1aca5eb350c32d974ae4ffcc725705355956d8
2023-02-21 18:12:03 -05:00
8b87ccb8cc
SWDEV-381402 - convert host_device to host_context of type amd::Context*
...
Change-Id: Ic1cb9a3fa64e16699fad7e9ec6679f1d34b14bef
2023-02-16 17:49:12 -05:00
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
33eef6d95e
SWDEV-364576 - use hipLimitMallocHeapSize to set initial heap buffer size
...
Change-Id: I2f1d3b229bc28571ce6c55f93f8ef73dda516b50
2023-01-12 23:34:29 -05:00
a643c199de
SWDEV-356549 - del Null strm in destroyAllStreams
...
Change-Id: Ie04172ee39e6333247d07791dffda753a8b9ef41
2022-12-29 15:45:54 -05:00
2cde04bf9b
SWDEV-367745 - Report hipDeviceAttributeUnifiedAddressing
...
Change-Id: I4d1d598f64f613430fecdc0d6b4cfa9845e04687
2022-11-15 15:53:02 -05:00
4e2f7192e3
SWDEV-362367 - pciBusId should be large enough to store 13 characters including the NULL-terminator.
...
Change-Id: Ie58be0495065713bae7e13923ac04a4643e246be
2022-11-03 00:04:27 -04:00
84fa61a39b
SWDEV-363850 - fix a bug in mutual exclusive flags
...
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com >
Change-Id: If7687b5bf7ec7ff1978991cbf7dafa0612912274
2022-10-27 11:23:35 -04:00
8d2885f331
SWDEV-345024 - Restore break
...
Commit 60656d9fc9
2022-10-21 18:04:20 -04:00
9f9fd859db
SWDEV-286739 - Support hipDeviceAttributeWallClockRate
...
Part 3: Add missing declaration of wall_clock64() to fix
compiling issue in device code.
Add querying hipDeviceAttributeWallClockRate.
Change-Id: Ie54771c2f58eeaacdc0248bc116ef193f99eb9b9
2022-07-28 13:02:42 -04:00
030e7702f1
SWDEV-343160 - correct mutual exclusive flags
...
- flags passed should be only one type at a time
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com >
Change-Id: I3e56f036e51d8cc84fe5c18c06cfa11cf785233f
2022-07-12 08:35:39 -04:00
4b9ea686f6
SWDEV-342831 - Fix hipGetDeviceCount return
...
Change-Id: I3b0338a51027258319c1926ac02de8d0af01d498
2022-06-27 00:39:08 -04:00
c6647487e0
SWDEV-336538 - Return hipErrorNotSupported for unsupported APIs
...
Change-Id: Ie54771c2f58eebacdc0248bc116ef093f99eb9b8
2022-06-23 07:31:31 -04:00
7f92a98a3c
SWDEV-331066- Added hipDeviceSetLimit
...
Change-Id: I4de099387ad34ca7c195588274b546649038e2aa
2022-06-21 06:06:05 +00:00
60656d9fc9
SWDEV-322620 - Virtual Memory Management
...
Report virtual memory management support.
Change-Id: I448a66c86ab1b2d28f6052e8896ea505e56eb2d2
2022-05-17 16:24:53 -04:00
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
80e1e2e6db
SWDEV-325708 - Query for FineGrained support
...
Change-Id: I3a8d2bca50d0874c0ff60efa457006876b1fe963
2022-03-28 07:17:55 -04:00
2ef41ff5be
SWDEV-323899 - More capping of caps
...
Change-Id: If8ba22d01326b85455eaaee55e1e2a4b9832ebb2
2022-03-22 11:02:49 -04:00
9a3b4a93d2
SWDEV-301947 - Add new query for physical CU count
...
Add hipDeviceAttributePhysicalMultiprocessorCount to get all
available CUs for a device.
Change-Id: Ie6a2c6e958df9627f39c91d0651b89ef5bffd8fe
2022-03-08 17:11:36 -05:00
086aee0fcb
SWDEV-301667 - Fix build warnings
...
Change-Id: Ice23b3d1a19a7958ca5c3caff34db2934b361a98
2022-03-02 20:49:18 -05:00
Rahul Manocha
victzhan
Ioannis Assiouras
Satyanvesh Dittakavi
kjayapra-amd
Anusha GodavarthySurya
Rahul Manocha
Todd tiantuo Li
Jatin Chaudhary
Rahul Garg
jiabaxie
Jaydeep Patel
pghafari
German Andryeyev
sdashmiz
Julia Jiang
Maneesh Gupta
Sourabh Betigeri
Tao Sang
Sarbojit Sarkar
Christophe Paquot
Saleel Kudchadker