AI/rocm-systems
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity
12 925 Commits 3 Branches 0 Tags
6c8ca0b3aa5906eb60ae4b8f3c8eeeff81760d36
Commit Graph

12925 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Ioannis Assiouras 6c8ca0b3aa SWDEV-455444 - Add the hiprtc sources to hiprtc library for static builds 
Change-Id: Ic17f22831376be37fe998aa1ec9a754738c9a147
 2024-05-28 06:31:10 +00:00
Tao Sang a1350fe8c1 Revert "SWDEV-433371 - use comgr to unbundle code objects" 
This reverts commit e53df57ffe.

Reason for revert: <INSERT REASONING HERE>
New comgr unbundling action leads to perf drop for uncompressed code object.   Will create a new patch to use old path for uncompressed , new unbundling api for compressed . 

Change-Id: I41ef53b71fc9f7aaa8cf231d4d70945f1117db52
 2024-05-28 06:31:10 +00:00
German Andryeyev a4dbc97bd7 SWDEV-451594 - Correct preMI100 detection 
Change-Id: I4f1570a64cebf1ff73b4d189c17b7d7db095009c
 2024-05-28 06:31:10 +00:00
Ioannis Assiouras 7b46701142 SWDEV-449620 - Added hipExternalMemoryGetMappedMipmappedArray in the dispatch table 
Change-Id: I79952f131dea1949296685ee92cae05a4f9aec30
 2024-05-28 06:31:10 +00:00
kjayapra-amd 931431fc38 SWDEV-417091 - Disable GWS Init for PAL/Windows side. 
Change-Id: Ib6295f063daa835c1f33f21f50c083241a9026ff
 2024-05-28 06:31:10 +00:00
Ajay d754ab4e30 SWDEV-460151 - enable gfx12 code in runtime 
Change-Id: I2d6fbf350c7cc2e1e4a698f0bad4ce8d512c4368
 2024-05-28 06:30:26 +00:00
Saleel Kudchadker badf2b0880 SWDEV-301667 - Refactor graph code 
- Remove Last graph node optimization and instead submit a barrier NOP
packet always. This simplifies the code.

Change-Id: Ied443173ba47a08b6df148ac7e3ead712acda11c
 2024-05-28 06:28:17 +00:00
Satyanvesh Dittakavi 3d540ec113 SWDEV-457755 - Add TS only for kernel packets in the Accumulate command 
Change-Id: I1b2f01c5763761808f49802fa117abc6306a22aa
 2024-05-28 06:28:17 +00:00
shadi e705e5e0d9 SWDEV-421027 - Add more Graph APIs 
Signed-off-by: shadi <shadi.dashmiz@amd.com>
Change-Id: I0a1fc284e48317a49ca88d4ed4e3a10e752efd58
 2024-05-28 06:28:17 +00:00
kjayapra-amd 31935b1d39 SWDEV-459325 - Remove hiprtc sources from libhipamd64 compilation. 
Change-Id: Ic70206c5936fb36a23c122e67110b91ae7e95e09
 2024-05-28 06:28:17 +00:00
kjayapra-amd 2cfc42368e SWDEV-445072 - Fixing error on static library for hip package. 
Change-Id: I96d2b9000e290739870e201b599bdef8859b971a
 2024-05-28 06:28:17 +00:00
kjayapra-amd b9c65fb7ff SWDEV-445072 - Enable RTC outside of BUILD_SHARED_LIBS variable. 
Change-Id: Iab9f1cb2bdf24163979e2b646bdbed3f1508b221
 2024-05-28 06:28:17 +00:00
Anusha GodavarthySurya bf4d10ff61 SWDEV-460770 - Handle Graph Exec release 
Handle GraphExec instance is destroyed before async launch completes
GraphExec instance is destroyed after async launch completes
GraphExec instance is destroyed without a launch

Change-Id: I45a7c82295fea916c7559bd8f796df710513aea1
 2024-05-28 06:28:17 +00:00
Saleel Kudchadker 51e4368723 SWDEV-459778 - Remove CPU wait for profiler 
- No cpu wait is needed when profiler is attached, Doing this changes
the application profile when roctracer is attached.

Change-Id: I2b9cfc48d697cf5ed54bb6a240d8c12bdb079171
 2024-05-28 06:28:17 +00:00
Anusha GodavarthySurya 45dccd6eab SWDEV-453739 - Added definition for undeclared methods 
Change-Id: I3f10e0a3fb4bbaf9d873a6a988847f05ac43a312
 2024-05-28 06:28:17 +00:00
Anusha GodavarthySurya de95625f09 SWDEV-454247 - Fix graph multi threading issue 
Change-Id: I565889da6f7091030b7f6a2d6234b82c389358e3
 2024-05-28 06:28:17 +00:00
Saleel Kudchadker 2d7912dc01 SWDEV-460080 - Do not wait for host side command complete 
- awaitCompletion would wait for host side command compelete(aka
cpuWait). The correct way is to check the completion signal and if not
dispatch a marker that has a signal.

Change-Id: I0f4f23c7ea68c329bf1d5f05e9735f631e5e3808
 2024-05-28 06:28:17 +00:00
kjayapra-amd c7461436d6 SWDEV-459254 - Change return type to support values > 128. 
Change-Id: Ib4c9a3718c4cb26b24503fe4d9af3e63e151e843
 2024-05-28 06:28:17 +00:00
kjayapra-amd dd1dd86fd7 SWDEV-459254 - Overwrite cacheline size to 256 for gfx12, as it is used for kernarg alignment. 
Change-Id: Ia6acf312ee84f6dde1c830fc21f10d3a8a9de5ee
 2024-05-28 06:28:17 +00:00
Ioannis Assiouras 2b746de6de SWDEV-451594 - Fallback to host kernel args on older devices 
On gfx8, gfx9 devices before MI100 and gfx10.0 or gfx10.1
none of the memory ordering workarounds for device kernel arguments
can be applied. Use host kernel arguments on these devices.

Change-Id: I9be6fbfe4b3986eb7d9f83998334df5f03fd4124
 2024-05-28 06:28:17 +00:00
Ioannis Assiouras 5bb30d7718 SWDEV-460581 - Fixed memory leak in hipIpcCloseMemHandle 
hsa_amd_ipc_memory_detach is called with an invalid mapped pointer.
Changed to pass the svm pointer of the owner memory instead.

Change-Id: I8203c6e2d718efb8ca3b028309bc78caff8d4c7d
 2024-05-28 06:28:17 +00:00
Rakesh Roy 87619af175 SWDEV-459556 - Revert "SWDEV-442724 - Remove uses of -amdgpu-early-inline-all to enable function calls" 
This reverts commit a09204388a.

Change-Id: I885b9e5910d90fd871ab48f7ee95796b6cd01297
 2024-05-28 06:28:17 +00:00
German Andryeyev 5b0bfdcbad SWDEV-460242 - Add system memory suballocator 
Switch commands creation to the new suballocator to avoid
frequent expensive OS calls

Change-Id: I3597c811820e577c15708bad8b8a41aa53acc400
 2024-05-28 06:28:17 +00:00
kjayapra-amd f5d0ee650b SWDEV-460151 - Enabling gfx12 in HIP runtime. 
Change-Id: I374ea7c3119b0c61f9846a862c4a448ddb179748
 2024-05-28 06:28:07 +00:00
Alex Xie 2eb30376ba SWDEV-451945 - Remove ShouldLoadPlatform function 
Change-Id: Iabb4071bb77201576bc2c0488a04f4fa188815df
 2024-05-06 10:42:59 -04:00
Saleel Kudchadker 4a9d24a211 SWDEV-301667 - Pass reference to kernel name 
Change-Id: I21abe109ddfabfe7640bf78a96c81a1317d31952
 2024-05-05 16:38:20 -04:00
kjayapra-amd 68ddd8f3a0 SWDEV-460091 - Handle cases where inline variables are included in multiple translation unit. 
Change-Id: I92179ad198abbdaf5aec9c3c4ba76eeb6b0cc761
 2024-05-03 15:52:28 -04:00
Maneesh Gupta 1bd8b4eaf5 SWDEV-433371 - Build needs comgr >= 2.8 
Unbundle compressed code objects needs comgr 2.8 or higher

Change-Id: I23942d2038e19b02c3ea5d3c9c1fe5367db87136
 2024-05-03 09:34:49 +00:00
Ioannis Assiouras 6cb7b6ec6b SWDEV-451594 - Change device kernel args to use HDP flush by default 
The Readback and Avoid HDP Flush memory ordering workaround is
used as a fallback solution only when HDP flush register is invalid

Change-Id: Ic284eba1f95ed22b0270d3abeb904fb902015b1a
 2024-05-02 19:35:13 +00:00
taosang2 e53df57ffe SWDEV-433371 - use comgr to unbundle code objects 
1.Make runtime use comgr to unbundle code objects
2.Support compressed/uncompressed modes
3.Remove HIP_USE_RUNTIME_UNBUNDLER and
  HIPRTC_USE_RUNTIME_UNBUNDLER to simplify logics
4.Add comgr wrapper for
  amd_comgr_action_info_set_bundle_entry_ids()

Change-Id: Ic41b1ad1b64cca1e31986437983a5146d52a7329
 2024-05-01 16:09:12 -04:00
Julia Jiang 996c16ad0a SWDEV-449327 - Adding CONTRIBUTING.md in clr repos 
Change-Id: I3601373f680aa4bff0075f4b3b9e885e54b4600d
 2024-05-01 11:48:29 -04:00
Rahul Manocha 59051ed3af [SWDEV-442583] - Fix hipLaunchCooperativeKernel API error codes 
Change-Id: Id3cb4b58b9efd3aceec4377d4d1d3a053c50333e
 2024-05-01 11:36:59 -04:00
Julia Jiang feaef7f54e SWDEV-455586 - create ocltst ASAN test instrumented pkg 
Change-Id: I820cacd75a36363d1387e2e881c96937281bc265
 2024-04-30 17:50:15 -04:00
Saleel Kudchadker f1ef05b121 SWDEV 301667 - Fix Debug dot print for graphs 
- Fix possible buffer overflow for long kernel names

Change-Id: I3c51669de7ff242d03f9210ee045b6d5e7ac274a
 2024-04-30 12:26:10 -04:00
Saleel Kudchadker 948ca5a931 SWDEV-301667 - Add LOG_TS mask 
- Add LOG_TS mask for printing signal times
- Read raw ticks from signals

Change-Id: Ibdd0bf06c790729f6c65083a4784c97a3c3219e0
 2024-04-30 12:24:48 -04:00
Jaydeep Patel 1d48f2a1ab SWDEV-456279 - Adding new hip flag to access contiguous memory and pass the flag to HSA API. 
Change-Id: I1bafeaa3096395c729723af958d609bc41e7845c
 2024-04-30 05:25:38 -04:00
Julia Jiang 08889f438f SWDEV-459583 - Update codeownder in clr repos 
Change-Id: Ief73138faed0af70b90186db5bde6689e0a83f88
 2024-04-29 19:00:20 -04:00
German Andryeyev 7a371503b2 SWDEV-311271 - Enable mempools under Linux 
Change-Id: I7fda94e61121f9d3a30f4ad185b8a97712922f3c
 2024-04-29 18:06:34 -04:00
kjayapra-amd 0e1a0572e6 SWDEV-413997 - Changes to use GlobalContext in views. 
Change-Id: I1f8411eae9ed49632667e244a25f223fed92c720
 2024-04-29 16:41:39 -04:00
amd-jmacaran d7d1e013d0 SWDEV-458516 - Add support for external CI builds using Azure Pipelines 
Change-Id: Iedd6290a813d6e43a4350709484f78e05b08adc8
 2024-04-29 15:31:26 -04:00
Ranjith Ramakrishnan 9e74f6de8a SWDEV-451004 - Remove .bat files from hip-dev/devel package 
The .bat file will not be removed from windows pacakge.
Also used cmake install(PROGRAMS …), which will set the correct permission rather than hard coding the permission

Change-Id: I8b57778b59f70e01de949be2ea353b67eec70d2f
 2024-04-29 14:13:26 -04:00
kjayapra-amd 49b4aef8c9 SWDEV-413997 - Handling cases where multiple phys_mem is mapped into a single virtual address. 
Change-Id: Ie678e607a64f2e5c35a10b9083185f041c5527ac
 2024-04-28 08:28:12 -04:00
German Andryeyev 5c1804aa14 SWDEV-353281 - Corret VA unmap 
Make sure graph mempool unmaps VA on release

Change-Id: Id3f1bd8d0115b533ae60aa5ba3676b8bf7e5b961
 2024-04-26 09:37:01 -04:00
Ioannis Assiouras cffff4e1cb SWDEV-457859 - Initialize isWGPMode_ in WorkGroupInfo 
Change-Id: Ie3f3c0bcea84368c1b0607fd52b4bc7cae41c512
 2024-04-25 16:36:55 -04:00
shadi f2b01782ac SWDEV-420016 - Add more driver side graph APIs 
Signed-off-by: shadi <shadi.dashmiz@amd.com>
Change-Id: Iff3ee7dcbcd24836f227fdc9bd5ff4b554ac914f
 2024-04-25 12:50:43 -04:00
German Andryeyev 9fdddb7c5d SWDEV-447691 - Correct handle type for DX12 semaphore 
Change-Id: Id23882286cb2a0d0472964ffc501ab27b7dc7f00
 2024-04-25 11:24:56 -04:00
Ioannis Assiouras 2841aab017 SWDEV-451099 - Added include for __half type definitions for non-HIP code on windows 
Change-Id: Id80cef5a36db8707276de052cbaf73b6826d222f
 2024-04-24 15:31:31 -04:00
German Andryeyev 5c23440199 SWDEV-353281 - Align VA size 
Lower layer ignores alignment

Change-Id: If16df951ecefddc804a6effe013058afc595d30f
 2024-04-24 15:22:20 -04:00
Julia Jiang 1761f1b7f5 457619 - Fixed the broken link to build HIP instructions 
Change-Id: Ica87b4ab511d26e0372502f069afc0e3baaa3256
 2024-04-24 11:41:07 -04:00
Rahul Manocha 880963346d [SWDEV-454661][SWDEV-454653] - GraphExecMemcpyNodeSetParam to return error on memcpy direction change 
Change-Id: I2c8f5ea394caeaaa6895003e63cd62a052c491f8
 2024-04-23 12:56:30 -04:00