ab70925687
SWDEV-456279 - Adding new hip flag to access contiguous memory and pass the flag to HSA API.
...
Change-Id: I1bafeaa3096395c729723af958d609bc41e7845c
[ROCm/clr commit: 1d48f2a1ab
2024-04-30 05:25:38 -04:00
154a113a88
SWDEV-413997 - Changes to use GlobalContext in views.
...
Change-Id: I1f8411eae9ed49632667e244a25f223fed92c720
[ROCm/clr commit: 0e1a0572e6
2024-04-29 16:41:39 -04:00
d49fa8d06b
SWDEV-413997 - Handling cases where multiple phys_mem is mapped into a single virtual address.
...
Change-Id: Ie678e607a64f2e5c35a10b9083185f041c5527ac
[ROCm/clr commit: 49b4aef8c9
2024-04-28 08:28:12 -04:00
b1c0f73229
SWDEV-353281 - Corret VA unmap
...
Make sure graph mempool unmaps VA on release
Change-Id: Id3f1bd8d0115b533ae60aa5ba3676b8bf7e5b961
[ROCm/clr commit: 5c1804aa14
2024-04-26 09:37:01 -04:00
15b8dc404c
SWDEV-420016 - Add more driver side graph APIs
...
Signed-off-by: shadi <shadi.dashmiz@amd.com >
Change-Id: Iff3ee7dcbcd24836f227fdc9bd5ff4b554ac914f
[ROCm/clr commit: f2b01782ac
2024-04-25 12:50:43 -04:00
d1507ad475
SWDEV-353281 - Align VA size
...
Lower layer ignores alignment
Change-Id: If16df951ecefddc804a6effe013058afc595d30f
[ROCm/clr commit: 5c23440199
2024-04-24 15:22:20 -04:00
85a372e4eb
[SWDEV-454661][SWDEV-454653] - GraphExecMemcpyNodeSetParam to return error on memcpy direction change
...
Change-Id: I2c8f5ea394caeaaa6895003e63cd62a052c491f8
[ROCm/clr commit: 880963346d
2024-04-23 12:56:30 -04:00
2335c92a1a
SWDEV-455041 - Continue processing fat binary even if other code object bundle processing fail.
...
Change-Id: Iea553ab0265c08341f915644075ce2b6ed9b3200
[ROCm/clr commit: 863c56262e
2024-04-20 14:25:49 -04:00
00fb29aab6
SWDEV-353281 - Reuse timestamp on memory reuse
...
Mempool may reuse memory without a wait. Hence, the timestamp has
to be preserved and can't be destroyed.
Change-Id: I6f095f44afa69887a4b7aeb3b329804aedd96f3e
[ROCm/clr commit: ffb516db3e
2024-04-19 18:00:29 -04:00
2e58154d80
SWDEV-446610 - Attribute HIP_POINTER_ATTRIBUTE_SYNC_MEMOPS should return the correct value
...
Change-Id: Ieced2ee61bba28f2d1df96893a661287b0a5c7b7
[ROCm/clr commit: 8f7acbdadb
2024-04-19 14:40:09 -04:00
2f430138c5
SWDEV-451594 - Implement Readback and Avoid HDP Flush workaround for device kernel args
...
Change-Id: I6d41a089a17f55306e7ff402588a1e831b20a7a7
[ROCm/clr commit: bf74ef4025
2024-04-19 09:29:20 -04:00
c7022ad6ce
SWDEV-455869 - Revert "SWDEV-410751 - Consider null amd::memory is invalid."
...
This reverts commit 60a3077ed4e829ef68e4
2024-04-19 00:54:26 -04:00
71aa6ff3a0
SWDEV-413997 - VMM IPC implementation for Linux.
...
Change-Id: Icfeb83ca51e96be35abb67a94d6e3e1a1ca5a934
[ROCm/clr commit: 56ebf5157a
2024-04-18 11:28:13 -04:00
b77908a819
SWDEV-450053 - Handle MemcpyNodeSetParamsTo/FromSymbol negative parameters
...
For all windows allocation on SVM memory tagged with flag ROCCLR_MEM_INTERPROCESS.
hipHostMalloc validation is based on flag. So remove ROCCLR_MEM_INTERPROCESS before check.
Change-Id: I823bbf228d9a4a9acb4abffc01ac6b3f544c6e12
[ROCm/clr commit: 8179fa98a2
2024-04-18 05:39:35 -04:00
3dae883e73
SWDEV-453535 - Capture hipMemset3DAsync.
...
Change-Id: I517c2557573db258b3e3e353f02f6a56652b0fde
[ROCm/clr commit: 12e0bdcd32
2024-04-18 00:05:45 -04:00
d2b2b2c5fa
SWDEV-441603 - Correct dst device
...
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com >
Change-Id: Ie60aa598dd73df66cdf02c1d96daf2dfccba7a59
[ROCm/clr commit: d511e57257
2024-04-17 09:21:06 -04:00
7f195e2996
SWDEV-444670 - Enable teardown class
...
Force implicit runtime teardown with a global destructor.
Change-Id: Iabe63dedf5b94fefc98668585c45a61607120669
[ROCm/clr commit: c95a75a2bf
2024-04-16 12:00:06 -04:00
854cbe1d24
SWDEV-422580 - Adding back the pcie.function to PCI address string in hipGetDevicePCIBusId.
...
Change-Id: I932724cc872d7ae2643ce6ac2924901cb49cd7ad
[ROCm/clr commit: a1e0970d6d
2024-04-16 07:28:48 -04:00
26b7b7b951
SWDEV-453577 - Fixes to account for right CU count based on WGP or CU mode
...
Change-Id: Ib9739f9917bc6ff69cc76f444d909311922ebc1e
[ROCm/clr commit: fcfe2ec88b
2024-04-15 11:53:43 -04:00
867769b0ec
SWDEV-413997 - Fixing alignment validation check for power of 2 instead of granularity factor.
...
Change-Id: I1e0db6e0628c09d26850e5a0339e2a4660442db8
[ROCm/clr commit: 00ddc3e284
2024-04-15 09:45:29 -04:00
79b3fc1fb8
SWDEV-413997 - Read Access can be valid now that ROCr takes care of access.
...
Change-Id: Iecda74ca0207c95d3fbed8b4e15c8c4c5895d939
[ROCm/clr commit: 815e450cfd
2024-04-15 06:00:14 -04:00
765e6f5d2f
SWDEV-413997 - Fixing multiple device cases.
...
Change-Id: I10ad3fbfca887e92cd81f68392fa1acf753cbd2b
[ROCm/clr commit: d52d16c8e6
2024-04-13 06:14:03 -04:00
9630492a1d
SWDEV-450361 - Add nullptr validation for waitStream
...
- Application is passing null for parameter stream in API hipStreamWaitEvent
- When event stream isn't capturing and event is not recorded, causes segfault because we are accessing deviceId() from waitStream
Change-Id: I8b87ffd6f234677f68b66dcb7ef44b2ff04a7c91
[ROCm/clr commit: 880f1f0049
2024-04-04 02:07:18 -04:00
ff29b47bb8
SWDEV-452787 - correct hipDrvGraphAddMemcpyNode check
...
Change-Id: Id58f982edd4f17d675f7a0f61a9b4dea0baebd9b
[ROCm/clr commit: ea4f09e8c0
2024-03-29 00:56:12 -04:00
ae296c8fad
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
[ROCm/clr commit: 19b4660cbb
2024-03-28 22:10:31 -04:00
c4239ed8e8
SWDEV-446992 - Request can be for bytes OR dptr OR both.
...
Change-Id: Ib479c744b90125b74d99cbf18b7f4b8cf765bf1c
[ROCm/clr commit: 09328f45b3
2024-03-26 11:10:24 -04:00
e46ab0bff5
SWDEV-353281 - Change pool type for graphs
...
Under ROCr physical allocations don't have initial VA and require extra
flag in ROCclr. Add an option to have a mempool of physical allocations.
Change-Id: I4d062fe0dd8113d4eaf6e8b51749ed56d8701d1e
[ROCm/clr commit: f296159f62
2024-03-25 10:21:05 -04:00
1bbbff9dd9
SWDEV-452299 - Pass dst pitch while capturing hipMemcpyParam2DAsync & elementSize should be 1 as width is in bytes while capturing hipMemset2DAsync.
...
Change-Id: I8f9122a30cba0a07c097dfd7609432090caab142
[ROCm/clr commit: 0be92b8f09
2024-03-21 12:49:34 -04:00
a3b6fd539f
SWDEV-449146 - Call hipDeviceSynchronize before removeFatBinary
...
Added call to hipDeviceSynchronize in __hipUnregisterFatBinary
to ensure that all HSA async signal handlers complete before removeFatBinary
Change-Id: I756fecca1c2a5eae092613d8079de266399e5685
[ROCm/clr commit: ad32e604c7
2024-03-20 23:40:46 +00:00
8b875d0248
SWDEV-430437,SWDEV-434702 - Split the streamset per device
...
Change-Id: If1bcca45825c9899462bb95ed6f637f5af806cc8
[ROCm/clr commit: be2bdabb76
2024-03-18 19:08:52 -04:00
b46d3c0f8d
SWDEV-451166 - Disable kernel args for non-XGMI if HDP flush register is invalid
...
Change-Id: I227e046e2b9cb25476a50240f5d070adbd558f21
[ROCm/clr commit: 96f5c44851
2024-03-15 05:27:52 -04:00
ec391d7249
SWDEV-436126 - hipStreamDestroy to remove stream from capture list
...
Change-Id: Ie735f27b9c5df4faf39bd4be10fbe4401fd88cdb
[ROCm/clr commit: 476dc4c87c
2024-03-14 11:32:10 -04:00
15f01694f4
SWDEV-444021 - Implement hipGetFuncBySymbol
...
Change-Id: I7ef13d02c5b5c6ce2386ccb92b5602d005b35988
[ROCm/clr commit: 684fd60c8f
2024-03-14 02:56:30 -04:00
2d8d4d5821
SWDEV-447384 - Handle double free case.
...
Change-Id: I7a1d45c2f7510180911507d56ec863982b161f6c
[ROCm/clr commit: 43e2bb6126
2024-03-13 23:08:27 -04:00
5af8ba8513
SWDEV-450204 - hipGetProcAddress check for null corrected
...
Change-Id: Ic34b0d561d3d70f3411a60924a64c3b89954394f
[ROCm/clr commit: 14bcbcc25b
2024-03-13 16:44:08 -04:00
05fccb2d7e
SWDEV-447525 - Fix merge conflict.
...
Change-Id: I9dc852e634fb702a0d17ace3fad53e14178d4da0
[ROCm/clr commit: 79162c244b
2024-03-13 11:52:28 +00:00
844765d7e0
SWDEV-447525 - maxSize param for Mem pool props.
...
Change-Id: Ib743611a66921aeaa449b6622b933cc8b9190d87
[ROCm/clr commit: b72d8da1bd
2024-03-13 00:58:48 -04:00
8947420e41
SWDEV-423835 - Fixing kernel launch issues on Virtual Memory Management path.
...
Change-Id: I9f5e8a3d83af3809b2c50b21a10697e26113dd23
[ROCm/clr commit: f5ca620baa
2024-03-12 17:22:07 -04:00
8cc8dda1cd
SWDEV-450225 - Add missing targets in hipRtc
...
Change-Id: Ifccdddfc8ac72585f6ba145578e5bbb7e3cd1643
[ROCm/clr commit: 4c82df817f
2024-03-12 10:34:08 -04:00
f3db4e12e6
SWDEV-311271 - Correct the error codes in mempool
...
Change-Id: Iacf8ad2cc454dfe53ccdb47c08d871b24ecf4107
[ROCm/clr commit: 1d8562eb7d
2024-03-12 10:18:44 -04:00
0c65a7baea
SWDEV-447458 - remove check for image support
...
- remove the check from hipmallocpitch
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com >
Change-Id: Ife3a95381be703b1c1b7492abfd4432c4a8141c8
[ROCm/clr commit: 315d0fc46e
2024-03-11 11:39:14 -04:00
79a57a6fc1
SWDEV-446219 - Validate option value.
...
Change-Id: Ifccdddfc8ac71585f6ba045578e5bbb7e3cd1649
[ROCm/clr commit: 66f6a3e255
2024-03-07 12:53:34 -05:00
41ec66ff67
SWDEV-448586 - Added implementation for new API hipStreamBeginCaptureToGraph
...
Change-Id: I1ce802102cef2b66c92d3375f769983841de793f
[ROCm/clr commit: 4feb1f9337
2024-03-07 05:24:49 +00:00
4bb028a49d
SWDEV-311271 - Add dependency tracking for streams
...
Mempool has capability to track dependency between streams for
faster memory reuse. Enable that capability.
Change-Id: I28266a7e38d0fc4c5d027b9542d3719653840821
[ROCm/clr commit: 17d0c166d2
2024-03-05 12:53:09 -05:00
396b3f8de7
SWDEV-311271 - Return different errors
...
Match errors with the tests
Change-Id: I32db83843e45e0f09359149ea9fd7a532c881e16
[ROCm/clr commit: 11a6be1ede
2024-03-04 17:02:30 -05:00
286599824e
SWDEV-441629 - add some missing hiprtc link options
...
Change-Id: I10019823e212c6d4de6df30c0fe1c20d9e992f29
[ROCm/clr commit: 7f9651d4bb
2024-03-01 07:49:57 -05:00
5ca2131ce0
SWDEV-413377 - Segfault for hipLaunchKernel with multi GPUs
...
- Using runtime unbundler, no any gfx device can load fat binary,
if there is any device without available code object.
- Extract available code object to corresponding gfx devices. So
users can work ROCm with those ready devices without segmentation
fault.
Change-Id: I9f14c65ecebf2d3c4b127a007cb434a3ae98c450
[ROCm/clr commit: 6723277ad4
2024-03-01 02:24:22 -05:00
0a269e98a9
[SWDEV-448077][SWDEV-448067] - Changes to Kernel Node Attribute related APIs
...
Change-Id: Ibbf773fd5f134a62b7ce04f6956b10c1086b1782
[ROCm/clr commit: 2c0fa829b4
2024-02-28 18:14:41 -05:00
f1e5162757
SWDEV-447545 - Fix Enable/Disable node with hipGraph
...
Node can be enabled/disabled only for kernel, memcpy and memset nodes.
If the node is disabled it becomes empty node.
To maintain ordering just enqueue marker with respective node dependencies.
Change-Id: I710f3e88ab4e76c81f6f86a40a7dc61fd4c7e440
[ROCm/clr commit: e0e63eb04d
2024-02-28 17:34:03 -05:00
67543a60f1
SWDEV-444988 - Fix hiddenheap variable initialization
...
Change-Id: Icdb32ef4718b8ca0beedd569a4aaf40a9f4fb49d
[ROCm/clr commit: ea66946399
2024-02-28 17:22:32 -05:00
Jaydeep Patel
kjayapra-amd
German Andryeyev
shadi
Rahul Manocha
Satyanvesh Dittakavi
Ioannis Assiouras
Anusha GodavarthySurya
Sourabh Betigeri
Rakesh Roy
jiabaxie
taosang2
Jatin Chaudhary
ChingShihLi
Rahul Manocha