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
31935b1d39
SWDEV-459325 - Remove hiprtc sources from libhipamd64 compilation.
...
Change-Id: Ic70206c5936fb36a23c122e67110b91ae7e95e09
2024-05-28 06:28:17 +00:00
2cfc42368e
SWDEV-445072 - Fixing error on static library for hip package.
...
Change-Id: I96d2b9000e290739870e201b599bdef8859b971a
2024-05-28 06:28:17 +00:00
b9c65fb7ff
SWDEV-445072 - Enable RTC outside of BUILD_SHARED_LIBS variable.
...
Change-Id: Iab9f1cb2bdf24163979e2b646bdbed3f1508b221
2024-05-28 06:28:17 +00:00
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
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
45dccd6eab
SWDEV-453739 - Added definition for undeclared methods
...
Change-Id: I3f10e0a3fb4bbaf9d873a6a988847f05ac43a312
2024-05-28 06:28:17 +00:00
de95625f09
SWDEV-454247 - Fix graph multi threading issue
...
Change-Id: I565889da6f7091030b7f6a2d6234b82c389358e3
2024-05-28 06:28:17 +00:00
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
c7461436d6
SWDEV-459254 - Change return type to support values > 128.
...
Change-Id: Ib4c9a3718c4cb26b24503fe4d9af3e63e151e843
2024-05-28 06:28:17 +00:00
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
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
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
87619af175
SWDEV-459556 - Revert "SWDEV-442724 - Remove uses of -amdgpu-early-inline-all to enable function calls"
...
This reverts commit a09204388a
2024-05-28 06:28:17 +00:00
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
f5d0ee650b
SWDEV-460151 - Enabling gfx12 in HIP runtime.
...
Change-Id: I374ea7c3119b0c61f9846a862c4a448ddb179748
2024-05-28 06:28:07 +00:00
2eb30376ba
SWDEV-451945 - Remove ShouldLoadPlatform function
...
Change-Id: Iabb4071bb77201576bc2c0488a04f4fa188815df
2024-05-06 10:42:59 -04:00
4a9d24a211
SWDEV-301667 - Pass reference to kernel name
...
Change-Id: I21abe109ddfabfe7640bf78a96c81a1317d31952
2024-05-05 16:38:20 -04:00
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
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
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
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
996c16ad0a
SWDEV-449327 - Adding CONTRIBUTING.md in clr repos
...
Change-Id: I3601373f680aa4bff0075f4b3b9e885e54b4600d
2024-05-01 11:48:29 -04:00
59051ed3af
[SWDEV-442583] - Fix hipLaunchCooperativeKernel API error codes
...
Change-Id: Id3cb4b58b9efd3aceec4377d4d1d3a053c50333e
2024-05-01 11:36:59 -04:00
feaef7f54e
SWDEV-455586 - create ocltst ASAN test instrumented pkg
...
Change-Id: I820cacd75a36363d1387e2e881c96937281bc265
2024-04-30 17:50:15 -04:00
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
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
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
08889f438f
SWDEV-459583 - Update codeownder in clr repos
...
Change-Id: Ief73138faed0af70b90186db5bde6689e0a83f88
2024-04-29 19:00:20 -04:00
7a371503b2
SWDEV-311271 - Enable mempools under Linux
...
Change-Id: I7fda94e61121f9d3a30f4ad185b8a97712922f3c
2024-04-29 18:06:34 -04:00
0e1a0572e6
SWDEV-413997 - Changes to use GlobalContext in views.
...
Change-Id: I1f8411eae9ed49632667e244a25f223fed92c720
2024-04-29 16:41:39 -04:00
d7d1e013d0
SWDEV-458516 - Add support for external CI builds using Azure Pipelines
...
Change-Id: Iedd6290a813d6e43a4350709484f78e05b08adc8
2024-04-29 15:31:26 -04:00
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
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
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
cffff4e1cb
SWDEV-457859 - Initialize isWGPMode_ in WorkGroupInfo
...
Change-Id: Ie3f3c0bcea84368c1b0607fd52b4bc7cae41c512
2024-04-25 16:36:55 -04:00
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
9fdddb7c5d
SWDEV-447691 - Correct handle type for DX12 semaphore
...
Change-Id: Id23882286cb2a0d0472964ffc501ab27b7dc7f00
2024-04-25 11:24:56 -04:00
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
5c23440199
SWDEV-353281 - Align VA size
...
Lower layer ignores alignment
Change-Id: If16df951ecefddc804a6effe013058afc595d30f
2024-04-24 15:22:20 -04:00
1761f1b7f5
457619 - Fixed the broken link to build HIP instructions
...
Change-Id: Ica87b4ab511d26e0372502f069afc0e3baaa3256
2024-04-24 11:41:07 -04:00
880963346d
[SWDEV-454661][SWDEV-454653] - GraphExecMemcpyNodeSetParam to return error on memcpy direction change
...
Change-Id: I2c8f5ea394caeaaa6895003e63cd62a052c491f8
2024-04-23 12:56:30 -04:00
5a715ed160
Switch luxmark to lightning compiler for all ASICs
...
Change-Id: Idcd37628a2167f0bd2db2a83132a1862cbd051b0
2024-04-23 10:00:39 -04:00
74ffc5f0d5
SWDEV-413997 - Cleanup fixes for Virtual Memory Management.
...
Change-Id: I9a4a4d9087b5daf15e3ba31e786d34db431212a1
2024-04-22 10:58:06 -04:00
0ccdb3e160
SWDEV-440746 - Release last command on terminate
...
Change-Id: Ib6a9b8fc9a8692eb17b39b854cefd92c6b59733f
2024-04-22 09:57:38 -04:00
7448113cfc
SWDEV-440746 - Remove obsolete code
...
The "optimized" version of memcpy is outdated and
was used in win32 only.
Change-Id: I7f2e0e9051e37cec95438266824b5b0025c324c6
2024-04-22 09:56:42 -04:00
863c56262e
SWDEV-455041 - Continue processing fat binary even if other code object bundle processing fail.
...
Change-Id: Iea553ab0265c08341f915644075ce2b6ed9b3200
2024-04-20 14:25:49 -04:00
fb217fa9e0
SWDEV-453180 - Add UUID support for HIP_VISIBLE_DEVICES on Windows
...
- UUID needs to be specified in the format GPU-<body>, <body> encodes UUID as a 16 chars
- Convert set UUID in HIP_VISIBLE_DEVICES to device index internally
- Then use existing device index logic for HIP_VISIBLE_DEVICES
Change-Id: I654f492a49cd4d7a9b7339360ab558165240caa5
2024-04-20 02:39:19 -04:00
329ba271fa
SWDEV-440746 - Wait for signal before release
...
Change-Id: I9e2aefdbcbba153c7f1080d80aab7a345eaf1eb4
2024-04-19 18:33:28 -04:00
ffb516db3e
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
2024-04-19 18:00:29 -04:00
shadi
kjayapra-amd
Anusha GodavarthySurya
Saleel Kudchadker
Ioannis Assiouras
Rakesh Roy
German Andryeyev
Alex Xie
Maneesh Gupta
taosang2
Julia Jiang
Rahul Manocha
Jaydeep Patel
amd-jmacaran
Ranjith Ramakrishnan
Rahul Manocha
Konstantin Zhuravlyov