AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
12,880 Commits 3 Branches 0 Tags
08e7942cf8715d37978950a431c2001d5d899c09
Commit Graph

6576 Commits

Author SHA1 Message Date
Ioannis Assiouras b052e90ea8 SWDEV-451099 - Added include for __half type definitions for non-HIP code on windows 
Change-Id: Id80cef5a36db8707276de052cbaf73b6826d222f


[ROCm/clr commit: 2841aab017]
 2024-04-24 15:31:31 -04:00
German Andryeyev 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
Rahul Manocha 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
kjayapra-amd 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
German Andryeyev 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
Satyanvesh Dittakavi 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
Ioannis Assiouras 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
Anusha GodavarthySurya c7022ad6ce SWDEV-455869 - Revert "SWDEV-410751 - Consider null amd::memory is invalid." 
This reverts commit 60a3077ed4.

Change-Id: I26c4b3c74b2861afc17f979492d025b59d4388ab


[ROCm/clr commit: e829ef68e4]
 2024-04-19 00:54:26 -04:00
kjayapra-amd 71aa6ff3a0 SWDEV-413997 - VMM IPC implementation for Linux. 
Change-Id: Icfeb83ca51e96be35abb67a94d6e3e1a1ca5a934


[ROCm/clr commit: 56ebf5157a]
 2024-04-18 11:28:13 -04:00
Anusha GodavarthySurya 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
Jaydeep Patel 3dae883e73 SWDEV-453535 - Capture hipMemset3DAsync. 
Change-Id: I517c2557573db258b3e3e353f02f6a56652b0fde


[ROCm/clr commit: 12e0bdcd32]
 2024-04-18 00:05:45 -04:00
sdashmiz 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
Jatin Chaudhary 5a7b0c50ad SWDEV-379007 - fix bool check for fp8_fnuz 
for fnuz nums zero val is 0x00, -0 i.e. 0x80 would be a NaN

Change-Id: Ibdc4fb4b9fb307b5952434f08d45a8ddd6262db8


[ROCm/clr commit: d7b0d78fad]
 2024-04-17 05:31:21 -04:00
Sameer Sahasrabuddhe c44b565943 SWDEV-454959 - ignore the upper half of the mask in wave32 mode 
Change-Id: If027dd8cbe5cbe142fff353cb72c16f08e9aea8e


[ROCm/clr commit: 03562a2547]
 2024-04-17 10:12:57 +05:30
Jatin Chaudhary 80f02a1534 SWDEV-379007 - use avx instruction for bf16 cvt 
AMD CPUs have had avx512_bf16 support for quite some time now (from
consumer Ryzen 7000 series to enterprise grade CPUs). This
patch should allow users to use the hardware bf16 unit when running the
__host__ variants of the function. This can be enabled via `hipcc ...
-mavx512vl -mavx512bf16`.

Change-Id: I67c377afc95ddfe8d45a048dce078a247d4a1878


[ROCm/clr commit: 49349f168c]
 2024-04-16 18:35:08 -04:00
German Andryeyev 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
kjayapra-amd 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
Jatin Chaudhary 5e42260071 SWDEV-379007 initial implementation of fp8 header 
Change-Id: Id9a5a85641882961e4d860a815217c641e6f3387


[ROCm/clr commit: ca07f59fb1]
 2024-04-16 05:37:59 -04:00
Sourabh Betigeri 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
kjayapra-amd 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
kjayapra-amd 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
kjayapra-amd 765e6f5d2f SWDEV-413997 - Fixing multiple device cases. 
Change-Id: I10ad3fbfca887e92cd81f68392fa1acf753cbd2b


[ROCm/clr commit: d52d16c8e6]
 2024-04-13 06:14:03 -04:00
Jatin Chaudhary 565f915ebe SWDEV-379007 - add __hip_bfloat16_raw types 
This also brings bfloat16 implementation closer to CUDA's.

Change-Id: I23f381141faacd6537923ae9b88ada4d661db496


[ROCm/clr commit: 481912a1fd]
 2024-04-09 05:32:13 -04:00
Rakesh Roy 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
Anusha GodavarthySurya ff29b47bb8 SWDEV-452787 - correct hipDrvGraphAddMemcpyNode check 
Change-Id: Id58f982edd4f17d675f7a0f61a9b4dea0baebd9b


[ROCm/clr commit: ea4f09e8c0]
 2024-03-29 00:56:12 -04:00
Anusha GodavarthySurya 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
Jaydeep Patel 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
kjayapra-amd a17f9d2d75 SWDEV-448288 - Remove references to deprecated llvm references. 
Change-Id: I7b58177c41dc0c6c59813977cb90e65a6cb3be72


[ROCm/clr commit: 5b28e386f6]
 2024-03-26 10:23:18 -04:00
German Andryeyev 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
Jaydeep Patel 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
Ioannis Assiouras 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
Ioannis Assiouras 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
Ioannis Assiouras 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
Anusha GodavarthySurya 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
David Salinas 7de3d5a95a roc-obj uses incorrect path to find ROCm's llvm-objdump 
SWDEV-448278 - [LLNLA-260] (ELCAP-546) roc-obj uses bad path

Change-Id: I1a19f1fea29b301cfc183018fa050a8b8aeaaf02


[ROCm/clr commit: 383ed4cedf]
 2024-03-14 10:55:25 -04:00
Satyanvesh Dittakavi 15f01694f4 SWDEV-444021 - Implement hipGetFuncBySymbol 
Change-Id: I7ef13d02c5b5c6ce2386ccb92b5602d005b35988


[ROCm/clr commit: 684fd60c8f]
 2024-03-14 02:56:30 -04:00
Jaydeep Patel 2d8d4d5821 SWDEV-447384 - Handle double free case. 
Change-Id: I7a1d45c2f7510180911507d56ec863982b161f6c


[ROCm/clr commit: 43e2bb6126]
 2024-03-13 23:08:27 -04:00
jiabaxie 5af8ba8513 SWDEV-450204 - hipGetProcAddress check for null corrected 
Change-Id: Ic34b0d561d3d70f3411a60924a64c3b89954394f


[ROCm/clr commit: 14bcbcc25b]
 2024-03-13 16:44:08 -04:00
Jaydeep Patel 05fccb2d7e SWDEV-447525 - Fix merge conflict. 
Change-Id: I9dc852e634fb702a0d17ace3fad53e14178d4da0


[ROCm/clr commit: 79162c244b]
 2024-03-13 11:52:28 +00:00
Jaydeep Patel 844765d7e0 SWDEV-447525 - maxSize param for Mem pool props. 
Change-Id: Ib743611a66921aeaa449b6622b933cc8b9190d87


[ROCm/clr commit: b72d8da1bd]
 2024-03-13 00:58:48 -04:00
kjayapra-amd 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
taosang2 8cc8dda1cd SWDEV-450225 - Add missing targets in hipRtc 
Change-Id: Ifccdddfc8ac72585f6ba145578e5bbb7e3cd1643


[ROCm/clr commit: 4c82df817f]
 2024-03-12 10:34:08 -04:00
German Andryeyev f3db4e12e6 SWDEV-311271 - Correct the error codes in mempool 
Change-Id: Iacf8ad2cc454dfe53ccdb47c08d871b24ecf4107


[ROCm/clr commit: 1d8562eb7d]
 2024-03-12 10:18:44 -04:00
sdashmiz 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
Shilei Tian d90a0d9c57 SWDEV-442724 - Remove uses of -amdgpu-early-inline-all to enable function calls 
Currently we force inlining everything for HIP. Now we'd like to enable function
supports. The first step is to remove uses of `-amdgpu-early-inline-all` in
various places. This patch is to remove all of them from clr.

Change-Id: Ib0cad1f586714c9989778b00746aa4c47a4eec95


[ROCm/clr commit: a09204388a]
 2024-03-11 10:02:12 -04:00
Sameer Sahasrabuddhe dcd3673e66 SWDEV-295298: hide warp sync builtins in ROCm 6.2 (absent in 6.1) 
Change-Id: I6d59e4f3a133dce5ea0521fc9d09f93f9fd0f376


[ROCm/clr commit: 0421a35f71]
 2024-03-11 02:44:20 -04:00
Jaydeep Patel 79a57a6fc1 SWDEV-446219 - Validate option value. 
Change-Id: Ifccdddfc8ac71585f6ba045578e5bbb7e3cd1649


[ROCm/clr commit: 66f6a3e255]
 2024-03-07 12:53:34 -05:00
Anusha GodavarthySurya 41ec66ff67 SWDEV-448586 - Added implementation for new API hipStreamBeginCaptureToGraph 
Change-Id: I1ce802102cef2b66c92d3375f769983841de793f


[ROCm/clr commit: 4feb1f9337]
 2024-03-07 05:24:49 +00:00
German Andryeyev 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
German Andryeyev 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