From c4e5952687aa0d609a1c083c249e75babe0a67e6 Mon Sep 17 00:00:00 2001 From: ajay Date: Wed, 14 Jun 2023 19:21:32 +0000 Subject: [PATCH] SWDEV-404940 - __amd_rocclr_initHeap in pal. Avoid Seg fault on Windows Change-Id: I3901c003dd33222ec9e2600c519d8503f5e81c01 [ROCm/clr commit: 169d17f47fd372376f39467f675793848a907882] --- projects/clr/rocclr/device/pal/palblitcl.cpp | 7 +++++++ 1 file changed, 7 insertions(+) diff --git a/projects/clr/rocclr/device/pal/palblitcl.cpp b/projects/clr/rocclr/device/pal/palblitcl.cpp index 862919c85a..d85f68e016 100644 --- a/projects/clr/rocclr/device/pal/palblitcl.cpp +++ b/projects/clr/rocclr/device/pal/palblitcl.cpp @@ -28,6 +28,8 @@ extern void __amd_streamOpsWrite(__global uint*, __global ulong*, ulong, ulong); \n extern void __amd_streamOpsWait(__global uint*,__global ulong*, ulong, ulong, ulong); \n +extern void __ockl_dm_init_v1(ulong, ulong, uint, uint); +\n __kernel void __amd_rocclr_streamOpsWrite(__global uint* ptrInt, __global ulong* ptrUlong, ulong value, ulong sizeBytes) { __amd_streamOpsWrite(ptrInt, ptrUlong, value, sizeBytes); @@ -37,6 +39,11 @@ __kernel void __amd_rocclr_streamOpsWait(__global uint* ptrInt, __global ulong* ulong value, ulong flags, ulong mask) { __amd_streamOpsWait(ptrInt, ptrUlong, value, flags, mask); } +\n +__kernel void __amd_rocclr_initHeap(ulong heap_to_initialize, ulong initial_blocks, + uint heap_size, uint number_of_initial_blocks) { + __ockl_dm_init_v1(heap_to_initialize, initial_blocks, heap_size, number_of_initial_blocks); +} \n);