Cycles Intel oneAPI device feedback

mostly_games · October 24, 2022, 11:26pm

So, I tried the whole thing with a Ubuntu 22.04 distrobox following the official guide on Intel’s website only installing the drivers mentioned (except for the kernel, which is shared from the host system) and I’m getting the same crash scenario here:

./blender --debug-cycles --verbose 6
Warning: Falling back to the standard locale ("C")
Read prefs: /home/alex/.config/blender/3.4/config/userpref.blend
hwconfig key 77 (UNKNOWN_INTEL_HWCONFIG) unhandled!
hwconfig key 78 (UNKNOWN_INTEL_HWCONFIG) unhandled!
hwconfig key 79 (UNKNOWN_INTEL_HWCONFIG) unhandled!
hwconfig key 80 (UNKNOWN_INTEL_HWCONFIG) unhandled!
I1025 01:15:04.518229 30587 device.cpp:104] Added device "Intel(R) Graphics [0x56a1]" with id "ONEAPI_Intel(R) Level-Zero_Intel(R) Graphics [0x56a1]_0000:2b:00.0".
I1025 01:15:21.886343 30587 device_impl.cpp:40] oneAPI queue has been successfully created for the device "Intel(R) Graphics [0x56a1]"
I1025 01:15:21.886368 30587 device_impl.cpp:52] Successfully created global/constant memory segment (kernel globals object)
terminate called after throwing an instance of 'sycl::_V1::runtime_error'
  what():  Native API failed. Native API returns: -997 (The plugin has emitted a backend specific error) -997 (The plugin has emitted a backend specific error)
fish: Job 1, './blender --debug-cycles --verb…' terminated by signal SIGABRT (Abort)

Unfortunately, debug output is not very useful.

resizeable bar is activated in my BIOS and seems to be detected as such, assuming for the A750 the memory address is different than the one mentioned in the Intel docs:

lspci -v |grep -A8 VGA

lspci: Unable to load libkmod resources: error -2
2b:00.0 VGA compatible controller: Intel Corporation Device 56a1 (rev 08) (prog-if 00 [VGA controller])
	Subsystem: Intel Corporation Device 1021
	Flags: bus master, fast devsel, latency 0, IRQ 76, IOMMU group 19
	Memory at fb000000 (64-bit, non-prefetchable) [size=16M]
	Memory at 7c00000000 (64-bit, prefetchable) [size=8G]
	Expansion ROM at fc000000 [disabled] [size=2M]
	Capabilities: <access denied>

So for the moment, I have to assume that this is either an issue with trying to run blender in a container and/or an issue with using kernel 6.1. Since I don’t want to install Ubuntu on “bare metal”, I guess I will have to wait for drivers and compatibility to improve for other distributions/configurations.

xavier · October 25, 2022, 7:36am

It’s definitely not explicit but seeing the stage at which it’s failing is still helpful, here it’s as soon as it allocates memory. That confirms an incompatibility across some of your driver components, especially intel-gmmlib vs the rest.
You’re right it will improve over time but if you still want to get it working now with kernel 6.1, I recommend using all components listed in latest release from GitHub - intel/compute-runtime: Intel® Graphics Compute Runtime for oneAPI Level Zero and OpenCL™ Driver instead of in https://dgpu-docs.intel.com/releases/stable_449_3_20220930.html that is targeting a more specific kernel.

mostly_games · October 25, 2022, 9:21am

Unfortunately, that didn’t help. I installed all packages from the latest release (which basically put me in the same situation I had been before with Arch), but Blender still crashes with the same error message at the same point.

xavier · October 25, 2022, 9:42am

That was still worth trying. Everything upstream is still expected to work: Intel Arc Graphics A750 + A770 Are Ready To Run On Open-Source Linux Drivers - Phoronix had success with it.
Do you have Mesa 22.2 or 22.3, latest linux-firmware.git on the host?
It may be smoother to make the whole stack work on your Fedora first before looking at distrobox.

mostly_games · October 25, 2022, 9:49am

Yes, I have also tried with the very latest Mesa drivers (mesa-git 22.3) and firmware drivers from git. No difference. Performance and compatibility in 3D applications on Linux is still very bad overall, as other users on e.g. reddit are also reporting. I was hoping to be at least able to test/run the cards compute capabilities in the mean time, but Blender won’t let me.

Installing the whole stack on Fedora is a lot more tricky than on Ubuntu and Arch, but might be worth a shot. Maybe Intel could be convinced to distribute the drivers in a more distro agnostic way in the future

For now, I will try to build blender myself and see, if that makes any difference.

xavier · October 25, 2022, 10:33am

I’m not expecting it to make any difference considering the current issue, sorry. Expect it to be a smooth process though, since on Linux the whole toolchain is open source down to the graphics compiler and pre-packaged on svn

The dgpu-docs website focuses on a restricted set of distributions but repositories and work upstream are distro agnostic. It takes time for latest developments to reach all distributions and it’s always more complex if you want to stay ahead to use latest hardware, I’m not sure what could be done to make it easier.

I’m using ubuntu 22.04 with xorg and I don’t know the perf and compatibility with other games and applications but I can say Blender is running well there with similar performance as Windows.

mostly_games · November 7, 2022, 5:06pm

I just came by to report hat after 2 weeks worth of driver updates, testing many different distros and the most recent versions of blender, I still can’t get Cycles OneAPI working on Linux with Intel Arc 750. So no progress has been made. I always get the same crash and error message, as mentioned before:

terminate called after throwing an instance of 'sycl::_V1::runtime_error'
  what():  Native API failed. Native API returns: -997 (The plugin has emitted a backend specific error) -997 (The plugin has emitted a backend specific error)

Since there are no reports from other users so far, the issue could be anything from faulty hardware on my end to an actual bug in the blender implementation of Cycles oneapi or drivers simply still not being up to snuff. I will report back periodically in case I make any progress.

igor · November 10, 2022, 7:54pm

I’ve been able to run blender cycles successfully with Arc A380 using official Intel’s linux driver release.
Installed drivers and APIs as described here (has to downgrade kernel from 6.0 to 5.19-oem):
https://intel.github.io/intel-extension-for-tensorflow/latest/docs/install/install_for_gpu.html#install-oneapi-base-toolkit-packages
Here is blender output:

I1110 14:42:26.657354 77152 device.cpp:70] oneAPI kernel shared library has been loaded successfully
I1110 14:42:26.714324 77152 device.cpp:159] Added device "Intel(R) Graphics [0x56a5]" with id "ONEAPI_Intel(R) Level-Zero_Intel(R) Graphics [0x56a5]_0000:03:00.0".
I1110 14:42:34.785164 77456 device_impl.cpp:58] Using AVX2 CPU kernels.
I1110 14:42:35.301255 77456 sync.cpp:288] Total time spent synchronizing data: 0.515468
I1110 14:42:35.302474 77458 film.cpp:584] Effective scene passes:
I1110 14:42:35.302575 77458 film.cpp:586] - type: combined, name: "Combined", mode: DENOISED, is_written: True
I1110 14:42:35.302631 77458 film.cpp:586] - type: combined, name: "Noisy Image", mode: NOISY, is_written: True
I1110 14:42:35.302680 77458 film.cpp:586] - type: denoising_normal, name: "", mode: NOISY, is_written: True
I1110 14:42:35.302727 77458 film.cpp:586] - type: denoising_albedo, name: "", mode: NOISY, is_written: True
I1110 14:42:35.302771 77458 film.cpp:586] - type: depth, name: "Depth", mode: NOISY, is_written: True
I1110 14:42:35.302872 77458 scene.cpp:591] Requested features:
I1110 14:42:35.302927 77458 scene.cpp:592] Use BSDF True
I1110 14:42:35.302973 77458 scene.cpp:593] Use Principled BSDF True
I1110 14:42:35.303021 77458 scene.cpp:595] Use Emission True
I1110 14:42:35.303067 77458 scene.cpp:597] Use Volume True
I1110 14:42:35.303114 77458 scene.cpp:598] Use Bump False
I1110 14:42:35.303160 77458 scene.cpp:599] Use Voronoi False
I1110 14:42:35.303208 77458 scene.cpp:601] Use Shader Raytrace False
I1110 14:42:35.303256 77458 scene.cpp:603] Use MNEEFalse
I1110 14:42:35.303304 77458 scene.cpp:604] Use Transparent True
I1110 14:42:35.303351 77458 scene.cpp:606] Use Denoising True
I1110 14:42:35.303398 77458 scene.cpp:607] Use Path Tracing True
I1110 14:42:35.303447 77458 scene.cpp:609] Use Hair True
I1110 14:42:35.303493 77458 scene.cpp:610] Use Pointclouds False
I1110 14:42:35.303539 77458 scene.cpp:612] Use Object Motion False
I1110 14:42:35.303593 77458 scene.cpp:614] Use Camera Motion False
I1110 14:42:35.303642 77458 scene.cpp:616] Use Baking False
I1110 14:42:35.303689 77458 scene.cpp:617] Use Subsurface True
I1110 14:42:35.303733 77458 scene.cpp:618] Use Volume True
I1110 14:42:35.303781 77458 scene.cpp:619] Use Patch Evaluation False
I1110 14:42:35.303828 77458 scene.cpp:621] Use Shadow Catcher False
I1110 14:42:35.713069 77458 device_impl.cpp:107] Runtime compilation done for "Intel(R) Graphics [0x56a5]"
I1110 14:42:35.713124 77458 svm.cpp:73] Total 12 shaders.
I1110 14:42:35.884994 77458 svm.cpp:149] Shader manager updated 12 shaders in 0.171873 seconds.
I1110 14:42:35.885095 77458 object.cpp:691] Total 9 objects.
I1110 14:42:35.921519 77458 particles.cpp:108] Total 0 particle systems.
I1110 14:42:35.949064 77458 geometry.cpp:1805] Total 9 meshes.
I1110 14:42:36.347718 77458 geometry.cpp:1294] Using BVH2 layout.
I1110 14:42:36.685837 77458 camera.cpp:542] Camera is outside of the volume.
I1110 14:42:36.685868 77458 tables.cpp:37] Total 1 lookup tables.
I1110 14:42:36.686214 77458 light.cpp:982] Total 1 lights.
I1110 14:42:36.686237 77458 light.cpp:961] Number of lights sent to the device: 1
I1110 14:42:36.686247 77458 light.cpp:963] Number of lights without contribution: 0
I1110 14:42:36.686607 77458 light.cpp:314] Total 31745 of light distribution primitives.
I1110 14:42:36.692528 77458 tables.cpp:37] Total 2 lookup tables.
I1110 14:42:36.693300 77458 scene.cpp:378] System memory statistics after full device sync:
  Usage: 33,868,042 (32.30M)
  Peak: 34,134,282 (32.55M)
I1110 14:42:36.693351 77458 device_impl.cpp:58] Using AVX2 CPU kernels.
I1110 14:42:37.322999 77458 path_trace.cpp:387] Rendered 1 samples in 0.60295 seconds (0.60295 seconds per sample), occupancy: 0.050666
I1110 14:42:37.323666 77458 path_trace_work_gpu.cpp:852] Using naive GPU display update.
I1110 14:42:41.738976 77458 path_trace.cpp:387] Rendered 14 samples in 4.40846 seconds (0.31489 seconds per sample), occupancy: 0.372979
I1110 14:42:50.005512 77458 path_trace.cpp:387] Rendered 26 samples in 8.26171 seconds (0.317758 seconds per sample), occupancy: 0.478899
I1110 14:43:02.218780 77458 path_trace.cpp:387] Rendered 38 samples in 12.2099 seconds (0.321314 seconds per sample), occupancy: 0.52293
I1110 14:43:08.803202 77458 path_trace.cpp:387] Rendered 21 samples in 6.57638 seconds (0.313161 seconds per sample), occupancy: 0.466492
I1110 14:43:18.243932 77458 session.cpp:152] Rendering in main loop is done in 41.5251 seconds.
I1110 14:43:18.243964 77458 session.cpp:153] 
Full path tracing report

Path tracing on: Intel(R) Graphics [0x56a5] (oneAPI) [ONEAPI_Intel(R) Level-Zero_Intel(R) Graphics [0x56a5]_0000:03:00.0]

Denoising on: Intel Core i5-10400 CPU @ 2.90GHz (CPU) (12 threads) [CPU]

Render Scheduler Summary

Mode: Background
Resolution: 960x540

Adaptive sampling:
  Use: False

Denoiser:
  Use: True
  Type: OpenImageDenoise
  Start Sample: 0
  Passes: Color, Albedo, Normal

Time (in seconds):
                                       Wall              Average
          Path Tracing            32.059757             0.320598
              Denoiser             9.322865             9.322865
        Display Update             0.040613             0.008123

  Total: 41.423235

Rendered 100 samples in 41.524962 seconds
Average time per sample: 0.415250 seconds
I1110 14:43:18.245975 77456 session.cpp:461] Total render time: 43.4992
I1110 14:43:18.246012 77456 session.cpp:462] Render time (without synchronization): 41.5272

mostly_games · November 11, 2022, 11:52am

What happened before the kernel downgrade? Did blender crash or was your card simply not detected as a compatible device?

igor · November 11, 2022, 2:19pm

The installation didn’t go well with kernel 6.0. At some stage I got message about “unsupported kernel”.
This happened when I was running the following line from guide:
sudo apt-get install -y intel-i915-dkms intel-fw-gpu
So I re-installed Ubuntu 22.04 and installed kernel 5.17.0-1019-oem (as described in guide, sorry, not 5.19 - my mistake).
Initially I had Ubuntu 22.10 with mesa 22.3 and latest Neo driver, Blender didn’t detect Intel GPU hardware.

mostly_games · November 30, 2022, 11:35am

Update: Blender still crashes immediately even with version 3.5 Beta whenever I enable GPU Compute for Cycles with my Intel Arc A750

I am running Fedora 37 on Kernel 6.0.10-300, intel-compute-runtime version 22.43.24558, mesa 22.2.3

As stated above I have tested other distrubtions with different kernel and driver versions with the same result.

Currently all reports of people sucessfully running Blender with Cycles OneAPI on Intel Arc have been from people running Ubuntu with OEM Kernel 5.17 (+ DKMS modules by Intel). Is this being looked into to make Cycles oneAPI usable (i.e. not crash) with other/newer Linux Kernels so we are not forced to use Ubuntu?

I have attached my console output (running blender with SYCL_PI_TRACE=2 and --debug-cycles --verbose 6) in case this might be helpful:

 ---> piPlatformsGet(
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48fd74
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piPlatformsGet(
 	<unknown> : 1
 	<unknown> : 0x7f38e7de7c18
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e7de7c18[ 0x7f38e89ea300 ... ]
 
 ---> piPlatformGetInfo(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 2306
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48fc48
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piPlatformGetInfo(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 2306
 	<unknown> : 20
 	<char * > : 0x7f38e5e37320
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDevicesGet(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 4294967295
 	<unknown> : 0
 	<unknown> : 0
 	<unknown> : 0x7ffd4c48fbbc
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0[ nullptr ]
 
 ---> piDevicesGet(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 4294967295
 	<unknown> : 1
 	<unknown> : 0x7f38e7de7cd8
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e7de7cd8[ 0x7f38e5e04600 ... ]
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4096
 	<unknown> : 8
 	<unknown> : 0x7ffd4c48fbf0
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4096
 	<unknown> : 8
 	<unknown> : 0x7f38e8cfdbd8
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4162
 	<unknown> : 8
 	<unknown> : 0x7f38e8cfdbe0
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e8cfdbe0[ 0 ... ]
 
 ---> piDeviceRetain(
 	<unknown> : 0x7f38e5e04600
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4144
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48f8e8
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4144
 	<unknown> : 215
 	<char * > : 0x7f39222054e0
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceRelease(
 	<unknown> : 0x7f38e5e04600
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDevicesGet(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 4
 	<unknown> : 0
 	<unknown> : 0
 	<unknown> : 0x7ffd4c48fcec
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0[ nullptr ]
 
 ---> piDevicesGet(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 4
 	<unknown> : 1
 	<unknown> : 0x7f38e7de7c18
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e7de7c18[ 0x7f38e5e04600 ... ]
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4096
 	<unknown> : 8
 	<unknown> : 0x7ffd4c48fd20
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4096
 	<unknown> : 8
 	<unknown> : 0x7f38e8cfdc38
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4162
 	<unknown> : 8
 	<unknown> : 0x7f38e8cfdc40
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e8cfdc40[ 0 ... ]
 
 ---> piDeviceRetain(
 	<unknown> : 0x7f38e5e04600
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4144
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48fa18
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4144
 	<unknown> : 215
 	<char * > : 0x7f39222054e0
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65569
 	<unknown> : 8
 	<unknown> : 0x7ffd4c48fe20
 	<unknown> : 0x7ffd4c48fe18
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65569
 	<unknown> : 4
 	<unknown> : 0x7ffd4c48fddc
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65810
 	<unknown> : 8
 	<unknown> : 0x7ffd4c48fe20
 	<unknown> : 0x7ffd4c48fe18
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65810
 	<unknown> : 4
 	<unknown> : 0x7ffd4c48fddc
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4141
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48fd78
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4141
 	<unknown> : 10
 	<char * > : 0x7f38e5df47f0
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piPlatformGetInfo(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 2306
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48fe18
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piPlatformGetInfo(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 2306
 	<unknown> : 20
 	<char * > : 0x7f38e5e37340
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4139
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48fe88
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4139
 	<unknown> : 27
 	<char * > : 0x7f38e5e37340
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65568
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48feb8
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65568
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48fe98
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65568
 	<unknown> : 13
 	<char * > : 0x7f38e5df47e0
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceRelease(
 	<unknown> : 0x7f38e5e04600
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piPlatformsGet(
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48f4a4
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piPlatformsGet(
 	<unknown> : 1
 	<unknown> : 0x7f38e7de7cf0
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e7de7cf0[ 0x7f38e89ea300 ... ]
 
 ---> piPlatformGetInfo(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 2306
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48f378
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piPlatformGetInfo(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 2306
 	<unknown> : 20
 	<char * > : 0x7f38e667d100
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDevicesGet(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 4294967295
 	<unknown> : 0
 	<unknown> : 0
 	<unknown> : 0x7ffd4c48f2ec
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0[ nullptr ]
 
 ---> piDevicesGet(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 4294967295
 	<unknown> : 1
 	<unknown> : 0x7f38e7de7a30
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e7de7a30[ 0x7f38e5e04600 ... ]
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4096
 	<unknown> : 8
 	<unknown> : 0x7ffd4c48f320
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4096
 	<unknown> : 8
 	<unknown> : 0x7f38d86f9458
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4162
 	<unknown> : 8
 	<unknown> : 0x7f38d86f9460
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38d86f9460[ 0 ... ]
 
 ---> piDeviceRetain(
 	<unknown> : 0x7f38e5e04600
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4144
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48f018
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4144
 	<unknown> : 215
 	<char * > : 0x7f38d8811020
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceRelease(
 	<unknown> : 0x7f38e5e04600
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDevicesGet(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 4
 	<unknown> : 0
 	<unknown> : 0
 	<unknown> : 0x7ffd4c48f41c
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0[ nullptr ]
 
 ---> piDevicesGet(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 4
 	<unknown> : 1
 	<unknown> : 0x7f38e7de7cf0
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e7de7cf0[ 0x7f38e5e04600 ... ]
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4096
 	<unknown> : 8
 	<unknown> : 0x7ffd4c48f450
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4096
 	<unknown> : 8
 	<unknown> : 0x7f38f361c018
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4162
 	<unknown> : 8
 	<unknown> : 0x7f38f361c020
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38f361c020[ 0 ... ]
 
 ---> piDeviceRetain(
 	<unknown> : 0x7f38e5e04600
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4144
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48f148
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4144
 	<unknown> : 215
 	<char * > : 0x7f38d8811020
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65569
 	<unknown> : 8
 	<unknown> : 0x7ffd4c48f550
 	<unknown> : 0x7ffd4c48f548
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65569
 	<unknown> : 4
 	<unknown> : 0x7ffd4c48f50c
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65810
 	<unknown> : 8
 	<unknown> : 0x7ffd4c48f550
 	<unknown> : 0x7ffd4c48f548
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65810
 	<unknown> : 4
 	<unknown> : 0x7ffd4c48f50c
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4141
 	<unknown> : 0
 	<nullptr>
 	<unknown> : 0x7ffd4c48f4a8
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4141
 	<unknown> : 10
 	<char * > : 0x7f38d880d540
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDevicesGet(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 4294967295
 	<unknown> : 0
 	<unknown> : 0
 	<unknown> : 0x7ffd4c48f2cc
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0[ nullptr ]
 
 ---> piDevicesGet(
 	pi_platform : 0x7f38e89ea300
 	<unknown> : 4294967295
 	<unknown> : 1
 	<unknown> : 0x7f38e7de7cf0
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e7de7cf0[ 0x7f38e5e04600 ... ]
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4096
 	<unknown> : 8
 	<unknown> : 0x7ffd4c48f300
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piContextCreate(
 	<nullptr>
 	<unknown> : 1
 	<unknown> : 0x7f38e7de7cf0
 	<nullptr>
 	<nullptr>
 	<unknown> : 0x7f38d88b2248
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e7de7cf0[ 0x7f38e5e04600 ... ]
 	[out]<unknown> ** : 0x7f38d88b2248[ 0x7f38f7bfc580 ... ]
 
 ---> piQueueCreate(
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0
 	<unknown> : 0x7ffd4c48f458
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7ffd4c48f458[ 0x7f38e8d357c0 ... ]
 
 ---> piextUSMHostAlloc(
 	<unknown> : 0x7ffd4c48f580
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7ffd4c48f5a0
 	<unknown> : 368
 	<unknown> : 16
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7ffd4c48f580[ 0x7f38f68e5000 ... ]
 
 ---> piextUSMEnqueueMemset(
 	<unknown> : 0x7f38e8d357c0
 	<unknown> : 0x7f38f68e5000
 	<unknown> : 0
 	<unknown> : 368
 	<unknown> : 0
 	pi_event * : 0[ nullptr ]
 	pi_event * : 0x7ffd4c48f548[ 0 ... ]
 ) ---> 	pi_result : PI_SUCCESS
 	[out]void * : 0x7f38f68e5000
 	[out]pi_event * : 0[ nullptr ]
 	[out]pi_event * : 0x7ffd4c48f548[ 0x7f38d880f420 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7ffd4c48f528
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7ffd4c48f570
 	<unknown> : 368
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7ffd4c48f528[ 0xffffd556aa350000 ... ]
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 4127
 	<unknown> : 8
 	<unknown> : 0x7ffd4c48f658
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piextUSMHostAlloc(
 	<unknown> : 0x7f38e4cf7b00
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e4cf7b20
 	<unknown> : 32
 	<unknown> : 16
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7b00[ 0x7f38f65e5000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7aa8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7af0
 	<unknown> : 32
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7aa8[ 0xffffd556aa350200 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7aa8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7af0
 	<unknown> : 32
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7aa8[ 0xffffd556aa350400 ... ]
 
 ---> piextUSMEnqueueMemcpy(
 	<unknown> : 0x7f38e8d357c0
 	<unknown> : 0
 	<unknown> : 0xffffd556aa350200
 	<unknown> : 0x7f38f65e5000
 	<unknown> : 32
 	<unknown> : 0
 	pi_event * : 0[ nullptr ]
 	pi_event * : 0x7f38e4cf7ad8[ 0 ... ]
 ) ---> 	pi_result : PI_SUCCESS
 	[out]void * : 0xffffd556aa350200
 	[out]pi_event * : 0[ nullptr ]
 	[out]pi_event * : 0x7f38e4cf7ad8[ 0x7f38d88111e0 ... ]
 
 ---> piEventRelease(
 	pi_event : 0x7f38d880f420
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piQueueFinish(
 	<unknown> : 0x7f38e8d357c0
 ) ---> 	pi_result : -997
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65569
 	<unknown> : 8
 	<unknown> : 0x7f38e4cf7c80
 	<unknown> : 0x7f38e4cf7c78
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65569
 	<unknown> : 4
 	<unknown> : 0x7f38e4cf7c3c
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65570
 	<unknown> : 8
 	<unknown> : 0x7f38e4cf7c80
 	<unknown> : 0x7f38e4cf7c78
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65810
 	<unknown> : 8
 	<unknown> : 0x7f38e4cf7c80
 	<unknown> : 0x7f38e4cf7c78
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65570
 	<unknown> : 4
 	<unknown> : 0x7f38e4cf7c3c
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65810
 	<unknown> : 4
 	<unknown> : 0x7f38e4cf7c3c
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65569
 	<unknown> : 8
 	<unknown> : 0x7f38e4cf7cb0
 	<unknown> : 0x7f38e4cf7ca8
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65569
 	<unknown> : 4
 	<unknown> : 0x7f38e4cf7c6c
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65570
 	<unknown> : 8
 	<unknown> : 0x7f38e4cf7cb0
 	<unknown> : 0x7f38e4cf7ca8
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65810
 	<unknown> : 8
 	<unknown> : 0x7f38e4cf7cb0
 	<unknown> : 0x7f38e4cf7ca8
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65570
 	<unknown> : 4
 	<unknown> : 0x7f38e4cf7c6c
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piDeviceGetInfo(
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 65810
 	<unknown> : 4
 	<unknown> : 0x7f38e4cf7c6c
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556aaa00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ab800000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ac600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ace00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ad600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ade00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ae600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556aee00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556af600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556afe00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556b0600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556b1400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556b1c00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 3670016
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffffffff600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556b2a00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556b3800000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556b4600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 44040192
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556b5400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556b7e00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 44040192
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556b8c00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 44040192
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556bb600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556be000000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556bee00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556bfc00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c0a00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c1800000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c2600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c3400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c4200000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c5000000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c5e00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c6c00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c7a00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c8800000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556c9600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ca400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556cac00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556cb400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556cbc00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556cc400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ccc00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556cd400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556cdc00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 44040192
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556cea00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 7340032
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556d1400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 3670016
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffffffff200000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 44040192
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556d1c00000 ... ]

mostly_games · November 30, 2022, 11:36am

 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 44040192
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556d4600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556d7000000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556d7e00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556d8c00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556d9a00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556da800000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556db600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556dc400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556dd200000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556de000000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556dee00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556dfc00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e0a00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e1800000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e2600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e3400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e4200000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e5000000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e5e00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e6c00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e7a00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e8800000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556e9600000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ea400000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556eb200000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ec000000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ece00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556edc00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556eea00000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7ae8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b30
 	<unknown> : 14680064
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7ae8[ 0xffffd556ef800000 ... ]
 
 ---> piextUSMDeviceAlloc(
 	<unknown> : 0x7f38e4cf7af8
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38e5e04600
 	<unknown> : 0x7f38e4cf7b40
 	<unknown> : 56
 	<unknown> : 0
 ) ---> 	pi_result : PI_SUCCESS
 	[out]<unknown> ** : 0x7f38e4cf7af8[ 0xffffd556aa350600 ... ]
 
 ---> piextUSMEnqueueMemset(
 	<unknown> : 0x7f38e8d357c0
 	<unknown> : 0xffffd556aa350600
 	<unknown> : 0
 	<unknown> : 56
 	<unknown> : 0
 	pi_event * : 0[ nullptr ]
 	pi_event * : 0x7f38e4cf7bd8[ 0 ... ]
 ) ---> 	pi_result : PI_SUCCESS
 	[out]void * : 0xffffd556aa350600
 	[out]pi_event * : 0[ nullptr ]
 	[out]pi_event * : 0x7f38e4cf7bd8[ 0x7f38d8811560 ... ]
 
 ---> piEventRelease(
 	pi_event : 0x7f38d88111e0
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piextUSMEnqueueMemcpy(
 	<unknown> : 0x7f38e8d357c0
 	<unknown> : 0
 	<unknown> : 0x7f38d88a3020
 	<unknown> : 0xffffd556aa350600
 	<unknown> : 56
 	<unknown> : 0
 	pi_event * : 0[ nullptr ]
 	pi_event * : 0x7f38e4cf7b88[ 0 ... ]
 ) ---> 	pi_result : PI_SUCCESS
 	[out]void * : 0x7f38d88a3020
 	[out]pi_event * : 0[ nullptr ]
 	[out]pi_event * : 0x7f38e4cf7b88[ 0x7f38d8811720 ... ]
 
 ---> piEventRelease(
 	pi_event : 0x7f38d8811560
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piextUSMGetMemAllocInfo(
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0x7f38d88a3020
 	<unknown> : 16794
 	<unknown> : 4
 	<unknown> : 0x7f38e4cf7c4c
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piextUSMGetMemAllocInfo(
 	<unknown> : 0x7f38f7bfc580
 	<unknown> : 0xffffd556aa350600
 	<unknown> : 16794
 	<unknown> : 4
 	<unknown> : 0x7f38e4cf7c4c
 	<nullptr>
 ) ---> 	pi_result : PI_SUCCESS
 
 ---> piEventsWait(
 	<unknown> : 1
 	pi_event * : 0x7f38d873bad8[ 0x7f38d8811720 ... ]
 ) ---> 	pi_result : -997
 	[out]pi_event * : 0x7f38d873bad8[ 0x7f38d8811720 ... ]
terminate called after throwing an instance of 'sycl::_V1::runtime_error'
  what():  Native API failed. Native API returns: -997 (The plugin has emitted a backend specific error) >-997 (The plugin has emitted a backend specific error)
fish: Job 1, 'SYCL_PI_TRACE=2 LD_LIBRARY_PATH…' terminated by signal SIGABRT

LazyDodo · November 30, 2022, 3:37pm

Moderation notice: fixed your logs a tiny bit, next time please reconsider posting a 2km long log directly into the forum.

xavier · December 6, 2022, 9:46am

Your logs show it’s failing a bit further than before, during memory copies, after the allocations.
Release 22.43.24595.30 · intel/compute-runtime · GitHub just got released and now claims production quality for Intel Arc when used with DKMS driver so it has good chances to work.
If it still doesn’t work, next step will be to open a bug report there.