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
fd81490bb8
SWDEV-440746 - Don't set CL_SUBMITTED twice
...
Change-Id: I9ba34454f7487d6bc0d398b322a147cbac6c6443
2024-04-19 17:36:51 -04:00
8f7acbdadb
SWDEV-446610 - Attribute HIP_POINTER_ATTRIBUTE_SYNC_MEMOPS should return the correct value
...
Change-Id: Ieced2ee61bba28f2d1df96893a661287b0a5c7b7
2024-04-19 14:40:09 -04:00
bf74ef4025
SWDEV-451594 - Implement Readback and Avoid HDP Flush workaround for device kernel args
...
Change-Id: I6d41a089a17f55306e7ff402588a1e831b20a7a7
2024-04-19 09:29:20 -04:00
e829ef68e4
SWDEV-455869 - Revert "SWDEV-410751 - Consider null amd::memory is invalid."
...
This reverts commit a9ff2c5a43
2024-04-19 00:54:26 -04:00
56ebf5157a
SWDEV-413997 - VMM IPC implementation for Linux.
...
Change-Id: Icfeb83ca51e96be35abb67a94d6e3e1a1ca5a934
2024-04-18 11:28:13 -04:00
8179fa98a2
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
2024-04-18 05:39:35 -04:00
12e0bdcd32
SWDEV-453535 - Capture hipMemset3DAsync.
...
Change-Id: I517c2557573db258b3e3e353f02f6a56652b0fde
2024-04-18 00:05:45 -04:00
8942939fac
SWDEV-455346 - End wait if HostcallListener terminates.
...
Change-Id: I21ec8eadb189147c579ec65acf68de40d604686b
2024-04-18 00:04:00 -04:00
62559a6e5a
SWDEV-440746 - Fix the hostcall buffer creation
...
Avoid a deadlock on the host call buffer creation. Since the buffer will be
allocated in the queue thread, then use direct device memory allocation
skipping the global context lock.
Change-Id: I09b55ee03bb42ab5d320c152b52a8c842c5fdcc1
2024-04-17 12:37:23 -04:00
d511e57257
SWDEV-441603 - Correct dst device
...
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com >
Change-Id: Ie60aa598dd73df66cdf02c1d96daf2dfccba7a59
2024-04-17 09:21:06 -04:00
d7b0d78fad
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
2024-04-17 05:31:21 -04:00
03562a2547
SWDEV-454959 - ignore the upper half of the mask in wave32 mode
...
Change-Id: If027dd8cbe5cbe142fff353cb72c16f08e9aea8e
2024-04-17 10:12:57 +05:30
5ddca5854c
SWDEV-455699 - removing HW_REG_TRAPSTS for gfx12
...
Change-Id: I5f8b030eefdb37d3d51da3e135e5aa0f18ad9018
2024-04-16 19:46:21 -04:00
49349f168c
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
2024-04-16 18:35:08 -04:00
c95a75a2bf
SWDEV-444670 - Enable teardown class
...
Force implicit runtime teardown with a global destructor.
Change-Id: Iabe63dedf5b94fefc98668585c45a61607120669
2024-04-16 12:00:06 -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
ca07f59fb1
SWDEV-379007 initial implementation of fp8 header
...
Change-Id: Id9a5a85641882961e4d860a815217c641e6f3387
2024-04-16 05:37:59 -04:00
fcfe2ec88b
SWDEV-453577 - Fixes to account for right CU count based on WGP or CU mode
...
Change-Id: Ib9739f9917bc6ff69cc76f444d909311922ebc1e
2024-04-15 11:53:43 -04:00
00ddc3e284
SWDEV-413997 - Fixing alignment validation check for power of 2 instead of granularity factor.
...
Change-Id: I1e0db6e0628c09d26850e5a0339e2a4660442db8
2024-04-15 09:45:29 -04:00
815e450cfd
SWDEV-413997 - Read Access can be valid now that ROCr takes care of access.
...
Change-Id: Iecda74ca0207c95d3fbed8b4e15c8c4c5895d939
2024-04-15 06:00:14 -04:00
52db98edd9
SWDEV-453180 - Add UUID support for HIP_VISIBLE_DEVICES on Linux
...
- UUID is Ascii string with a maximum of 21 chars which uniquely identifies a GPU
- Convert set UUID in HIP_VISIBLE_DEVICES to device index internally
- Then use existing device index logic for HIP_VISIBLE_DEVICES
Change-Id: I8cab4fe42459f8209b97f909300789e6e687b9ac
2024-04-13 22:07:19 -04:00
d52d16c8e6
SWDEV-413997 - Fixing multiple device cases.
...
Change-Id: I10ad3fbfca887e92cd81f68392fa1acf753cbd2b
2024-04-13 06:14:03 -04:00
7de7da4016
SWDEV-455254 - Reduce blit kernels signature
...
Remove offset from blit kernels, since it can be applied in setup.
Change-Id: I06b585068d68a0ee8e125ddf46a36fccb372f30d
2024-04-12 14:45:55 -04:00
35c80dd482
SWDEV-424956 - Fix half vector printf issue
...
Refactor PrintfDbg::outputArgument() to remove potential risk.
Fix half vector printf issue on all devices.
Fix FEAT-56794 as well.
Change-Id: Iae39359d2128588def2e43d77fe58e868b8e71ff
2024-04-12 14:25:44 -04:00
Julia Jiang
Saleel Kudchadker
Jaydeep Patel
German Andryeyev
kjayapra-amd
amd-jmacaran
Ranjith Ramakrishnan
Ioannis Assiouras
shadi
Rahul Manocha
Konstantin Zhuravlyov
Rakesh Roy
Satyanvesh Dittakavi
Anusha GodavarthySurya
Jatin Chaudhary
Sameer Sahasrabuddhe
pghafari
Sourabh Betigeri
taosang2