devbox
小惠珠哦
这个屌丝很懒，什么也没留下！
关注作者
热门标签
热门文章
当前位置:   article > 正文

基于AMDGPU-ROCm的深度学习环境搭建_amd 上使用gpu 做深度学习

作者：小惠珠哦 | 2024-08-08 05:46:28

赞

踩

amd 上使用gpu 做深度学习

在风起云涌的AI江湖，NVIDIA凭借其CUDA生态和优秀的硬件大杀四方，立下赫赫战功，而另一家公司AMD也不甘示弱，带着他的生态解决方案ROCm开始了与不世出的NVIDA的正面硬钢，"ROCm is the answer to CUDA", AMD官网如是说。ROCm全称是Radeon Open Compute，从功能上，它是AMD提供的一套用于支持异构计算和GPU加速计算的开发工具和平台。

根据ROCm的官方介绍，这套框架不但支持AMD专业的计算卡，也支持AMD消费级的电脑显卡，之前有搭建过N卡CUDA的学习平台，这里尝试基于AMDGPU，搭建一个ROCm的学习平台。

平台信息

基于Ubuntu 20.04.6 LTS x86_64，显卡为AMD Ryzen 5 5600G with Radeon Graphics集显，应该是VEGA系列，支持VULKAN，OPENCL，当然，不支持CUDA。

搭建步骤

执行如下命令序列，添加用户组和安装ROCm一步到位：

  1. sudo apt update && sudo apt dist-upgrade
  2. sudo apt-get install wget gnupg2 
  3. sudo usermod -a -G video $LOGNAME
  4. sudo usermod -a -G render $LOGNAME
  5. echo 'ADD_EXTRA_GROUPS=1' | sudo tee -a /etc/adduser.conf
  6. echo 'EXTRA_GROUPS=video' | sudo tee -a /etc/adduser.conf
  7. echo 'EXTRA_GROUPS=render' | sudo tee -a /etc/adduser.conf
  8. sudo wget https://repo.radeon.com/amdgpu-install/22.10/ubuntu/focal/amdgpu-install_22.10.50100-1_all.deb
  9. sudo apt-get install ./amdgpu-install_22.10.50100-1_all.deb 
  10. sudo amdgpu-install --usecase=dkms
  11. amdgpu-install -y --usecase=rocm
  12. echo 'export PATH=$PATH:/opt/rocm/bin:/opt/rocm/profiler/bin:/opt/rocm/opencl/bin' | sudo tee -a /etc/profile.d/rocm.sh

安装结束后，ROCm开发SDK将会出现在/opt目录下， 包括LLVM编译器, opencl, profile, tools等开发工具，便于用户开发自己的基于AMDGPU加速的应用程序。总的来说， ROCm SDK提供了完整的栈支持，包括运行时、编译器、调试器、性能分析工具等，以满足不同开发和优化需求。

AMDGPU编译器目录

测试环境

执行rocm-smi获取显卡设备信息，执行时发现在获取SCLK和功耗两个参数时报错，可能是SDK和显卡兼容方面的问题，不过没有影响后面的简单测试，所以也就没有理会。

AMD一直提倡一种混合异构架构（HSA），这种架构下CPU和GPU乃至各种异构算力被一视同仁，被纳入统一的编程模型开发，从rocminfo工具的输出可以看到这一点，每一个异构算力被认为是一个agent：

$ sudo /opt/rocm/bin/rocminfo

我的计算平台有两个AGENT，分别是CPU和GPU，CPU是通用算例，有12个compute unit，对应的是6核12线程SMT。

GPU Agent信息，计算单元数量，计算最大的TENSOR维数信息，QUEUE数量，WAVE(Warpper)大小等信息：

opencl支持信息

ROCm不直接支持CUDA，但是 support another GPU programming mode opencl,通过clinfo查看：

/opt/rocm/opencl/bin/clinfo

docker容器运行测试

下载pytorch环境的docker:

sudo docker run -it -v $HOME:/data --privileged --rm --device=/dev/kfd --device=/dev/dri --group-add video --name pytorch rocm/pytorch:latest

之后，在docker终端中执行如下命令，验证对CUDA的支持（猜测是利用CUDA的生态，底层是CUDA转OpenCL的算子实现）：

  1. >>> import torch
  2. >>> torch.cuda.is_available()

输出为TRUE，说明AMDGPU的硬件加速平台搭建成功了。

简单分析

细心的同学可能注意到，在启动docker的测试命令中，传入了一个设备参数--device=/dev/kfd给到DOCKER环境，这个非常重要,kfd本身就是代表AMDGPU异构计算的GPU设备驱动（KMD）的设备节点，它是用户操作GPU的基础。

架构上，AMDKFD驱动程序是Radeon GPU计算软件栈的Linux内核代码，也是该公司ROCm产品的一部分，从 功能上可以理解为在 DRM 子系统中提供了 CPU 与 GPU 沟通的快速通道，使得两者可以平等的访问内存资源而无需额外拷贝。

我们可以在运行上面的测试时，简单追踪以下对KFD内核驱动的调用，以验证加速环境确实使用的AMDGPU显卡，KFD是一个字符设备，所以可以追踪其中的几个FOPS调用，不出所料，在docker中执行如上命令后，内核中则追踪到了如下对KFD的调用栈：

这个例子说明了ROCm穿上了CUDA的外衣，摇身一变实现了对TF框架的支持，但是核心引擎仍然用的是AMDGPU自己的加速实现，包括AMD的编译器，AMD的底层KMD KFD，数学加速库等等实现。

ROCm和CUDA编程模型对比

1.NVIDIA和AMD都支持OpenCL,毕竟CL是个开放标准。

2.OpenACC对标OpenMP,网上有很多例子.

3.HIP对标Cuda,Cuda Source可以翻译为 HIP，然后由ROCm编译为AMDGPU上可运行的代码。

大概意思针对异构计算，深度系学习场景，双方各自都有底牌，目前OpenCL打个平手，HIP和CUDA相比较生态弱一些，OpenACC和OpenMP旗鼓相当。

AMDGPU对CUDA支持方式的分析

以下内容来源于网上的资料和自己不负责任的分析,基于一个原理，计算机中的任何问题都可以通过增加一个中间层来解决:

实现方式是针对hip api（Heterogeneous-Computing Interface for Portability）做CUDA的接口套壳，即将cuda的API接口作为标准接口，用AMD ROCm实现cuda的API（目的就是保证对外的API与CUDA完全相同），但实际调用 HIP+ROCm 的相关接口实现（即实际在A卡上运行），编译生成动态库libcuda*.so，并替换cuda相关动态库，从而完成适配，达到兼容CUDA生态的接口的目的。ROCm也提供了HIPIFY工具，用于将CUDA源代码转换为HIP源代码，实现CUDA代码到HIP的移植。

ROCm API libraries — ROCm Documentation

Hipify工具

HIP是 CUDA API 的”山寨克隆“版。除了一些不常用的功能（e.g. managed memory）外，几乎全盘拷贝 CUDA API，是 CUDA 的一个子集。HIP让开发人员能够使用HIPIFY将CUDA应用程序移植到ROCm，HIPIFY会自动转换CUDA应用程序成为HIP内核语言和运行时API，使用NVIDIA的CUDA编译器或AMDCLANG编译为目标GPU的运行代码。

基于AMDGPU如何运行OpenCL测试用例

参考网络上基于CPU算例的OpenCL的例子，写一个cl的helloworld demo,这个并不太难，因为OpenCL是开源机构Khronos Group定义的标准，在这个标准下所有的头文件，运行时标准等等都是定义好的，所以源码级没有太多改动，基本上拷贝过来就能跑。重点是分析其基于AMDGPU的执行机制。

下面是一份简单的opencl的代码，基本上和C没有什么差别，除了需要提供device端的代码，没有也没有关系，简单的测试用例可以只在主机上跑。

  1. #include <stdio.h>
  2. #include <stdlib.h>
  3. #include <alloca.h>
  4. #include <CL/cl.h>
  5.  
  6. void displayPlatformInfo(cl_platform_id id,
  7.                          cl_platform_info param_name,
  8.                          const char* paramNameAsStr)
  9. {
  10.     cl_int error = 0;
  11.     size_t paramSize = 0;
  12.     error = clGetPlatformInfo( id, param_name, 0, NULL, &paramSize );
  13.     char* moreInfo = (char*)alloca( sizeof(char) * paramSize);
  14.     error = clGetPlatformInfo( id, param_name, paramSize, moreInfo, NULL );
  15.     if (error != CL_SUCCESS ) {
  16.         perror("Unable to find any OpenCL platform information");
  17.         return;
  18.     }
  19.     printf("%s: %s\n", paramNameAsStr, moreInfo);
  20. }
  21.  
  22. int main(void) {
  23.  
  24.    /* OpenCL 1.1 data structures */
  25.    cl_platform_id* platforms;
  26.  
  27.    /* OpenCL 1.1 scalar data types */
  28.    cl_uint numOfPlatforms;
  29.    cl_int  error;
  30.  
  31.    /* 
  32.       Get the number of platforms 
  33.       Remember that for each vendor's SDK installed on the computer,
  34.       the number of available platform also increased. 
  35.     */
  36.    error = clGetPlatformIDs(0, NULL, &numOfPlatforms);
  37.    if(error != CL_SUCCESS) {			
  38.       perror("Unable to find any OpenCL platforms");
  39.       exit(1);
  40.    }
  42.    // Allocate memory for the number of installed platforms.
  43.    // alloca(...) occupies some stack space but is automatically freed on return
  44.    platforms = (cl_platform_id*) alloca(sizeof(cl_platform_id) * numOfPlatforms);
  45.    printf("Number of OpenCL platforms found: %d\n", numOfPlatforms);
  47.    error = clGetPlatformIDs(numOfPlatforms, platforms, NULL);
  48.    if(error != CL_SUCCESS) {			
  49.       perror("Unable to find any OpenCL platforms");
  50.       exit(1);
  51.    }
  52.    // We invoke the API 'clPlatformInfo' twice for each parameter we're trying to extract
  53.    // and we use the return value to create temporary data structures (on the stack) to store
  54.    // the returned information on the second invocation.
  55.    for(cl_uint i = 0; i < numOfPlatforms; ++i) {
  56.         displayPlatformInfo( platforms[i], CL_PLATFORM_PROFILE, "CL_PLATFORM_PROFILE" );
  57.         displayPlatformInfo( platforms[i], CL_PLATFORM_VERSION, "CL_PLATFORM_VERSION" );
  58.         displayPlatformInfo( platforms[i], CL_PLATFORM_NAME,    "CL_PLATFORM_NAME" );
  59.         displayPlatformInfo( platforms[i], CL_PLATFORM_VENDOR,  "CL_PLATFORM_VENDOR" );
  60.         displayPlatformInfo( platforms[i], CL_PLATFORM_EXTENSIONS, "CL_PLATFORM_EXTENSIONS" );
  61.    }
  62.  
  63.    return 0;
  64. }

编译

ROCm环境安装了OpenCL开发所需要的编译器，OpenCL运行时环境，以及标准的Khronos Group头文件，使用如下命令编译：

/opt/rocm/llvm/bin/clang opencl.c -I/opt/rocm/opencl/include -L/opt/rocm/opencl/lib -lOpenCL
编译，运行测试没有问题

strace追踪系统调用，发现opencl的测试用例确实打开了/dev/kfd设备节点，并对GPU进行IOCTL操作：

strace -tt -T -f -e trace=file,close,openat,ioctl -o strace.log ./a.out

这个用例比较简单，调用的IOCTL 列表如下：

开发OpenCL Kernel测试用例

前面的例子只有主机侧的代码，没有GPU运行的代码，实际上没有调用AMDGPU的异构计算能力，参考网上的代码，写一个实现两个一维向量加和的kernel,投到AMDGPU上得到计算结果：

  1. #include <stdio.h>
  2. #include <stdlib.h>
  3. #include <alloca.h>
  4. #include <CL/cl.h>
  5. #pragma warning( disable : 4996 )
  6. int main() {
  7. 	cl_int error;
  8. 	cl_platform_id platforms;
  9.  
  10. 	cl_device_id devices;
  11.  
  12. 	cl_context context;
  13.  
  14. 	FILE *program_handle;
  15. 	size_t program_size;
  16. 	char *program_buffer;
  17. 	cl_program program;
  18.  
  19. 	size_t log_size;
  20. 	char *program_log;
  21.  
  22. 	char kernel_name[] = "createBuffer";
  23. 	cl_kernel kernel;
  24.  
  25. 	cl_command_queue queue;
  26. 	//获取平台
  27. 	error = clGetPlatformIDs(1, &platforms, NULL);
  28. 	if (error != 0) {
  29. 		printf("Get platform failed!");
  30. 		return -1;
  31. 	}
  32. 	//获取设备
  33. 	error = clGetDeviceIDs(platforms, CL_DEVICE_TYPE_GPU, 1, &devices, NULL);
  34. 	if (error != 0) {
  35. 		printf("Get device failed!");
  36. 		return -1;
  37. 	}
  38. 	//创建上下文
  39. 	context = clCreateContext(NULL,1,&devices,NULL,NULL,&error);
  40. 	if (error != 0) {
  41. 		printf("Creat context failed!");
  42. 		return -1;
  43. 	}
  44. 	//创建程序；注意要用"rb"
  45. 	program_handle = fopen("kernel.cl","rb");
  46. 	if (program_handle == NULL) {
  47. 		printf("The kernle can not be opened!");
  48. 		return -1;
  49. 	}
  50. 	fseek(program_handle,0,SEEK_END);
  51. 	program_size = ftell(program_handle);
  52. 	rewind(program_handle);
  53.  
  54. 	program_buffer = (char *)malloc(program_size+1);
  55. 	program_buffer[program_size] = '\0';
  56. 	error=fread(program_buffer,sizeof(char),program_size,program_handle);
  57. 	if (error == 0) {
  58. 		printf("Read kernel failed!");
  59. 		return -1;
  60. 	}
  61. 	fclose(program_handle);
  62. 	program = clCreateProgramWithSource(context,1,(const char **)&program_buffer, 
  63. 	                                     &program_size,&error);
  64. 	if (error < 0) {
  65. 		printf("Couldn't create the program!");
  66. 		return -1;
  67. 	}
  68. 	//编译程序
  69. 	error = clBuildProgram(program,1,&devices,NULL,NULL,NULL);
  70. 	if (error < 0) {
  71. 		//确定日志文件的大小
  72. 		clGetProgramBuildInfo(program,devices,CL_PROGRAM_BUILD_LOG,0,NULL,&log_size);
  73. 		program_log = (char *)malloc(log_size+1);
  74. 		program_log[log_size] = '\0';
  75. 		//读取日志
  76. 		clGetProgramBuildInfo(program, devices, CL_PROGRAM_BUILD_LOG, 
  77. 		                       log_size+1, program_log, NULL);
  78. 		printf("%s\n",program_log);
  79. 		free(program_log);
  80. 		return -1;
  81. 	}
  82. 	free(program_buffer);
  83. 	//创建命令队列
  84. 	queue = clCreateCommandQueue(context, devices, CL_QUEUE_PROFILING_ENABLE, &error);
  85. 	if (error < 0) {
  86. 		printf("Coudn't create the command queue");
  87. 		return -1;
  88. 	}
  89. 	//创建内核
  90. 	kernel = clCreateKernel(program,kernel_name,&error);
  91. 	if (kernel==NULL) {
  92. 		printf("Couldn't create kernel!\n");
  93. 		return -1;
  94. 	}
  95. 	//初始化参数
  96. 	float result[100];
  97. 	float a_in[100];
  98. 	float b_in[100];
  99. 	for (int i = 0; i < 100; i++) {
  100. 		a_in[i] = i;
  101. 		b_in[i] = i*2.0;
  102. 	}
  103. 	//创建缓存对象
  104. 	cl_mem memObject1 = clCreateBuffer(context,CL_MEM_READ_ONLY|CL_MEM_COPY_HOST_PTR,sizeof(float)*100,a_in,&error);
  105. 	if (error < 0) {
  106. 		printf("Creat memObject1 failed!\n");
  107. 		return -1;
  108. 	}
  109. 	cl_mem memObject2 = clCreateBuffer(context, CL_MEM_READ_ONLY | CL_MEM_COPY_HOST_PTR, 
  110. 	                                    sizeof(float) * 100, b_in, &error);
  111. 	if (error < 0) {
  112. 		printf("Creat memObject2 failed!\n");
  113. 		return -1;
  114. 	}
  115. 	cl_mem memObject3 = clCreateBuffer(context, CL_MEM_WRITE_ONLY , 
  116. 	                                       sizeof(float) * 100, NULL, &error);
  117. 	if (error < 0) {
  118. 		printf("Creat memObject3 failed!\n");
  119. 		return -1;
  120. 	}
  121. 	//设置内核参数
  122. 	error = clSetKernelArg(kernel,0,sizeof(cl_mem),&memObject1);
  123. 	error|= clSetKernelArg(kernel, 1, sizeof(cl_mem), &memObject2);
  124. 	error |= clSetKernelArg(kernel, 2, sizeof(cl_mem), &memObject3);
  125. 	if (error != CL_SUCCESS) {
  126. 		printf("Error setting kernel arguments!\n");
  127. 		return -1;
  128. 	}
  129. 	//执行内核
  130. 	size_t globalWorkSize[1] = {100};
  131. 	size_t localWorkSize[1] = {1};
  132. 	error = clEnqueueNDRangeKernel(queue,kernel,1,NULL,globalWorkSize, 
  133. 	                                localWorkSize,0,NULL,NULL);
  134. 	if (error != CL_SUCCESS) {
  135. 		printf("Error queuing kernel for execution!\n");
  136. 		return -1;
  137. 	}
  138. 	//读取执行结果
  139. 	error = clEnqueueReadBuffer(queue,memObject3,CL_TRUE,0,100*sizeof(float), 
  140. 	                             result,0,NULL,NULL);
  141. 	if (error != CL_SUCCESS) {
  142. 		printf("Error reading result buffer!\n");
  143. 		return -1;
  144. 	}
  145. 	//显示结果
  146. 	for (int i = 0; i < 100; i++) {
  147. 		printf("%f ",result[i]);
  148. 	}
  149. 	printf("\n");
  150. 	//释放资源
  151. 	clReleaseDevice(devices);
  152. 	clReleaseContext(context);
  153. 	clReleaseCommandQueue(queue);
  154. 	clReleaseProgram(program);
  155. 	clReleaseKernel(kernel);
  156. 	clReleaseMemObject(memObject1);
  157. 	clReleaseMemObject(memObject2);
  158. 	clReleaseMemObject(memObject3);
  159. 	return 0;
  160. }

设备端代码：

  1. __kernel void createBuffer(__global const float *a_in,
  2. 	__global const float *b_in,
  3. 	__global float *result) {
  4. int gid = get_global_id(0);
  5. result[gid] = a_in[gid] + b_in[gid];
  6. }

编译命令不变，kernel.cl会被主文件读入，然后被ROCm动态编译为GPU端指令，通过ROCm runtime加载道GPU端运行，得到计算结果，计算结果符合预期：

作为驱动开发者，实际上最关心的是KFD端的调用序列，通过追踪可以看到，此时由于加入了设备端计算的功能，KFD的IOCTL调用序列明显比前面长了好多，其中包括了COMMAND QUEUE创建的IOCTL也被调用到，因为设备端代码要通过COMMAND QUEUE传递给AMDGPU去执行。对应此用例，TRACE到的KFD主要调用流程如下：

  1. root@love-A520MS:/sys/kernel/debug/tracing# cat trace
  2. # tracer: function
  3. #
  4. # entries-in-buffer/entries-written: 0/0   #P:12
  5. #
  6. #                                _-----=> irqs-off
  7. #                               / _----=> need-resched
  8. #                              | / _---=> hardirq/softirq
  9. #                              || / _--=> preempt-depth
  10. #                              ||| / _-=> migrate-disable
  11. #                              |||| /     delay
  12. #           TASK-PID     CPU#  |||||  TIMESTAMP  FUNCTION
  13. #              | |         |   |||||     |         |
  14. root@love-A520MS:/sys/kernel/debug/tracing# cat trace
  15. # tracer: function
  16. #
  17. # entries-in-buffer/entries-written: 36/36   #P:12
  18. #
  19. #                                _-----=> irqs-off
  20. #                               / _----=> need-resched
  21. #                              | / _---=> hardirq/softirq
  22. #                              || / _--=> preempt-depth
  23. #                              ||| / _-=> migrate-disable
  24. #                              |||| /     delay
  25. #           TASK-PID     CPU#  |||||  TIMESTAMP  FUNCTION
  26. #              | |         |   |||||     |         |
  27.            a.out-3866    [010] .....  2681.619393: kfd_open <-chrdev_open
  28.            a.out-3866    [010] .....  2681.619397: <stack trace>
  29.  => kfd_open
  30.  => chrdev_open
  31.  => do_dentry_open
  32.  => vfs_open
  33.  => path_openat
  34.  => do_filp_open
  35.  => do_sys_openat2
  36.  => do_sys_open
  37.  => __x64_sys_openat
  38.  => do_syscall_64
  39.  => entry_SYSCALL_64_after_hwframe
  40.            a.out-3866    [010] .....  2681.619472: amdgpu_vm_set_pasid <-amdgpu_driver_open_kms
  41.            a.out-3866    [010] .....  2681.619473: <stack trace>
  42.  => amdgpu_vm_set_pasid
  43.  => amdgpu_driver_open_kms
  44.  => drm_file_alloc
  45.  => drm_open
  46.  => drm_stub_open
  47.  => chrdev_open
  48.  => do_dentry_open
  49.  => vfs_open
  50.  => path_openat
  51.  => do_filp_open
  52.  => do_sys_openat2
  53.  => do_sys_open
  54.  => __x64_sys_openat
  55.  => do_syscall_64
  56.  => entry_SYSCALL_64_after_hwframe
  57.            a.out-3866    [010] .....  2681.619522: amdgpu_vm_set_pasid <-amdgpu_driver_open_kms
  58.            a.out-3866    [010] .....  2681.619523: <stack trace>
  59.  => amdgpu_vm_set_pasid
  60.  => amdgpu_driver_open_kms
  61.  => drm_file_alloc
  62.  => drm_open
  63.  => drm_stub_open
  64.  => chrdev_open
  65.  => do_dentry_open
  66.  => vfs_open
  67.  => path_openat
  68.  => do_filp_open
  69.  => do_sys_openat2
  70.  => do_sys_open
  71.  => __x64_sys_openat
  72.  => do_syscall_64
  73.  => entry_SYSCALL_64_after_hwframe
  74.            a.out-3866    [010] .....  2681.619618: amdgpu_vm_set_pasid <-amdgpu_vm_fini
  75.            a.out-3866    [010] .....  2681.619619: <stack trace>
  76.  => amdgpu_vm_set_pasid
  77.  => amdgpu_vm_fini
  78.  => amdgpu_driver_postclose_kms
  79.  => drm_file_free.part.0
  80.  => drm_close_helper.isra.0
  81.  => drm_release
  82.  => __fput
  83.  => ____fput
  84.  => task_work_run
  85.  => exit_to_user_mode_prepare
  86.  => syscall_exit_to_user_mode
  87.  => do_syscall_64
  88.  => entry_SYSCALL_64_after_hwframe
  89.            a.out-3866    [010] .....  2681.619632: amdgpu_vm_set_pasid <-amdgpu_amdkfd_gpuvm_acquire_process_vm
  90.            a.out-3866    [010] .....  2681.619632: <stack trace>
  91.  => amdgpu_vm_set_pasid
  92.  => amdgpu_amdkfd_gpuvm_acquire_process_vm
  93.  => kfd_process_device_init_vm
  94.  => kfd_ioctl_acquire_vm
  95.  => kfd_ioctl
  96.  => __x64_sys_ioctl
  97.  => do_syscall_64
  98.  => entry_SYSCALL_64_after_hwframe
  99.            a.out-3866    [010] .....  2681.619634: amdgpu_vm_set_pasid <-amdgpu_amdkfd_gpuvm_acquire_process_vm
  100.            a.out-3866    [010] .....  2681.619635: <stack trace>
  101.  => amdgpu_vm_set_pasid
  102.  => amdgpu_amdkfd_gpuvm_acquire_process_vm
  103.  => kfd_process_device_init_vm
  104.  => kfd_ioctl_acquire_vm
  105.  => kfd_ioctl
  106.  => __x64_sys_ioctl
  107.  => do_syscall_64
  108.  => entry_SYSCALL_64_after_hwframe
  109.            a.out-3866    [001] .....  2681.644166: amdgpu_vm_set_pasid <-amdgpu_driver_open_kms
  110.            a.out-3866    [001] .....  2681.644170: <stack trace>
  111.  => amdgpu_vm_set_pasid
  112.  => amdgpu_driver_open_kms
  113.  => drm_file_alloc
  114.  => drm_open
  115.  => drm_stub_open
  116.  => chrdev_open
  117.  => do_dentry_open
  118.  => vfs_open
  119.  => path_openat
  120.  => do_filp_open
  121.  => do_sys_openat2
  122.  => do_sys_open
  123.  => __x64_sys_openat
  124.  => do_syscall_64
  125.  => entry_SYSCALL_64_after_hwframe
  126.            a.out-3866    [001] .....  2681.644827: amdgpu_vm_set_pasid <-amdgpu_vm_fini
  127.            a.out-3866    [001] .....  2681.644829: <stack trace>
  128.  => amdgpu_vm_set_pasid
  129.  => amdgpu_vm_fini
  130.  => amdgpu_driver_postclose_kms
  131.  => drm_file_free.part.0
  132.  => drm_close_helper.isra.0
  133.  => drm_release
  134.  => __fput
  135.  => ____fput
  136.  => task_work_run
  137.  => exit_to_user_mode_prepare
  138.  => syscall_exit_to_user_mode
  139.  => do_syscall_64
  140.  => entry_SYSCALL_64_after_hwframe
  141.            a.out-3869    [006] .....  2681.691350: pqm_create_queue <-kfd_ioctl_create_queue
  142.            a.out-3869    [006] .....  2681.691355: <stack trace>
  143.  => pqm_create_queue
  144.  => kfd_ioctl_create_queue
  145.  => kfd_ioctl
  146.  => __x64_sys_ioctl
  147.  => do_syscall_64
  148.  => entry_SYSCALL_64_after_hwframe
  149.            a.out-3869    [006] .....  2681.691355: register_process <-pqm_create_queue
  150.            a.out-3869    [006] .....  2681.691356: <stack trace>
  151.  => register_process
  152.  => pqm_create_queue
  153.  => kfd_ioctl_create_queue
  154.  => kfd_ioctl
  155.  => __x64_sys_ioctl
  156.  => do_syscall_64
  157.  => entry_SYSCALL_64_after_hwframe
  158.            a.out-3869    [006] .....  2681.691356: update_qpd_v9 <-register_process
  159.            a.out-3869    [006] .....  2681.691357: <stack trace>
  160.  => update_qpd_v9
  161.  => register_process
  162.  => pqm_create_queue
  163.  => kfd_ioctl_create_queue
  164.  => kfd_ioctl
  165.  => __x64_sys_ioctl
  166.  => do_syscall_64
  167.  => entry_SYSCALL_64_after_hwframe
  168.            a.out-3869    [006] .....  2681.692511: pqm_create_queue <-kfd_ioctl_create_queue
  169.            a.out-3869    [006] .....  2681.692513: <stack trace>
  170.  => pqm_create_queue
  171.  => kfd_ioctl_create_queue
  172.  => kfd_ioctl
  173.  => __x64_sys_ioctl
  174.  => do_syscall_64
  175.  => entry_SYSCALL_64_after_hwframe
  176.            a.out-3866    [001] .....  2681.860371: pqm_create_queue <-kfd_ioctl_create_queue
  177.            a.out-3866    [001] .....  2681.860377: <stack trace>
  178.  => pqm_create_queue
  179.  => kfd_ioctl_create_queue
  180.  => kfd_ioctl
  181.  => __x64_sys_ioctl
  182.  => do_syscall_64
  183.  => entry_SYSCALL_64_after_hwframe
  184.            a.out-3866    [001] .....  2681.861108: pqm_create_queue <-kfd_ioctl_create_queue
  185.            a.out-3866    [001] .....  2681.861110: <stack trace>
  186.  => pqm_create_queue
  187.  => kfd_ioctl_create_queue
  188.  => kfd_ioctl
  189.  => __x64_sys_ioctl
  190.  => do_syscall_64
  191.  => entry_SYSCALL_64_after_hwframe
  192.            a.out-3869    [006] .....  2681.861627: pqm_create_queue <-kfd_ioctl_create_queue
  193.            a.out-3869    [006] .....  2681.861630: <stack trace>
  194.  => pqm_create_queue
  195.  => kfd_ioctl_create_queue
  196.  => kfd_ioctl
  197.  => __x64_sys_ioctl
  198.  => do_syscall_64
  199.  => entry_SYSCALL_64_after_hwframe
  200.            a.out-3866    [001] .....  2681.887874: kfd_release <-__fput
  201.            a.out-3866    [001] .....  2681.887882: <stack trace>
  202.  => kfd_release
  203.  => __fput
  204.  => ____fput
  205.  => task_work_run
  206.  => do_exit
  207.  => do_group_exit
  208.  => __x64_sys_exit_group
  209.  => do_syscall_64
  210.  => entry_SYSCALL_64_after_hwframe
  211.      kworker/1:0-3510    [001] .....  2681.888555: amdgpu_vm_set_pasid <-amdgpu_vm_release_compute
  212.      kworker/1:0-3510    [001] .....  2681.888559: <stack trace>
  213.  => amdgpu_vm_set_pasid
  214.  => amdgpu_vm_release_compute
  215.  => amdgpu_amdkfd_gpuvm_release_process_vm
  216.  => kfd_process_destroy_pdds
  217.  => kfd_process_wq_release
  218.  => process_one_work
  219.  => worker_thread
  220.  => kthread
  221.  => ret_from_fork
  222.      kworker/1:0-3510    [001] .....  2681.893914: amdgpu_vm_set_pasid <-amdgpu_vm_fini
  223.      kworker/1:0-3510    [001] .....  2681.893919: <stack trace>
  224.  => amdgpu_vm_set_pasid
  225.  => amdgpu_vm_fini
  226.  => amdgpu_driver_postclose_kms
  227.  => drm_file_free.part.0
  228.  => drm_close_helper.isra.0
  229.  => drm_release
  230.  => __fput
  231.  => delayed_fput
  232.  => process_one_work
  233.  => worker_thread
  234.  => kthread
  235.  => ret_from_fork
  236. root@love-A520MS:/sys/kernel/debug/tracing#

完整的KFD调用序列记录如下，方便以后分析：

  1. 5684  00:08:54.545211 ioctl(5, AMDKFD_IOC_GET_VERSION, 0x7ffe0edc1e00) = 0 <0.000005>
  2. 5684  00:08:54.549152 ioctl(5, AMDKFD_IOC_GET_PROCESS_APERTURES_NEW, 0x7ffe0edc1ab0) = 0 <0.000005>
  3. 5684  00:08:54.549169 ioctl(5, AMDKFD_IOC_ACQUIRE_VM, 0x7ffe0edc1ab0) = 0 <0.000033>
  4. 5684  00:08:54.549262 ioctl(5, AMDKFD_IOC_SET_MEMORY_POLICY, 0x7ffe0edc1ab0) = 0 <0.000004>
  5. 5684  00:08:54.549301 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc1970) = 0 <0.000007>
  6. 5684  00:08:54.549333 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1990) = 0 <0.000091>
  7. 5684  00:08:54.581556 ioctl(5, AMDKFD_IOC_GET_CLOCK_COUNTERS, 0x7ffe0edc1a40) = 0 <0.000006>
  8. 5684  00:08:54.581583 ioctl(5, AMDKFD_IOC_GET_CLOCK_COUNTERS, 0x7ffe0edc1e30) = 0 <0.000004>
  9. 5684  00:08:54.581626 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc1b90) = 0 <0.000012>
  10. 5684  00:08:54.581677 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1c60) = 0 <0.000239>
  11. 5684  00:08:54.581933 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1db0) = 0 <0.000014>
  12. 5684  00:08:54.582012 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc1ad0) = 0 <0.000022>
  13. 5684  00:08:54.582043 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1b00) = 0 <0.000029>
  14. 5684  00:08:54.582084 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1ca0) = 0 <0.000004>
  15. 5684  00:08:54.582259 ioctl(5, AMDKFD_IOC_SET_SCRATCH_BACKING_VA, 0x7ffe0edc1d40) = 0 <0.000002>
  16. 5684  00:08:54.582322 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc1750) = 0 <0.000010>
  17. 5684  00:08:54.582342 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1780) = 0 <0.000031>
  18. 5684  00:08:54.582388 ioctl(5, AMDKFD_IOC_SET_TRAP_HANDLER, 0x7ffe0edc1e10) = 0 <0.000006>
  19. 5687  00:08:54.582511 ioctl(5, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  20. 5684  00:08:54.587645 ioctl(5, AMDKFD_IOC_GET_TILE_CONFIG, 0x7ffe0edc1310) = 0 <0.000005>
  21. 5684  00:08:54.587777 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc19d0) = 0 <0.000153>
  22. 5684  00:08:54.587945 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc19e0) = 0 <0.000246>
  23. 5684  00:08:54.588269 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc19d0) = 0 <0.000146>
  24. 5684  00:08:54.588429 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc19e0) = 0 <0.000035>
  25. 5684  00:08:54.588477 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1be0) = 0 <0.000007>
  26. 5689  00:08:54.650506 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef744e0) = 0 <0.000028>
  27. 5689  00:08:54.650547 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74510) = 0 <0.000222>
  28. 5689  00:08:54.650832 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74490) = 0 <0.000009>
  29. 5689  00:08:54.650851 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef744c0) = 0 <0.000035>
  30. 5689  00:08:54.650897 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74700) = 0 <0.000006>
  31. 5689  00:08:54.650964 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74240) = 0 <0.000008>
  32. 5689  00:08:54.650982 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef742b0) = 0 <0.000034>
  33. 5689  00:08:54.651053 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74200) = 0 <0.000008>
  34. 5689  00:08:54.651090 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef742b0) = 0 <0.000036>
  35. 5689  00:08:54.651186 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74240) = 0 <0.000376>
  36. 5689  00:08:54.651573 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef742b0) = 0 <0.000114>
  37. 5689  00:08:54.651697 ioctl(5, AMDKFD_IOC_CREATE_QUEUE, 0x7fae7ef74420) = 0 <0.000177>
  38. 5689  00:08:54.651914 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef742c0) = 0 <0.000008>
  39. 5689  00:08:54.651945 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74330) = 0 <0.000025>
  40. 5689  00:08:54.651981 ioctl(5, AMDKFD_IOC_SET_EVENT, 0x7fae7ef74710) = 0 <0.000007>
  41. 5689  00:08:54.652000 ioctl(5, AMDKFD_IOC_SET_EVENT, 0x7fae7ef74710) = 0 <0.000006>
  42. 5689  00:08:54.652067 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74510) = 0 <0.000010>
  43. 5689  00:08:54.652086 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74540) = 0 <0.000024>
  44. 5689  00:08:54.652175 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef745f0) = 0 <0.000009>
  45. 5689  00:08:54.652196 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74620) = 0 <0.000028>
  46. 5687  00:08:54.652231 ioctl(5, AMDKFD_IOC_WAIT_EVENTS, 0x7fae7f7e8c20) = 0 <0.000008>
  47. 5687  00:08:54.652251 ioctl(5, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  48. 5689  00:08:54.652295 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef745a0) = 0 <0.000048>
  49. 5689  00:08:54.652353 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef745d0) = 0 <0.000029>
  50. 5689  00:08:54.652446 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74350) = 0 <0.000010>
  51. 5689  00:08:54.652467 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef743c0) = 0 <0.000024>
  52. 5689  00:08:54.652531 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74310) = 0 <0.000008>
  53. 5689  00:08:54.652565 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef743c0) = 0 <0.000030>
  54. 5689  00:08:54.652654 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74350) = 0 <0.000390>
  55. 5689  00:08:54.653057 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef743c0) = 0 <0.000119>
  56. 5689  00:08:54.653190 ioctl(5, AMDKFD_IOC_CREATE_QUEUE, 0x7fae7ef74530) = 0 <0.000068>
  57. 5689  00:08:54.653271 ioctl(5, AMDKFD_IOC_SET_EVENT, 0x7fae7ef74820) = 0 <0.000007>
  58. 5689  00:08:54.653290 ioctl(5, AMDKFD_IOC_SET_EVENT <unfinished ...>
  59. 5689  00:08:54.653366 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74620) = 0 <0.000010>
  60. 5689  00:08:54.653386 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74650) = 0 <0.000025>
  61. 5689  00:08:54.653480 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU <unfinished ...>
  62. 5687  00:08:54.653532 ioctl(5, AMDKFD_IOC_WAIT_EVENTS, 0x7fae7f7e8c20) = 0 <0.000005>
  63. 5687  00:08:54.653551 ioctl(5, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  64. 5689  00:08:54.653590 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74a30) = 0 <0.000025>
  65. 5689  00:08:54.836246 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef73c80) = 0 <0.000022>
  66. 5689  00:08:54.836303 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef73cf0) = 0 <0.000049>
  67. 5689  00:08:54.836417 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef73da0) = 0 <0.000019>
  68. 5689  00:08:54.836447 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef73dd0) = 0 <0.000031>
  69. 5689  00:08:54.836509 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74690) = 0 <0.000007>
  70. 5689  00:08:54.836582 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74590) = 0 <0.000010>
  71. 5689  00:08:54.836603 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef745c0) = 0 <0.000029>
  72. 5689  00:08:54.836696 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74140) = 0 <0.000007>
  73. 5689  00:08:54.836714 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74170) = 0 <0.000023>
  74. 5689  00:08:54.836800 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74140) = 0 <0.000007>
  75. 5689  00:08:54.836818 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74170) = 0 <0.000027>
  76. 5689  00:08:54.837235 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74140) = 0 <0.000018>
  77. 5689  00:08:54.837266 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74170) = 0 <0.000085>
  78. 5689  00:08:54.837497 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74840) = 0 <0.000009>
  79. 5689  00:08:54.837519 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74840) = 0 <0.000025>
  80. 5689  00:08:54.837558 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000007>
  81. 5689  00:08:54.837577 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000005>
  82. 5689  00:08:54.837599 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000007>
  83. 5689  00:08:54.837618 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000004>
  84. 5689  00:08:54.837632 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000004>
  85. 5689  00:08:54.837647 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000004>
  86. 5689  00:08:54.837662 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000004>
  87. 5689  00:08:54.837676 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000004>
  88. 5689  00:08:54.837691 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000004>
  89. 5689  00:08:54.837705 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000008>
  90. 5689  00:08:54.837723 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000004>
  91. 5689  00:08:54.837738 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000004>
  92. 5689  00:08:54.837752 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000004>
  93. 5689  00:08:54.837766 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000004>
  94. 5689  00:08:54.837835 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef748b0) = 0 <0.000011>
  95. 5689  00:08:54.837857 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef748e0) = 0 <0.000080>
  96. 5689  00:08:54.837951 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  97. 5689  00:08:54.837971 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000009>
  98. 5689  00:08:54.837999 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000009>
  99. 5689  00:08:54.838024 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  100. 5689  00:08:54.838046 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  101. 5689  00:08:54.838067 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  102. 5689  00:08:54.838088 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  103. 5689  00:08:54.838109 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  104. 5689  00:08:54.838130 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  105. 5689  00:08:54.838151 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  106. 5689  00:08:54.838172 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  107. 5689  00:08:54.838193 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  108. 5689  00:08:54.838214 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  109. 5689  00:08:54.838236 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  110. 5689  00:08:54.838257 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  111. 5689  00:08:54.838278 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  112. 5689  00:08:54.838299 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  113. 5689  00:08:54.838321 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74b50) = 0 <0.000006>
  114. 5684  00:08:54.838720 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc14a0) = 0 <0.000020>
  115. 5684  00:08:54.838757 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc14d0) = 0 <0.000032>
  116. 5684  00:08:54.838963 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc1840) = 0 <0.000014>
  117. 5684  00:08:54.838994 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1870) = 0 <0.000032>
  118. 5684  00:08:54.839099 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc17f0) = 0 <0.000044>
  119. 5684  00:08:54.839154 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1820) = 0 <0.000024>
  120. 5684  00:08:54.839247 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc15a0) = 0 <0.000008>
  121. 5684  00:08:54.839266 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1610) = 0 <0.000027>
  122. 5684  00:08:54.839331 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc1560) = 0 <0.000007>
  123. 5684  00:08:54.839366 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1610) = 0 <0.000032>
  124. 5684  00:08:54.839457 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc15a0) = 0 <0.000281>
  125. 5684  00:08:54.839754 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1610) = 0 <0.000104>
  126. 5684  00:08:54.839873 ioctl(5, AMDKFD_IOC_CREATE_QUEUE, 0x7ffe0edc1780) = 0 <0.000162>
  127. 5684  00:08:54.840049 ioctl(5, AMDKFD_IOC_SET_EVENT, 0x7ffe0edc1a70) = 0 <0.000006>
  128. 5684  00:08:54.840071 ioctl(5, AMDKFD_IOC_SET_EVENT, 0x7ffe0edc1a70) = 0 <0.000003>
  129. 5684  00:08:54.840148 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc1870) = 0 <0.000010>
  130. 5684  00:08:54.840169 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc18a0) = 0 <0.000032>
  131. 5684  00:08:54.840267 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU <unfinished ...>
  132. 5687  00:08:54.840306 ioctl(5, AMDKFD_IOC_WAIT_EVENTS, 0x7fae7f7e8c20) = 0 <0.000007>
  133. 5687  00:08:54.840324 ioctl(5, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  134. 5684  00:08:54.840351 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1c80) = 0 <0.000033>
  135. 5684  00:08:54.840433 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc1a90) = 0 <0.000007>
  136. 5684  00:08:54.840452 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1a90) = 0 <0.000024>
  137. 5684  00:08:54.840489 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000005>
  138. 5684  00:08:54.840506 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  139. 5684  00:08:54.840520 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  140. 5684  00:08:54.840534 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  141. 5684  00:08:54.840548 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  142. 5684  00:08:54.840562 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  143. 5684  00:08:54.840576 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  144. 5684  00:08:54.840589 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  145. 5684  00:08:54.840603 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  146. 5684  00:08:54.840617 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  147. 5684  00:08:54.840630 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  148. 5684  00:08:54.840644 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  149. 5684  00:08:54.840658 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  150. 5684  00:08:54.840672 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  151. 5684  00:08:54.840686 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  152. 5684  00:08:54.840700 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  153. 5684  00:08:54.840714 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  154. 5684  00:08:54.840728 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  155. 5684  00:08:54.840741 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  156. 5684  00:08:54.840755 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  157. 5684  00:08:54.840769 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  158. 5684  00:08:54.840782 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  159. 5684  00:08:54.840796 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  160. 5684  00:08:54.840810 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  161. 5684  00:08:54.840824 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  162. 5684  00:08:54.840837 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  163. 5684  00:08:54.840854 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  164. 5684  00:08:54.840869 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  165. 5684  00:08:54.840883 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000009>
  166. 5684  00:08:54.840902 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000004>
  167. 5684  00:08:54.840916 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  168. 5684  00:08:54.840930 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1da0) = 0 <0.000003>
  169. 5684  00:08:54.840998 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc19b0) = 0 <0.000130>
  170. 5684  00:08:54.841144 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc19e0) = 0 <0.000119>
  171. 5684  00:08:54.841363 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffe0edc16e0) = 0 <0.000008>
  172. 5684  00:08:54.841382 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffe0edc1750) = 0 <0.000023>
  173. 5684  00:08:54.841416 ioctl(5, AMDKFD_IOC_CREATE_QUEUE, 0x7ffe0edc18c0) = 0 <0.000025>
  174. 5684  00:08:54.841452 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1b60) = 0 <0.000004>
  175. 5684  00:08:54.841466 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7ffe0edc1b60) = 0 <0.000004>
  176. 5689  00:08:54.841551 ioctl(5, AMDKFD_IOC_GET_CLOCK_COUNTERS, 0x7fae7ef748a0) = 0 <0.000007>
  177. 5689  00:08:54.841637 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef745d0) = 0 <0.000150>
  178. 5689  00:08:54.841800 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74600) = 0 <0.000090>
  179. 5689  00:08:54.841996 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef74300) = 0 <0.000010>
  180. 5689  00:08:54.842018 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74370) = 0 <0.000024>
  181. 5689  00:08:54.842054 ioctl(5, AMDKFD_IOC_CREATE_QUEUE, 0x7fae7ef744e0) = 0 <0.000033>
  182. 5689  00:08:54.842099 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74780) = 0 <0.000005>
  183. 5689  00:08:54.842172 ioctl(5, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7fae7ef744e0) = 0 <0.000011>
  184. 5689  00:08:54.842194 ioctl(5, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7fae7ef74510) = 0 <0.000029>
  185. 5689  00:08:54.842235 ioctl(5, AMDKFD_IOC_CREATE_EVENT, 0x7fae7ef74780) = 0 <0.000004>
  186. 5689  00:08:54.842440 ioctl(5, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7fae7ef74c30) = 0 <0.000011>
  187. 5689  00:08:54.842468 ioctl(5, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7fae7ef74c70) = 0 <0.000011>
  188. 5689  00:08:54.842517 ioctl(5, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7fae7ef74bf0) = 0 <0.000006>
  189. 5689  00:08:54.842536 ioctl(5, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7fae7ef74c40) = 0 <0.000010>
  190. 5689  00:08:54.842603 ioctl(5, AMDKFD_IOC_SET_EVENT, 0x7fae7ef74d10) = 0 <0.000006>
  191. 5687  00:08:54.842634 ioctl(5, AMDKFD_IOC_SET_EVENT, 0x7fae7f7e8da0) = 0 <0.000007>
  192. 5689  00:08:54.842654 ioctl(5, AMDKFD_IOC_DESTROY_QUEUE <unfinished ...>
  193. 5687  00:08:54.842660 ioctl(5, AMDKFD_IOC_SET_EVENT, 0x7fae7f7e8df0) = 0 <0.000007>
  194. 5689  00:08:54.842752 ioctl(5, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7fae7ef74c30) = 0 <0.000007>
  195. 5689  00:08:54.842770 ioctl(5, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7fae7ef74c80) = 0 <0.000006>
  196. 5689  00:08:54.842841 ioctl(5, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU <unfinished ...>
  197. 5687  00:08:54.842879 ioctl(5, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  198. 5689  00:08:54.842899 ioctl(5, AMDKFD_IOC_FREE_MEMORY_OF_GPU <unfinished ...>
  199. 5687  00:08:54.842906 ioctl(5, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  200. 5689  00:08:54.843095 ioctl(5, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7fae7ef74c50) = 0 <0.000006>
  201. 5689  00:08:54.843114 ioctl(5, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7fae7ef74ca0) = 0 <0.000007>
  202. 5689  00:08:54.843151 ioctl(5, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7fae7ef74ba0) = 0 <0.000006>
  203. 5689  00:08:54.843167 ioctl(5, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7fae7ef74bf0) = 0 <0.000007>
  204. 5689  00:08:54.843220 ioctl(5, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7fae7ef74bc0) = 0 <0.000006>
  205. 5689  00:08:54.843239 ioctl(5, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7fae7ef74c10) = 0 <0.000006>
  206. 5689  00:08:54.843279 ioctl(5, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7fae7ef74bc0) = 0 <0.000006>
  207. 5689  00:08:54.843295 ioctl(5, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7fae7ef74c10) = 0 <0.000007>
  208. 5684  00:08:54.843339 ioctl(5, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffe0edc1f60) = 0 <0.000007>
  209. 5684  00:08:54.843355 ioctl(5, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffe0edc1fb0) = 0 <0.000008>
runtime arch

OpenMP测试：

进入目录/opt/rocm-5.1.0/llvm/examples/openmp/veccopy，执行如下编译：

/opt/rocm-5.1.0/llvm/bin/clang -O3 -target x86_64-pc-linux-gnu -fopenmp -fopenmp-targets=amdgcn-amd-amdhsa -Xopenmp-target=amdgcn-amd-amdhsa -march=gfx908   veccopy.c -o veccopy

rocm_agent_enumerator用于发现支持AMD HSA的agent设备，测试环境发现了两个agent,分别是CPU和GPU。我们测试使用的是gfx908:

编译提示我们用错了offload arch, 所以可能无法将计算offloading 到device.不过没关系，不影响测试：

测试发现，openmp的计算实际上也是offload到GPU上运行的：

完整的TRACE LOG，日后分析：

  1. 5355  22:34:07.032008 execve("./veccopy", ["./veccopy"], 0x7ffcd9d23a78 /* 33 vars */) = 0 <0.000279>
  2. 5355  22:34:07.032525 access("/etc/ld.so.preload", R_OK) = -1 ENOENT (没有那个文件或目录) <0.000016>
  3. 5355  22:34:07.032710 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/tls/x86_64/x86_64/libomp.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000016>
  4. 5355  22:34:07.032772 stat("/opt/rocm-5.1.0/llvm/bin/../lib/tls/x86_64/x86_64", 0x7ffd164f6e80) = -1 ENOENT (没有那个文件或目录) <0.000024>
  5. 5355  22:34:07.032832 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/tls/x86_64/libomp.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000013>
  6. 5355  22:34:07.032876 stat("/opt/rocm-5.1.0/llvm/bin/../lib/tls/x86_64", 0x7ffd164f6e80) = -1 ENOENT (没有那个文件或目录) <0.000012>
  7. 5355  22:34:07.032917 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/tls/x86_64/libomp.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000012>
  8. 5355  22:34:07.032958 stat("/opt/rocm-5.1.0/llvm/bin/../lib/tls/x86_64", 0x7ffd164f6e80) = -1 ENOENT (没有那个文件或目录) <0.000011>
  9. 5355  22:34:07.032997 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/tls/libomp.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000012>
  10. 5355  22:34:07.033037 stat("/opt/rocm-5.1.0/llvm/bin/../lib/tls", 0x7ffd164f6e80) = -1 ENOENT (没有那个文件或目录) <0.000011>
  11. 5355  22:34:07.033076 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/x86_64/x86_64/libomp.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000012>
  12. 5355  22:34:07.033117 stat("/opt/rocm-5.1.0/llvm/bin/../lib/x86_64/x86_64", 0x7ffd164f6e80) = -1 ENOENT (没有那个文件或目录) <0.000012>
  13. 5355  22:34:07.033156 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/x86_64/libomp.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000013>
  14. 5355  22:34:07.033197 stat("/opt/rocm-5.1.0/llvm/bin/../lib/x86_64", 0x7ffd164f6e80) = -1 ENOENT (没有那个文件或目录) <0.000011>
  15. 5355  22:34:07.033236 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/x86_64/libomp.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000012>
  16. 5355  22:34:07.033276 stat("/opt/rocm-5.1.0/llvm/bin/../lib/x86_64", 0x7ffd164f6e80) = -1 ENOENT (没有那个文件或目录) <0.000011>
  17. 5355  22:34:07.033316 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libomp.so", O_RDONLY|O_CLOEXEC) = 3 <0.000014>
  18. 5355  22:34:07.033584 close(3)          = 0 <0.000012>
  19. 5355  22:34:07.033631 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libomptarget.so", O_RDONLY|O_CLOEXEC) = 3 <0.000015>
  20. 5355  22:34:07.033862 close(3)          = 0 <0.000011>
  21. 5355  22:34:07.033905 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libpthread.so.0", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000014>
  22. 5355  22:34:07.033946 openat(AT_FDCWD, "/etc/ld.so.cache", O_RDONLY|O_CLOEXEC) = 3 <0.000006>
  23. 5355  22:34:07.033984 close(3)          = 0 <0.000004>
  24. 5355  22:34:07.033999 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libpthread.so.0", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  25. 5355  22:34:07.034100 close(3)          = 0 <0.000003>
  26. 5355  22:34:07.034114 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libc.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  27. 5355  22:34:07.034132 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libc.so.6", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  28. 5355  22:34:07.034264 close(3)          = 0 <0.000003>
  29. 5355  22:34:07.034280 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/librt.so.1", O_RDONLY|O_CLOEXEC) = 3 <0.000006>
  30. 5355  22:34:07.034355 close(3)          = 0 <0.000004>
  31. 5355  22:34:07.034370 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libdl.so.2", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  32. 5355  22:34:07.034445 close(3)          = 0 <0.000003>
  33. 5355  22:34:07.034471 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libclang-cpp.so.14git", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  34. 5355  22:34:07.034547 close(3)          = 0 <0.000003>
  35. 5355  22:34:07.034566 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  36. 5355  22:34:07.034586 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/tls/x86_64/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  37. 5355  22:34:07.034602 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../lib/tls/x86_64/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  38. 5355  22:34:07.034616 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/tls/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  39. 5355  22:34:07.034631 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../lib/tls/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  40. 5355  22:34:07.034645 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/tls/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  41. 5355  22:34:07.034660 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../lib/tls/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  42. 5355  22:34:07.034674 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/tls/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  43. 5355  22:34:07.034688 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../lib/tls", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  44. 5355  22:34:07.034702 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/x86_64/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  45. 5355  22:34:07.034716 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../lib/x86_64/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  46. 5355  22:34:07.034730 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  47. 5355  22:34:07.034745 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../lib/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  48. 5355  22:34:07.034759 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  49. 5355  22:34:07.034774 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../lib/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  50. 5355  22:34:07.034788 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  51. 5355  22:34:07.034802 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../lib", {st_mode=S_IFDIR|0755, st_size=16384, ...}) = 0 <0.000004>
  52. 5355  22:34:07.034818 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/tls/x86_64/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000006>
  53. 5355  22:34:07.034835 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/tls/x86_64/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  54. 5355  22:34:07.034849 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/tls/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  55. 5355  22:34:07.034864 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/tls/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  56. 5355  22:34:07.034879 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/tls/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  57. 5355  22:34:07.034893 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/tls/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  58. 5355  22:34:07.034907 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/tls/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  59. 5355  22:34:07.034921 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/tls", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  60. 5355  22:34:07.034935 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/x86_64/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  61. 5355  22:34:07.034952 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/x86_64/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  62. 5355  22:34:07.034967 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  63. 5355  22:34:07.034981 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  64. 5355  22:34:07.034995 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/x86_64/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  65. 5355  22:34:07.035010 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/x86_64", 0x7ffd164f6d80) = -1 ENOENT (没有那个文件或目录) <0.000004>
  66. 5355  22:34:07.035024 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/libm.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  67. 5355  22:34:07.035038 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib", {st_mode=S_IFDIR|0755, st_size=4096, ...}) = 0 <0.000004>
  68. 5355  22:34:07.035055 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libm.so.6", O_RDONLY|O_CLOEXEC) = 3 <0.000006>
  69. 5355  22:34:07.035136 close(3)          = 0 <0.000003>
  70. 5355  22:34:07.035152 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libz.so.1", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  71. 5355  22:34:07.035167 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/libz.so.1", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  72. 5355  22:34:07.035182 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/libz.so.1", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  73. 5355  22:34:07.035197 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libz.so.1", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  74. 5355  22:34:07.035286 close(3)          = 0 <0.000003>
  75. 5355  22:34:07.035299 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libtinfo.so.5", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  76. 5355  22:34:07.035314 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/libtinfo.so.5", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  77. 5355  22:34:07.035329 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/libtinfo.so.5", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  78. 5355  22:34:07.035344 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libtinfo.so.5", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  79. 5355  22:34:07.035428 close(3)          = 0 <0.000003>
  80. 5355  22:34:07.035447 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libstdc++.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000006>
  81. 5355  22:34:07.035466 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/libstdc++.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000006>
  82. 5355  22:34:07.035482 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/libstdc++.so.6", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  83. 5355  22:34:07.035498 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libstdc++.so.6", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  84. 5355  22:34:07.035600 close(3)          = 0 <0.000003>
  85. 5355  22:34:07.035617 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libgcc_s.so.1", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  86. 5355  22:34:07.035632 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/libgcc_s.so.1", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  87. 5355  22:34:07.035647 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/libgcc_s.so.1", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  88. 5355  22:34:07.035663 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libgcc_s.so.1", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  89. 5355  22:34:07.035740 close(3)          = 0 <0.000003>
  90. 5355  22:34:07.042002 openat(AT_FDCWD, "/etc/ld.so.cache", O_RDONLY|O_CLOEXEC) = 3 <0.000010>
  91. 5355  22:34:07.042076 close(3)          = 0 <0.000004>
  92. 5355  22:34:07.042102 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/tls/x86_64/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000006>
  93. 5355  22:34:07.042122 stat("/lib/x86_64-linux-gnu/tls/x86_64/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  94. 5355  22:34:07.042140 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/tls/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  95. 5355  22:34:07.042156 stat("/lib/x86_64-linux-gnu/tls/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  96. 5355  22:34:07.042171 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/tls/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  97. 5355  22:34:07.042187 stat("/lib/x86_64-linux-gnu/tls/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  98. 5355  22:34:07.042202 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/tls/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  99. 5355  22:34:07.042218 stat("/lib/x86_64-linux-gnu/tls", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  100. 5355  22:34:07.042233 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/x86_64/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  101. 5355  22:34:07.042249 stat("/lib/x86_64-linux-gnu/x86_64/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  102. 5355  22:34:07.042264 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  103. 5355  22:34:07.042281 stat("/lib/x86_64-linux-gnu/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  104. 5355  22:34:07.042296 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  105. 5355  22:34:07.042312 stat("/lib/x86_64-linux-gnu/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  106. 5355  22:34:07.042327 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  107. 5355  22:34:07.042343 stat("/lib/x86_64-linux-gnu", {st_mode=S_IFDIR|0755, st_size=69632, ...}) = 0 <0.000004>
  108. 5355  22:34:07.042360 openat(AT_FDCWD, "/usr/lib/x86_64-linux-gnu/tls/x86_64/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  109. 5355  22:34:07.042376 stat("/usr/lib/x86_64-linux-gnu/tls/x86_64/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  110. 5355  22:34:07.042391 openat(AT_FDCWD, "/usr/lib/x86_64-linux-gnu/tls/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  111. 5355  22:34:07.042407 stat("/usr/lib/x86_64-linux-gnu/tls/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  112. 5355  22:34:07.042422 openat(AT_FDCWD, "/usr/lib/x86_64-linux-gnu/tls/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  113. 5355  22:34:07.042438 stat("/usr/lib/x86_64-linux-gnu/tls/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  114. 5355  22:34:07.042453 openat(AT_FDCWD, "/usr/lib/x86_64-linux-gnu/tls/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  115. 5355  22:34:07.042469 stat("/usr/lib/x86_64-linux-gnu/tls", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  116. 5355  22:34:07.042484 openat(AT_FDCWD, "/usr/lib/x86_64-linux-gnu/x86_64/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  117. 5355  22:34:07.042500 stat("/usr/lib/x86_64-linux-gnu/x86_64/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  118. 5355  22:34:07.042515 openat(AT_FDCWD, "/usr/lib/x86_64-linux-gnu/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  119. 5355  22:34:07.042531 stat("/usr/lib/x86_64-linux-gnu/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  120. 5355  22:34:07.042555 openat(AT_FDCWD, "/usr/lib/x86_64-linux-gnu/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  121. 5355  22:34:07.042573 stat("/usr/lib/x86_64-linux-gnu/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  122. 5355  22:34:07.042588 openat(AT_FDCWD, "/usr/lib/x86_64-linux-gnu/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  123. 5355  22:34:07.042604 stat("/usr/lib/x86_64-linux-gnu", {st_mode=S_IFDIR|0755, st_size=69632, ...}) = 0 <0.000004>
  124. 5355  22:34:07.042621 openat(AT_FDCWD, "/lib/tls/x86_64/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  125. 5355  22:34:07.042637 stat("/lib/tls/x86_64/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  126. 5355  22:34:07.042652 openat(AT_FDCWD, "/lib/tls/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  127. 5355  22:34:07.042667 stat("/lib/tls/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  128. 5355  22:34:07.042682 openat(AT_FDCWD, "/lib/tls/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  129. 5355  22:34:07.042698 stat("/lib/tls/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  130. 5355  22:34:07.042713 openat(AT_FDCWD, "/lib/tls/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  131. 5355  22:34:07.042729 stat("/lib/tls", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  132. 5355  22:34:07.042744 openat(AT_FDCWD, "/lib/x86_64/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  133. 5355  22:34:07.042760 stat("/lib/x86_64/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  134. 5355  22:34:07.042774 openat(AT_FDCWD, "/lib/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  135. 5355  22:34:07.042791 stat("/lib/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  136. 5355  22:34:07.042806 openat(AT_FDCWD, "/lib/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  137. 5355  22:34:07.042821 stat("/lib/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  138. 5355  22:34:07.042836 openat(AT_FDCWD, "/lib/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  139. 5355  22:34:07.042851 stat("/lib", {st_mode=S_IFDIR|0755, st_size=4096, ...}) = 0 <0.000004>
  140. 5355  22:34:07.042868 openat(AT_FDCWD, "/usr/lib/tls/x86_64/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  141. 5355  22:34:07.042884 stat("/usr/lib/tls/x86_64/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  142. 5355  22:34:07.042899 openat(AT_FDCWD, "/usr/lib/tls/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  143. 5355  22:34:07.042914 stat("/usr/lib/tls/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  144. 5355  22:34:07.042929 openat(AT_FDCWD, "/usr/lib/tls/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  145. 5355  22:34:07.042944 stat("/usr/lib/tls/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  146. 5355  22:34:07.042959 openat(AT_FDCWD, "/usr/lib/tls/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  147. 5355  22:34:07.042974 stat("/usr/lib/tls", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  148. 5355  22:34:07.042989 openat(AT_FDCWD, "/usr/lib/x86_64/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  149. 5355  22:34:07.043004 stat("/usr/lib/x86_64/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  150. 5355  22:34:07.043019 openat(AT_FDCWD, "/usr/lib/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  151. 5355  22:34:07.043037 stat("/usr/lib/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  152. 5355  22:34:07.043053 openat(AT_FDCWD, "/usr/lib/x86_64/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  153. 5355  22:34:07.043068 stat("/usr/lib/x86_64", 0x7ffd164f72a0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  154. 5355  22:34:07.043083 openat(AT_FDCWD, "/usr/lib/libarcher.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  155. 5355  22:34:07.043099 stat("/usr/lib", {st_mode=S_IFDIR|0755, st_size=4096, ...}) = 0 <0.000004>
  156. 5355  22:34:07.043133 openat(AT_FDCWD, "/etc/ld.so.cache", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  157. 5355  22:34:07.043168 close(3)          = 0 <0.000003>
  158. 5355  22:34:07.043184 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libmemkind.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  159. 5355  22:34:07.043200 openat(AT_FDCWD, "/usr/lib/x86_64-linux-gnu/libmemkind.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  160. 5355  22:34:07.043216 openat(AT_FDCWD, "/lib/libmemkind.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  161. 5355  22:34:07.043231 openat(AT_FDCWD, "/usr/lib/libmemkind.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  162. 5355  22:34:07.043326 statfs("/dev/shm/", {f_type=TMPFS_MAGIC, f_bsize=4096, f_blocks=1966975, f_bfree=1883383, f_bavail=1883383, f_files=1966975, f_ffree=1965794, f_fsid={val=[0, 0]}, f_namelen=255, f_frsize=4096, f_flags=ST_VALID|ST_NOSUID|ST_NODEV}) = 0 <0.000007>
  163. 5355  22:34:07.043364 openat(AT_FDCWD, "/dev/shm/__KMP_REGISTERED_LIB_5355_0", O_RDWR|O_CREAT|O_EXCL|O_NOFOLLOW|O_CLOEXEC, 0666) = 3 <0.000026>
  164. 5355  22:34:07.043456 close(3)          = 0 <0.000005>
  165. 5355  22:34:07.043482 openat(AT_FDCWD, "/sys/devices/system/cpu", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 3 <0.000009>
  166. 5355  22:34:07.043564 close(3)          = 0 <0.000004>
  167. 5355  22:34:07.043655 openat(AT_FDCWD, "/usr/share/locale/zh_CN.UTF-8/libomp.cat", O_RDONLY) = -1 ENOENT (没有那个文件或目录) <0.000006>
  168. 5355  22:34:07.043674 openat(AT_FDCWD, "/usr/share/locale/zh_CN.UTF-8/LC_MESSAGES/libomp.cat", O_RDONLY) = -1 ENOENT (没有那个文件或目录) <0.000005>
  169. 5355  22:34:07.043692 openat(AT_FDCWD, "/usr/share/locale/zh/libomp.cat", O_RDONLY) = -1 ENOENT (没有那个文件或目录) <0.000005>
  170. 5355  22:34:07.043708 openat(AT_FDCWD, "/usr/share/locale/zh/LC_MESSAGES/libomp.cat", O_RDONLY) = -1 ENOENT (没有那个文件或目录) <0.000005>
  171. 5355  22:34:07.044163 stat("/sys/firmware/devicetree/base/ibm,firmware-versions/open-power", 0x7ffd164f7a68) = -1 ENOENT (没有那个文件或目录) <0.000019>
  172. 5355  22:34:07.044215 stat("/sys/firmware/devicetree/base/cpus/ibm,powerpc-cpu-features", 0x7ffd164f7a68) = -1 ENOENT (没有那个文件或目录) <0.000012>
  173. 5355  22:34:07.044256 stat("/sys/firmware/acpi", {st_mode=S_IFDIR|0755, st_size=0, ...}) = 0 <0.000012>
  174. 5355  22:34:07.044300 stat("/sys/module/acpi", {st_mode=S_IFDIR|0755, st_size=0, ...}) = 0 <0.000012>
  175. 5355  22:34:07.044350 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libomptarget.rtl.x86_64.so", O_RDONLY|O_CLOEXEC) = 3 <0.000015>
  176. 5355  22:34:07.044578 close(3)          = 0 <0.000010>
  177. 5355  22:34:07.044620 openat(AT_FDCWD, "/etc/ld.so.cache", O_RDONLY|O_CLOEXEC) = 3 <0.000014>
  178. 5355  22:34:07.044705 close(3)          = 0 <0.000009>
  179. 5355  22:34:07.044746 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libelf.so.1", O_RDONLY|O_CLOEXEC) = 3 <0.000013>
  180. 5355  22:34:07.044940 close(3)          = 0 <0.000010>
  181. 5355  22:34:07.045224 stat("/dev/nvidia0", 0x7ffd164f7a68) = -1 ENOENT (没有那个文件或目录) <0.000006>
  182. 5355  22:34:07.045241 stat("/sys/module/mdio_thunder/initstate", 0x7ffd164f7a68) = -1 ENOENT (没有那个文件或目录) <0.000006>
  183. 5355  22:34:07.045258 stat("fixme.so", 0x7ffd164f7a68) = -1 ENOENT (没有那个文件或目录) <0.000004>
  184. 5355  22:34:07.045273 stat("/dev/kfd", {st_mode=S_IFCHR|0660, st_rdev=makedev(0xea, 0), ...}) = 0 <0.000005>
  185. 5355  22:34:07.045292 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libomptarget.rtl.amdgpu.so", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  186. 5355  22:34:07.045383 close(3)          = 0 <0.000004>
  187. 5355  22:34:07.045403 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libhsa-runtime64.so.1", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000006>
  188. 5355  22:34:07.045421 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/libhsa-runtime64.so.1", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  189. 5355  22:34:07.045439 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/libhsa-runtime64.so.1", O_RDONLY|O_CLOEXEC) = 3 <0.000006>
  190. 5355  22:34:07.045515 close(3)          = 0 <0.000003>
  191. 5355  22:34:07.045535 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  192. 5355  22:34:07.045551 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/tls/x86_64/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  193. 5355  22:34:07.045567 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/tls/x86_64/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  194. 5355  22:34:07.045582 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/tls/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  195. 5355  22:34:07.045597 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/tls/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  196. 5355  22:34:07.045612 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/tls/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  197. 5355  22:34:07.045627 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/tls/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  198. 5355  22:34:07.045641 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/tls/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  199. 5355  22:34:07.045656 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/tls", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  200. 5355  22:34:07.045671 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/x86_64/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  201. 5355  22:34:07.045686 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/x86_64/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  202. 5355  22:34:07.045700 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  203. 5355  22:34:07.045715 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  204. 5355  22:34:07.045730 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  205. 5355  22:34:07.045745 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  206. 5355  22:34:07.045760 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  207. 5355  22:34:07.045774 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  208. 5355  22:34:07.045789 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/tls/x86_64/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  209. 5355  22:34:07.045804 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/tls/x86_64/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  210. 5355  22:34:07.045819 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/tls/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  211. 5355  22:34:07.045837 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/tls/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  212. 5355  22:34:07.045852 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/tls/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  213. 5355  22:34:07.045867 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/tls/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  214. 5355  22:34:07.045881 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/tls/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  215. 5355  22:34:07.045896 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/tls", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  216. 5355  22:34:07.045910 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/x86_64/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  217. 5355  22:34:07.045925 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/x86_64/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  218. 5355  22:34:07.045940 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  219. 5355  22:34:07.045955 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  220. 5355  22:34:07.045969 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  221. 5355  22:34:07.045984 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  222. 5355  22:34:07.045999 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  223. 5355  22:34:07.046014 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../../lib64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  224. 5355  22:34:07.046028 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/tls/x86_64/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  225. 5355  22:34:07.046043 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/tls/x86_64/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  226. 5355  22:34:07.046058 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/tls/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  227. 5355  22:34:07.046073 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/tls/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  228. 5355  22:34:07.046087 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/tls/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  229. 5355  22:34:07.046102 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/tls/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  230. 5355  22:34:07.046117 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/tls/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  231. 5355  22:34:07.046132 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/tls", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  232. 5355  22:34:07.046146 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/x86_64/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  233. 5355  22:34:07.046161 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/x86_64/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  234. 5355  22:34:07.046179 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  235. 5355  22:34:07.046195 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  236. 5355  22:34:07.046210 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/x86_64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  237. 5355  22:34:07.046225 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/x86_64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  238. 5355  22:34:07.046239 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64/libdrm.so.2", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000004>
  239. 5355  22:34:07.046254 stat("/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/../lib64", 0x7ffd164f68b0) = -1 ENOENT (没有那个文件或目录) <0.000004>
  240. 5355  22:34:07.046268 openat(AT_FDCWD, "/etc/ld.so.cache", O_RDONLY|O_CLOEXEC) = 3 <0.000004>
  241. 5355  22:34:07.046300 close(3)          = 0 <0.000003>
  242. 5355  22:34:07.046316 openat(AT_FDCWD, "/opt/amdgpu/lib/x86_64-linux-gnu/libdrm.so.2", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  243. 5355  22:34:07.046394 close(3)          = 0 <0.000003>
  244. 5355  22:34:07.046409 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/libdrm_amdgpu.so.1", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  245. 5355  22:34:07.046426 openat(AT_FDCWD, "/opt/amdgpu/lib/x86_64-linux-gnu/libdrm_amdgpu.so.1", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  246. 5355  22:34:07.046498 close(3)          = 0 <0.000003>
  247. 5355  22:34:07.046513 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/libnuma.so.1", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000005>
  248. 5355  22:34:07.046530 openat(AT_FDCWD, "/lib/x86_64-linux-gnu/libnuma.so.1", O_RDONLY|O_CLOEXEC) = 3 <0.000005>
  249. 5355  22:34:07.046612 close(3)          = 0 <0.000003>
  250. 5355  22:34:07.046927 openat(AT_FDCWD, "/proc/self/status", O_RDONLY) = 3 <0.000013>
  251. 5355  22:34:07.046995 close(3)          = 0 <0.000005>
  252. 5355  22:34:07.047011 openat(AT_FDCWD, "/sys/devices/system/node", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 3 <0.000006>
  253. 5355  22:34:07.047051 openat(AT_FDCWD, "/sys/devices/system/node/node0/meminfo", O_RDONLY) = 4 <0.000007>
  254. 5355  22:34:07.047106 close(4)          = 0 <0.000004>
  255. 5355  22:34:07.047129 close(3)          = 0 <0.000004>
  256. 5355  22:34:07.047151 openat(AT_FDCWD, "/sys/devices/system/cpu", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 3 <0.000005>
  257. 5355  22:34:07.047193 close(3)          = 0 <0.000003>
  258. 5355  22:34:07.047206 openat(AT_FDCWD, "/proc/self/status", O_RDONLY) = 3 <0.000007>
  259. 5355  22:34:07.047267 close(3)          = 0 <0.000004>
  260. 5355  22:34:07.057387 openat(AT_FDCWD, "/dev/kfd", O_RDWR|O_CLOEXEC) = 3 <0.001855>
  261. 5355  22:34:07.059272 ioctl(3, AMDKFD_IOC_GET_VERSION, 0x7ffd164f7190) = 0 <0.000008>
  262. 5355  22:34:07.059301 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/system_properties", O_RDONLY) = 4 <0.000014>
  263. 5355  22:34:07.059417 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 5 <0.000015>
  264. 5355  22:34:07.059544 close(5)          = 0 <0.000006>
  265. 5355  22:34:07.059571 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/0/gpu_id", O_RDONLY) = 5 <0.000011>
  266. 5355  22:34:07.059631 close(5)          = 0 <0.000007>
  267. 5355  22:34:07.059655 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/gpu_id", O_RDONLY) = 5 <0.000009>
  268. 5355  22:34:07.059704 close(5)          = 0 <0.000006>
  269. 5355  22:34:07.059726 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/properties", O_RDONLY) = 5 <0.000009>
  270. 5355  22:34:07.059800 openat(AT_FDCWD, "/dev/dri/renderD128", O_RDWR|O_CLOEXEC) = 6 <0.000026>
  271. 5355  22:34:07.059847 close(5)          = 0 <0.000006>
  272. 5355  22:34:07.059870 close(4)          = 0 <0.000006>
  273. 5355  22:34:07.059893 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/0/gpu_id", O_RDONLY) = 4 <0.000010>
  274. 5355  22:34:07.059953 close(4)          = 0 <0.000006>
  275. 5355  22:34:07.059975 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/0/properties", O_RDONLY) = 4 <0.000006>
  276. 5355  22:34:07.060028 close(4)          = 0 <0.000004>
  277. 5355  22:34:07.060042 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/gpu_id", O_RDONLY) = 4 <0.000009>
  278. 5355  22:34:07.060085 close(4)          = 0 <0.000005>
  279. 5355  22:34:07.060100 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/properties", O_RDONLY) = 4 <0.000005>
  280. 5355  22:34:07.060157 openat(AT_FDCWD, "/dev/dri/renderD128", O_RDWR|O_CLOEXEC) = 5 <0.000013>
  281. 5355  22:34:07.060199 stat("/sys/dev/char/226:128/device/drm", {st_mode=S_IFDIR|0755, st_size=0, ...}) = 0 <0.000012>
  282. 5355  22:34:07.060227 ioctl(5, DRM_IOCTL_VERSION, 0x1122ce0) = 0 <0.000004>
  283. 5355  22:34:07.060242 ioctl(5, DRM_IOCTL_VERSION, 0x1122ce0) = 0 <0.000004>
  284. 5355  22:34:07.060264 ioctl(7, DRM_IOCTL_AMDGPU_INFO or DRM_IOCTL_SIS_FB_FREE, 0x7ffd164f6a50) = 0 <0.000004>
  285. 5355  22:34:07.060279 ioctl(7, DRM_IOCTL_AMDGPU_INFO or DRM_IOCTL_SIS_FB_FREE, 0x7ffd164f6a20) = 0 <0.000030>
  286. 5355  22:34:07.060319 ioctl(7, DRM_IOCTL_AMDGPU_INFO or DRM_IOCTL_SIS_FB_FREE, 0x7ffd164f6a20) = 0 <0.000038>
  287. 5355  22:34:07.060369 openat(AT_FDCWD, "/opt/amdgpu/share/libdrm/amdgpu.ids", O_RDONLY) = 8 <0.000006>
  288. 5355  22:34:07.060445 close(8)          = 0 <0.000004>
  289. 5355  22:34:07.060459 close(7)          = 0 <0.000009>
  290. 5355  22:34:07.060502 close(5)          = 0 <0.000015>
  291. 5355  22:34:07.060527 close(4)          = 0 <0.000004>
  292. 5355  22:34:07.060541 ioctl(3, AMDKFD_IOC_GET_PROCESS_APERTURES_NEW, 0x7ffd164f6e40) = 0 <0.000004>
  293. 5355  22:34:07.060555 ioctl(3, AMDKFD_IOC_ACQUIRE_VM, 0x7ffd164f6e40) = 0 <0.000033>
  294. 5355  22:34:07.060645 ioctl(3, AMDKFD_IOC_SET_MEMORY_POLICY, 0x7ffd164f6e40) = 0 <0.000004>
  295. 5355  22:34:07.060683 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d00) = 0 <0.000007>
  296. 5355  22:34:07.060717 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6d20) = 0 <0.000224>
  297. 5355  22:34:07.060955 openat(AT_FDCWD, "/sys/bus/event_source/devices/amd_iommu_0/events", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = -1 ENOENT (没有那个文件或目录) <0.000010>
  298. 5355  22:34:07.060979 openat(AT_FDCWD, "/sys/bus/event_source/devices/amd_iommu/events", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = -1 ENOENT (没有那个文件或目录) <0.000006>
  299. 5355  22:34:07.061002 openat(AT_FDCWD, "/dev/shm/sem.hsakmt_semaphore", O_RDWR|O_NOFOLLOW) = 4 <0.000006>
  300. 5355  22:34:07.061040 close(4)          = 0 <0.000004>
  301. 5355  22:34:07.061054 openat(AT_FDCWD, "/dev/shm/hsakmt_shared_mem", O_RDWR|O_CREAT|O_NOFOLLOW|O_CLOEXEC, 0666) = 4 <0.000005>
  302. 5355  22:34:07.061100 ioctl(3, _IOC(_IOC_READ|_IOC_WRITE, 0x4b, 0x82, 0x28), 0x7ffd164f7130) = 0 <0.000004>
  303. 5355  22:34:07.061123 ioctl(3, _IOC(_IOC_READ|_IOC_WRITE, 0x4b, 0x82, 0x28), 0x7ffd164f71a0) = 0 <0.000005>
  304. 5355  22:34:07.061141 openat(AT_FDCWD, "/sys/devices/system/cpu/online", O_RDONLY|O_CLOEXEC) = 5 <0.000006>
  305. 5355  22:34:07.061169 close(5)          = 0 <0.000004>
  306. 5355  22:34:07.061183 openat(AT_FDCWD, "/proc/cpuinfo", O_RDONLY) = 5 <0.018582>
  307. 5355  22:34:07.080934 close(5)          = 0 <0.000015>
  308. 5355  22:34:07.081007 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/generation_id", O_RDONLY) = 5 <0.000037>
  309. 5355  22:34:07.081143 close(5)          = 0 <0.000014>
  310. 5355  22:34:07.081182 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/system_properties", O_RDONLY) = 5 <0.000017>
  311. 5355  22:34:07.081298 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000015>
  312. 5355  22:34:07.081415 close(7)          = 0 <0.000011>
  313. 5355  22:34:07.081454 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/0/gpu_id", O_RDONLY) = 7 <0.000018>
  314. 5355  22:34:07.081544 close(7)          = 0 <0.000011>
  315. 5355  22:34:07.081579 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/gpu_id", O_RDONLY) = 7 <0.000017>
  316. 5355  22:34:07.081665 close(7)          = 0 <0.000011>
  317. 5355  22:34:07.081714 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/properties", O_RDONLY) = 7 <0.000016>
  318. 5355  22:34:07.081846 close(7)          = 0 <0.000011>
  319. 5355  22:34:07.081880 close(5)          = 0 <0.000011>
  320. 5355  22:34:07.081916 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/0/gpu_id", O_RDONLY) = 5 <0.000015>
  321. 5355  22:34:07.081997 close(5)          = 0 <0.000010>
  322. 5355  22:34:07.082032 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/0/properties", O_RDONLY) = 5 <0.000015>
  323. 5355  22:34:07.082163 close(5)          = 0 <0.000011>
  324. 5355  22:34:07.082199 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/0/mem_banks/0/properties", O_RDONLY) = 5 <0.000017>
  325. 5355  22:34:07.082307 close(5)          = 0 <0.000011>
  326. 5355  22:34:07.082344 openat(AT_FDCWD, "/sys/devices/system/node/node0", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 5 <0.000015>
  327. 5355  22:34:07.082506 close(5)          = 0 <0.000010>
  328. 5355  22:34:07.082539 openat(AT_FDCWD, "/sys/devices/system/node/node0", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 5 <0.000013>
  329. 5355  22:34:07.082641 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu11/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000018>
  330. 5355  22:34:07.082749 close(7)          = 0 <0.000010>
  331. 5355  22:34:07.082786 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu11/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000019>
  332. 5355  22:34:07.082874 close(7)          = 0 <0.000012>
  333. 5355  22:34:07.082910 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu11/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000018>
  334. 5355  22:34:07.082996 close(7)          = 0 <0.000010>
  335. 5355  22:34:07.083030 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu11/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000018>
  336. 5355  22:34:07.083115 close(7)          = 0 <0.000010>
  337. 5355  22:34:07.083149 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu11/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  338. 5355  22:34:07.083233 close(7)          = 0 <0.000011>
  339. 5355  22:34:07.083267 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu9/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000017>
  340. 5355  22:34:07.083374 close(7)          = 0 <0.000015>
  341. 5355  22:34:07.083427 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu9/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000018>
  342. 5355  22:34:07.083517 close(7)          = 0 <0.000011>
  343. 5355  22:34:07.083552 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu9/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  344. 5355  22:34:07.083636 close(7)          = 0 <0.000011>
  345. 5355  22:34:07.083670 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu9/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  346. 5355  22:34:07.083775 close(7)          = 0 <0.000021>
  347. 5355  22:34:07.083824 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu9/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  348. 5355  22:34:07.083908 close(7)          = 0 <0.000011>
  349. 5355  22:34:07.083944 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu7/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000016>
  350. 5355  22:34:07.084048 close(7)          = 0 <0.000011>
  351. 5355  22:34:07.084085 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu7/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  352. 5355  22:34:07.084171 close(7)          = 0 <0.000010>
  353. 5355  22:34:07.084206 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu7/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000018>
  354. 5355  22:34:07.084290 close(7)          = 0 <0.000011>
  355. 5355  22:34:07.084325 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu7/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  356. 5355  22:34:07.084408 close(7)          = 0 <0.000010>
  357. 5355  22:34:07.084442 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu7/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  358. 5355  22:34:07.084526 close(7)          = 0 <0.000011>
  359. 5355  22:34:07.084561 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000016>
  360. 5355  22:34:07.084673 close(7)          = 0 <0.000011>
  361. 5355  22:34:07.084712 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  362. 5355  22:34:07.084796 close(7)          = 0 <0.000011>
  363. 5355  22:34:07.084831 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index0/level", O_RDONLY) = 7 <0.000018>
  364. 5355  22:34:07.084917 close(7)          = 0 <0.000011>
  365. 5355  22:34:07.084953 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index0/type", O_RDONLY) = 7 <0.000016>
  366. 5355  22:34:07.085035 close(7)          = 0 <0.000011>
  367. 5355  22:34:07.085070 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index0/size", O_RDONLY) = 7 <0.000016>
  368. 5355  22:34:07.085154 close(7)          = 0 <0.000011>
  369. 5355  22:34:07.085189 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index0/coherency_line_size", O_RDONLY) = 7 <0.000018>
  370. 5355  22:34:07.085648 close(7)          = 0 <0.000035>
  371. 5355  22:34:07.085723 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index0/ways_of_associativity", O_RDONLY) = 7 <0.000031>
  372. 5355  22:34:07.085824 close(7)          = 0 <0.000011>
  373. 5355  22:34:07.085860 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index0/physical_line_partition", O_RDONLY) = 7 <0.000018>
  374. 5355  22:34:07.085946 close(7)          = 0 <0.000011>
  375. 5355  22:34:07.085981 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index0/shared_cpu_map", O_RDONLY) = 7 <0.000017>
  376. 5355  22:34:07.086068 close(7)          = 0 <0.000010>
  377. 5355  22:34:07.086104 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  378. 5355  22:34:07.086190 close(7)          = 0 <0.000010>
  379. 5355  22:34:07.086223 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index1/level", O_RDONLY) = 7 <0.000017>
  380. 5355  22:34:07.086309 close(7)          = 0 <0.000011>
  381. 5355  22:34:07.086343 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index1/type", O_RDONLY) = 7 <0.000017>
  382. 5355  22:34:07.086428 close(7)          = 0 <0.000010>
  383. 5355  22:34:07.086462 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index1/size", O_RDONLY) = 7 <0.000016>
  384. 5355  22:34:07.086547 close(7)          = 0 <0.000010>
  385. 5355  22:34:07.086580 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index1/coherency_line_size", O_RDONLY) = 7 <0.000016>
  386. 5355  22:34:07.086663 close(7)          = 0 <0.000010>
  387. 5355  22:34:07.086698 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index1/ways_of_associativity", O_RDONLY) = 7 <0.000017>
  388. 5355  22:34:07.086782 close(7)          = 0 <0.000010>
  389. 5355  22:34:07.086816 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index1/physical_line_partition", O_RDONLY) = 7 <0.000017>
  390. 5355  22:34:07.086899 close(7)          = 0 <0.000010>
  391. 5355  22:34:07.086933 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index1/shared_cpu_map", O_RDONLY) = 7 <0.000016>
  392. 5355  22:34:07.087017 close(7)          = 0 <0.000010>
  393. 5355  22:34:07.087052 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  394. 5355  22:34:07.087136 close(7)          = 0 <0.000010>
  395. 5355  22:34:07.087169 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index2/level", O_RDONLY) = 7 <0.000016>
  396. 5355  22:34:07.087253 close(7)          = 0 <0.000010>
  397. 5355  22:34:07.087286 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index2/type", O_RDONLY) = 7 <0.000017>
  398. 5355  22:34:07.087371 close(7)          = 0 <0.000026>
  399. 5355  22:34:07.087436 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index2/size", O_RDONLY) = 7 <0.000025>
  400. 5355  22:34:07.087551 close(7)          = 0 <0.000010>
  401. 5355  22:34:07.087585 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index2/coherency_line_size", O_RDONLY) = 7 <0.000017>
  402. 5355  22:34:07.087668 close(7)          = 0 <0.000011>
  403. 5355  22:34:07.087702 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index2/ways_of_associativity", O_RDONLY) = 7 <0.000016>
  404. 5355  22:34:07.087784 close(7)          = 0 <0.000011>
  405. 5355  22:34:07.087827 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index2/physical_line_partition", O_RDONLY) = 7 <0.000016>
  406. 5355  22:34:07.087913 close(7)          = 0 <0.000010>
  407. 5355  22:34:07.087947 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index2/shared_cpu_map", O_RDONLY) = 7 <0.000016>
  408. 5355  22:34:07.088031 close(7)          = 0 <0.000011>
  409. 5355  22:34:07.088066 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu5/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  410. 5355  22:34:07.088149 close(7)          = 0 <0.000010>
  411. 5355  22:34:07.088185 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000017>
  412. 5355  22:34:07.088299 close(7)          = 0 <0.000011>
  413. 5355  22:34:07.088339 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000018>
  414. 5355  22:34:07.088427 close(7)          = 0 <0.000011>
  415. 5355  22:34:07.088463 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index0/level", O_RDONLY) = 7 <0.000017>
  416. 5355  22:34:07.088546 close(7)          = 0 <0.000010>
  417. 5355  22:34:07.088580 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index0/type", O_RDONLY) = 7 <0.000017>
  418. 5355  22:34:07.088664 close(7)          = 0 <0.000011>
  419. 5355  22:34:07.088699 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index0/size", O_RDONLY) = 7 <0.000018>
  420. 5355  22:34:07.088784 close(7)          = 0 <0.000011>
  421. 5355  22:34:07.088819 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index0/coherency_line_size", O_RDONLY) = 7 <0.000016>
  422. 5355  22:34:07.088901 close(7)          = 0 <0.000010>
  423. 5355  22:34:07.088936 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index0/ways_of_associativity", O_RDONLY) = 7 <0.000016>
  424. 5355  22:34:07.089019 close(7)          = 0 <0.000010>
  425. 5355  22:34:07.089053 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index0/physical_line_partition", O_RDONLY) = 7 <0.000016>
  426. 5355  22:34:07.089134 close(7)          = 0 <0.000010>
  427. 5355  22:34:07.089168 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index0/shared_cpu_map", O_RDONLY) = 7 <0.000016>
  428. 5355  22:34:07.089252 close(7)          = 0 <0.000010>
  429. 5355  22:34:07.089286 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000018>
  430. 5355  22:34:07.089386 close(7)          = 0 <0.000015>
  431. 5355  22:34:07.089427 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index1/level", O_RDONLY) = 7 <0.000017>
  432. 5355  22:34:07.089511 close(7)          = 0 <0.000010>
  433. 5355  22:34:07.089545 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index1/type", O_RDONLY) = 7 <0.000016>
  434. 5355  22:34:07.089628 close(7)          = 0 <0.000011>
  435. 5355  22:34:07.089662 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index1/size", O_RDONLY) = 7 <0.000016>
  436. 5355  22:34:07.089748 close(7)          = 0 <0.000011>
  437. 5355  22:34:07.089782 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index1/coherency_line_size", O_RDONLY) = 7 <0.000017>
  438. 5355  22:34:07.089865 close(7)          = 0 <0.000010>
  439. 5355  22:34:07.089899 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index1/ways_of_associativity", O_RDONLY) = 7 <0.000016>
  440. 5355  22:34:07.089983 close(7)          = 0 <0.000010>
  441. 5355  22:34:07.090017 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index1/physical_line_partition", O_RDONLY) = 7 <0.000017>
  442. 5355  22:34:07.090100 close(7)          = 0 <0.000010>
  443. 5355  22:34:07.090134 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index1/shared_cpu_map", O_RDONLY) = 7 <0.000016>
  444. 5355  22:34:07.090218 close(7)          = 0 <0.000010>
  445. 5355  22:34:07.090252 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000017>
  446. 5355  22:34:07.090336 close(7)          = 0 <0.000010>
  447. 5355  22:34:07.090369 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index2/level", O_RDONLY) = 7 <0.000016>
  448. 5355  22:34:07.090451 close(7)          = 0 <0.000018>
  449. 5355  22:34:07.090498 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index2/type", O_RDONLY) = 7 <0.000016>
  450. 5355  22:34:07.090585 close(7)          = 0 <0.000011>
  451. 5355  22:34:07.090619 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index2/size", O_RDONLY) = 7 <0.000017>
  452. 5355  22:34:07.090703 close(7)          = 0 <0.000010>
  453. 5355  22:34:07.090737 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index2/coherency_line_size", O_RDONLY) = 7 <0.000016>
  454. 5355  22:34:07.090819 close(7)          = 0 <0.000011>
  455. 5355  22:34:07.090854 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index2/ways_of_associativity", O_RDONLY) = 7 <0.000018>
  456. 5355  22:34:07.090938 close(7)          = 0 <0.000010>
  457. 5355  22:34:07.090972 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index2/physical_line_partition", O_RDONLY) = 7 <0.000016>
  458. 5355  22:34:07.091057 close(7)          = 0 <0.000010>
  459. 5355  22:34:07.091089 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index2/shared_cpu_map", O_RDONLY) = 7 <0.000007>
  460. 5355  22:34:07.091127 close(7)          = 0 <0.000004>
  461. 5355  22:34:07.091140 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu3/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  462. 5355  22:34:07.091173 close(7)          = 0 <0.000004>
  463. 5355  22:34:07.091186 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000007>
  464. 5355  22:34:07.091227 close(7)          = 0 <0.000004>
  465. 5355  22:34:07.091241 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000007>
  466. 5355  22:34:07.091275 close(7)          = 0 <0.000004>
  467. 5355  22:34:07.091289 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index0/level", O_RDONLY) = 7 <0.000006>
  468. 5355  22:34:07.091321 close(7)          = 0 <0.000004>
  469. 5355  22:34:07.091334 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index0/type", O_RDONLY) = 7 <0.000006>
  470. 5355  22:34:07.091366 close(7)          = 0 <0.000003>
  471. 5355  22:34:07.091381 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index0/size", O_RDONLY) = 7 <0.000007>
  472. 5355  22:34:07.091425 close(7)          = 0 <0.000004>
  473. 5355  22:34:07.091438 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index0/coherency_line_size", O_RDONLY) = 7 <0.000006>
  474. 5355  22:34:07.091471 close(7)          = 0 <0.000003>
  475. 5355  22:34:07.091483 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index0/ways_of_associativity", O_RDONLY) = 7 <0.000006>
  476. 5355  22:34:07.091515 close(7)          = 0 <0.000004>
  477. 5355  22:34:07.091528 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index0/physical_line_partition", O_RDONLY) = 7 <0.000006>
  478. 5355  22:34:07.091560 close(7)          = 0 <0.000003>
  479. 5355  22:34:07.091572 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index0/shared_cpu_map", O_RDONLY) = 7 <0.000007>
  480. 5355  22:34:07.091605 close(7)          = 0 <0.000003>
  481. 5355  22:34:07.091618 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  482. 5355  22:34:07.091650 close(7)          = 0 <0.000004>
  483. 5355  22:34:07.091663 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index1/level", O_RDONLY) = 7 <0.000006>
  484. 5355  22:34:07.091694 close(7)          = 0 <0.000003>
  485. 5355  22:34:07.091706 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index1/type", O_RDONLY) = 7 <0.000006>
  486. 5355  22:34:07.091738 close(7)          = 0 <0.000003>
  487. 5355  22:34:07.091751 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index1/size", O_RDONLY) = 7 <0.000006>
  488. 5355  22:34:07.091783 close(7)          = 0 <0.000003>
  489. 5355  22:34:07.091795 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index1/coherency_line_size", O_RDONLY) = 7 <0.000006>
  490. 5355  22:34:07.091827 close(7)          = 0 <0.000003>
  491. 5355  22:34:07.091840 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index1/ways_of_associativity", O_RDONLY) = 7 <0.000006>
  492. 5355  22:34:07.091871 close(7)          = 0 <0.000004>
  493. 5355  22:34:07.091886 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index1/physical_line_partition", O_RDONLY) = 7 <0.000006>
  494. 5355  22:34:07.091918 close(7)          = 0 <0.000004>
  495. 5355  22:34:07.091931 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index1/shared_cpu_map", O_RDONLY) = 7 <0.000006>
  496. 5355  22:34:07.091963 close(7)          = 0 <0.000004>
  497. 5355  22:34:07.091976 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000007>
  498. 5355  22:34:07.092008 close(7)          = 0 <0.000004>
  499. 5355  22:34:07.092022 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index2/level", O_RDONLY) = 7 <0.000006>
  500. 5355  22:34:07.092053 close(7)          = 0 <0.000003>
  501. 5355  22:34:07.092065 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index2/type", O_RDONLY) = 7 <0.000006>
  502. 5355  22:34:07.092098 close(7)          = 0 <0.000004>
  503. 5355  22:34:07.092110 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index2/size", O_RDONLY) = 7 <0.000007>
  504. 5355  22:34:07.092143 close(7)          = 0 <0.000004>
  505. 5355  22:34:07.092155 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index2/coherency_line_size", O_RDONLY) = 7 <0.000006>
  506. 5355  22:34:07.092187 close(7)          = 0 <0.000004>
  507. 5355  22:34:07.092200 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index2/ways_of_associativity", O_RDONLY) = 7 <0.000006>
  508. 5355  22:34:07.092231 close(7)          = 0 <0.000003>
  509. 5355  22:34:07.092244 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index2/physical_line_partition", O_RDONLY) = 7 <0.000006>
  510. 5355  22:34:07.092276 close(7)          = 0 <0.000003>
  511. 5355  22:34:07.092288 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index2/shared_cpu_map", O_RDONLY) = 7 <0.000006>
  512. 5355  22:34:07.092320 close(7)          = 0 <0.000003>
  513. 5355  22:34:07.092333 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu1/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  514. 5355  22:34:07.092366 close(7)          = 0 <0.000003>
  515. 5355  22:34:07.092378 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu10/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000007>
  516. 5355  22:34:07.092420 close(7)          = 0 <0.000003>
  517. 5355  22:34:07.092434 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu10/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000007>
  518. 5355  22:34:07.092467 close(7)          = 0 <0.000004>
  519. 5355  22:34:07.092479 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu10/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000007>
  520. 5355  22:34:07.092513 close(7)          = 0 <0.000004>
  521. 5355  22:34:07.092526 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu10/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000007>
  522. 5355  22:34:07.092562 close(7)          = 0 <0.000004>
  523. 5355  22:34:07.092576 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu10/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000007>
  524. 5355  22:34:07.092608 close(7)          = 0 <0.000004>
  525. 5355  22:34:07.092621 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu8/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000007>
  526. 5355  22:34:07.092663 close(7)          = 0 <0.000003>
  527. 5355  22:34:07.092676 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu8/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  528. 5355  22:34:07.092709 close(7)          = 0 <0.000004>
  529. 5355  22:34:07.092721 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu8/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000007>
  530. 5355  22:34:07.092754 close(7)          = 0 <0.000004>
  531. 5355  22:34:07.092766 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu8/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  532. 5355  22:34:07.092798 close(7)          = 0 <0.000003>
  533. 5355  22:34:07.092811 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu8/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000007>
  534. 5355  22:34:07.092845 close(7)          = 0 <0.000004>
  535. 5355  22:34:07.092858 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu6/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000006>
  536. 5355  22:34:07.092901 close(7)          = 0 <0.000003>
  537. 5355  22:34:07.092914 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu6/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000007>
  538. 5355  22:34:07.092947 close(7)          = 0 <0.000003>
  539. 5355  22:34:07.092959 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu6/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  540. 5355  22:34:07.092989 close(7)          = 0 <0.000003>
  541. 5355  22:34:07.093002 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu6/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  542. 5355  22:34:07.093032 close(7)          = 0 <0.000003>
  543. 5355  22:34:07.093044 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu6/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000005>
  544. 5355  22:34:07.093073 close(7)          = 0 <0.000003>
  545. 5355  22:34:07.093085 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000006>
  546. 5355  22:34:07.093123 close(7)          = 0 <0.000003>
  547. 5355  22:34:07.093135 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  548. 5355  22:34:07.093165 close(7)          = 0 <0.000003>
  549. 5355  22:34:07.093177 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index0/level", O_RDONLY) = 7 <0.000005>
  550. 5355  22:34:07.093206 close(7)          = 0 <0.000003>
  551. 5355  22:34:07.093217 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index0/type", O_RDONLY) = 7 <0.000005>
  552. 5355  22:34:07.093246 close(7)          = 0 <0.000003>
  553. 5355  22:34:07.093258 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index0/size", O_RDONLY) = 7 <0.000005>
  554. 5355  22:34:07.093287 close(7)          = 0 <0.000003>
  555. 5355  22:34:07.093299 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index0/coherency_line_size", O_RDONLY) = 7 <0.000005>
  556. 5355  22:34:07.093327 close(7)          = 0 <0.000003>
  557. 5355  22:34:07.093339 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index0/ways_of_associativity", O_RDONLY) = 7 <0.000005>
  558. 5355  22:34:07.093367 close(7)          = 0 <0.000003>
  559. 5355  22:34:07.093379 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index0/physical_line_partition", O_RDONLY) = 7 <0.000006>
  560. 5355  22:34:07.093409 close(7)          = 0 <0.000003>
  561. 5355  22:34:07.093420 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index0/shared_cpu_map", O_RDONLY) = 7 <0.000005>
  562. 5355  22:34:07.093449 close(7)          = 0 <0.000003>
  563. 5355  22:34:07.093461 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000005>
  564. 5355  22:34:07.093490 close(7)          = 0 <0.000003>
  565. 5355  22:34:07.093502 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index1/level", O_RDONLY) = 7 <0.000005>
  566. 5355  22:34:07.093531 close(7)          = 0 <0.000003>
  567. 5355  22:34:07.093542 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index1/type", O_RDONLY) = 7 <0.000005>
  568. 5355  22:34:07.093571 close(7)          = 0 <0.000003>
  569. 5355  22:34:07.093583 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index1/size", O_RDONLY) = 7 <0.000005>
  570. 5355  22:34:07.093612 close(7)          = 0 <0.000003>
  571. 5355  22:34:07.093623 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index1/coherency_line_size", O_RDONLY) = 7 <0.000005>
  572. 5355  22:34:07.093652 close(7)          = 0 <0.000003>
  573. 5355  22:34:07.093664 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index1/ways_of_associativity", O_RDONLY) = 7 <0.000005>
  574. 5355  22:34:07.093693 close(7)          = 0 <0.000003>
  575. 5355  22:34:07.093705 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index1/physical_line_partition", O_RDONLY) = 7 <0.000005>
  576. 5355  22:34:07.093735 close(7)          = 0 <0.000003>
  577. 5355  22:34:07.093747 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index1/shared_cpu_map", O_RDONLY) = 7 <0.000005>
  578. 5355  22:34:07.093775 close(7)          = 0 <0.000003>
  579. 5355  22:34:07.093787 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  580. 5355  22:34:07.093822 close(7)          = 0 <0.000003>
  581. 5355  22:34:07.093833 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index2/level", O_RDONLY) = 7 <0.000005>
  582. 5355  22:34:07.093862 close(7)          = 0 <0.000004>
  583. 5355  22:34:07.093875 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index2/type", O_RDONLY) = 7 <0.000005>
  584. 5355  22:34:07.093904 close(7)          = 0 <0.000003>
  585. 5355  22:34:07.093916 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index2/size", O_RDONLY) = 7 <0.000005>
  586. 5355  22:34:07.093945 close(7)          = 0 <0.000003>
  587. 5355  22:34:07.093956 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index2/coherency_line_size", O_RDONLY) = 7 <0.000005>
  588. 5355  22:34:07.093985 close(7)          = 0 <0.000003>
  589. 5355  22:34:07.093997 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index2/ways_of_associativity", O_RDONLY) = 7 <0.000005>
  590. 5355  22:34:07.094026 close(7)          = 0 <0.000003>
  591. 5355  22:34:07.094037 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index2/physical_line_partition", O_RDONLY) = 7 <0.000005>
  592. 5355  22:34:07.094066 close(7)          = 0 <0.000003>
  593. 5355  22:34:07.094078 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index2/shared_cpu_map", O_RDONLY) = 7 <0.000005>
  594. 5355  22:34:07.094107 close(7)          = 0 <0.000003>
  595. 5355  22:34:07.094119 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu4/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  596. 5355  22:34:07.094148 close(7)          = 0 <0.000003>
  597. 5355  22:34:07.094160 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000006>
  598. 5355  22:34:07.094198 close(7)          = 0 <0.000003>
  599. 5355  22:34:07.094209 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  600. 5355  22:34:07.094239 close(7)          = 0 <0.000003>
  601. 5355  22:34:07.094251 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index0/level", O_RDONLY) = 7 <0.000005>
  602. 5355  22:34:07.094279 close(7)          = 0 <0.000003>
  603. 5355  22:34:07.094291 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index0/type", O_RDONLY) = 7 <0.000005>
  604. 5355  22:34:07.094320 close(7)          = 0 <0.000003>
  605. 5355  22:34:07.094332 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index0/size", O_RDONLY) = 7 <0.000005>
  606. 5355  22:34:07.094361 close(7)          = 0 <0.000003>
  607. 5355  22:34:07.094372 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index0/coherency_line_size", O_RDONLY) = 7 <0.000005>
  608. 5355  22:34:07.094401 close(7)          = 0 <0.000003>
  609. 5355  22:34:07.094413 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index0/ways_of_associativity", O_RDONLY) = 7 <0.000005>
  610. 5355  22:34:07.094442 close(7)          = 0 <0.000003>
  611. 5355  22:34:07.094454 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index0/physical_line_partition", O_RDONLY) = 7 <0.000005>
  612. 5355  22:34:07.094482 close(7)          = 0 <0.000003>
  613. 5355  22:34:07.094494 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index0/shared_cpu_map", O_RDONLY) = 7 <0.000005>
  614. 5355  22:34:07.094522 close(7)          = 0 <0.000003>
  615. 5355  22:34:07.094534 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000005>
  616. 5355  22:34:07.094563 close(7)          = 0 <0.000003>
  617. 5355  22:34:07.094575 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index1/level", O_RDONLY) = 7 <0.000005>
  618. 5355  22:34:07.094604 close(7)          = 0 <0.000003>
  619. 5355  22:34:07.094616 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index1/type", O_RDONLY) = 7 <0.000005>
  620. 5355  22:34:07.094644 close(7)          = 0 <0.000003>
  621. 5355  22:34:07.094656 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index1/size", O_RDONLY) = 7 <0.000005>
  622. 5355  22:34:07.094685 close(7)          = 0 <0.000004>
  623. 5355  22:34:07.094698 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index1/coherency_line_size", O_RDONLY) = 7 <0.000006>
  624. 5355  22:34:07.094728 close(7)          = 0 <0.000003>
  625. 5355  22:34:07.094741 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index1/ways_of_associativity", O_RDONLY) = 7 <0.000006>
  626. 5355  22:34:07.094774 close(7)          = 0 <0.000003>
  627. 5355  22:34:07.094786 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index1/physical_line_partition", O_RDONLY) = 7 <0.000006>
  628. 5355  22:34:07.094815 close(7)          = 0 <0.000003>
  629. 5355  22:34:07.094826 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index1/shared_cpu_map", O_RDONLY) = 7 <0.000005>
  630. 5355  22:34:07.094856 close(7)          = 0 <0.000003>
  631. 5355  22:34:07.094867 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  632. 5355  22:34:07.094897 close(7)          = 0 <0.000003>
  633. 5355  22:34:07.094909 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index2/level", O_RDONLY) = 7 <0.000005>
  634. 5355  22:34:07.094937 close(7)          = 0 <0.000003>
  635. 5355  22:34:07.094949 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index2/type", O_RDONLY) = 7 <0.000005>
  636. 5355  22:34:07.094978 close(7)          = 0 <0.000003>
  637. 5355  22:34:07.094990 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index2/size", O_RDONLY) = 7 <0.000006>
  638. 5355  22:34:07.095020 close(7)          = 0 <0.000003>
  639. 5355  22:34:07.095032 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index2/coherency_line_size", O_RDONLY) = 7 <0.000005>
  640. 5355  22:34:07.095060 close(7)          = 0 <0.000003>
  641. 5355  22:34:07.095072 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index2/ways_of_associativity", O_RDONLY) = 7 <0.000005>
  642. 5355  22:34:07.095101 close(7)          = 0 <0.000003>
  643. 5355  22:34:07.095112 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index2/physical_line_partition", O_RDONLY) = 7 <0.000005>
  644. 5355  22:34:07.095141 close(7)          = 0 <0.000003>
  645. 5355  22:34:07.095152 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index2/shared_cpu_map", O_RDONLY) = 7 <0.000005>
  646. 5355  22:34:07.095181 close(7)          = 0 <0.000003>
  647. 5355  22:34:07.095193 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu2/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  648. 5355  22:34:07.095222 close(7)          = 0 <0.000003>
  649. 5355  22:34:07.095235 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 7 <0.000006>
  650. 5355  22:34:07.095273 close(7)          = 0 <0.000003>
  651. 5355  22:34:07.095285 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index0/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  652. 5355  22:34:07.095315 close(7)          = 0 <0.000003>
  653. 5355  22:34:07.095327 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index0/level", O_RDONLY) = 7 <0.000006>
  654. 5355  22:34:07.095357 close(7)          = 0 <0.000003>
  655. 5355  22:34:07.095369 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index0/type", O_RDONLY) = 7 <0.000010>
  656. 5355  22:34:07.095406 close(7)          = 0 <0.000004>
  657. 5355  22:34:07.095426 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index0/size", O_RDONLY) = 7 <0.000014>
  658. 5355  22:34:07.095465 close(7)          = 0 <0.000004>
  659. 5355  22:34:07.095478 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index0/coherency_line_size", O_RDONLY) = 7 <0.000006>
  660. 5355  22:34:07.095508 close(7)          = 0 <0.000003>
  661. 5355  22:34:07.095520 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index0/ways_of_associativity", O_RDONLY) = 7 <0.000006>
  662. 5355  22:34:07.095550 close(7)          = 0 <0.000003>
  663. 5355  22:34:07.095562 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index0/physical_line_partition", O_RDONLY) = 7 <0.000006>
  664. 5355  22:34:07.095592 close(7)          = 0 <0.000003>
  665. 5355  22:34:07.095605 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index0/shared_cpu_map", O_RDONLY) = 7 <0.000005>
  666. 5355  22:34:07.095646 close(7)          = 0 <0.000003>
  667. 5355  22:34:07.095658 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index1/shared_cpu_list", O_RDONLY) = 7 <0.000005>
  668. 5355  22:34:07.095687 close(7)          = 0 <0.000003>
  669. 5355  22:34:07.095702 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index1/level", O_RDONLY) = 7 <0.000006>
  670. 5355  22:34:07.095732 close(7)          = 0 <0.000003>
  671. 5355  22:34:07.095744 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index1/type", O_RDONLY) = 7 <0.000005>
  672. 5355  22:34:07.095773 close(7)          = 0 <0.000003>
  673. 5355  22:34:07.095785 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index1/size", O_RDONLY) = 7 <0.000006>
  674. 5355  22:34:07.095815 close(7)          = 0 <0.000004>
  675. 5355  22:34:07.095828 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index1/coherency_line_size", O_RDONLY) = 7 <0.000006>
  676. 5355  22:34:07.095858 close(7)          = 0 <0.000004>
  677. 5355  22:34:07.095870 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index1/ways_of_associativity", O_RDONLY) = 7 <0.000006>
  678. 5355  22:34:07.095900 close(7)          = 0 <0.000004>
  679. 5355  22:34:07.095912 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index1/physical_line_partition", O_RDONLY) = 7 <0.000006>
  680. 5355  22:34:07.095942 close(7)          = 0 <0.000003>
  681. 5355  22:34:07.095954 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index1/shared_cpu_map", O_RDONLY) = 7 <0.000005>
  682. 5355  22:34:07.095983 close(7)          = 0 <0.000003>
  683. 5355  22:34:07.095995 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index2/shared_cpu_list", O_RDONLY) = 7 <0.000005>
  684. 5355  22:34:07.096024 close(7)          = 0 <0.000003>
  685. 5355  22:34:07.096036 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index2/level", O_RDONLY) = 7 <0.000005>
  686. 5355  22:34:07.096064 close(7)          = 0 <0.000003>
  687. 5355  22:34:07.096076 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index2/type", O_RDONLY) = 7 <0.000005>
  688. 5355  22:34:07.096104 close(7)          = 0 <0.000003>
  689. 5355  22:34:07.096116 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index2/size", O_RDONLY) = 7 <0.000005>
  690. 5355  22:34:07.096145 close(7)          = 0 <0.000003>
  691. 5355  22:34:07.096157 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index2/coherency_line_size", O_RDONLY) = 7 <0.000005>
  692. 5355  22:34:07.096186 close(7)          = 0 <0.000003>
  693. 5355  22:34:07.096198 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index2/ways_of_associativity", O_RDONLY) = 7 <0.000006>
  694. 5355  22:34:07.096228 close(7)          = 0 <0.000003>
  695. 5355  22:34:07.096240 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index2/physical_line_partition", O_RDONLY) = 7 <0.000005>
  696. 5355  22:34:07.096268 close(7)          = 0 <0.000003>
  697. 5355  22:34:07.096280 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index2/shared_cpu_map", O_RDONLY) = 7 <0.000005>
  698. 5355  22:34:07.096309 close(7)          = 0 <0.000003>
  699. 5355  22:34:07.096321 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index3/shared_cpu_list", O_RDONLY) = 7 <0.000006>
  700. 5355  22:34:07.096350 close(7)          = 0 <0.000003>
  701. 5355  22:34:07.096362 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index3/level", O_RDONLY) = 7 <0.000005>
  702. 5355  22:34:07.096391 close(7)          = 0 <0.000003>
  703. 5355  22:34:07.096403 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index3/type", O_RDONLY) = 7 <0.000005>
  704. 5355  22:34:07.096432 close(7)          = 0 <0.000003>
  705. 5355  22:34:07.096443 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index3/size", O_RDONLY) = 7 <0.000005>
  706. 5355  22:34:07.096472 close(7)          = 0 <0.000003>
  707. 5355  22:34:07.096484 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index3/coherency_line_size", O_RDONLY) = 7 <0.000005>
  708. 5355  22:34:07.096513 close(7)          = 0 <0.000003>
  709. 5355  22:34:07.096525 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index3/ways_of_associativity", O_RDONLY) = 7 <0.000005>
  710. 5355  22:34:07.096553 close(7)          = 0 <0.000003>
  711. 5355  22:34:07.096565 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index3/physical_line_partition", O_RDONLY) = 7 <0.000005>
  712. 5355  22:34:07.096594 close(7)          = 0 <0.000003>
  713. 5355  22:34:07.096608 openat(AT_FDCWD, "/sys/devices/system/node/node0/cpu0/cache/index3/shared_cpu_map", O_RDONLY) = 7 <0.000010>
  714. 5355  22:34:07.096645 close(7)          = 0 <0.000003>
  715. 5355  22:34:07.096664 close(5)          = 0 <0.000003>
  716. 5355  22:34:07.096681 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/0/io_links/0/properties", O_RDONLY) = 5 <0.000008>
  717. 5355  22:34:07.096735 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/gpu_id", O_RDONLY) = 7 <0.000005>
  718. 5355  22:34:07.096767 close(7)          = 0 <0.000003>
  719. 5355  22:34:07.096779 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/properties", O_RDONLY) = 7 <0.000005>
  720. 5355  22:34:07.096821 close(7)          = 0 <0.000003>
  721. 5355  22:34:07.096834 close(5)          = 0 <0.000003>
  722. 5355  22:34:07.096846 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/gpu_id", O_RDONLY) = 5 <0.000005>
  723. 5355  22:34:07.096875 close(5)          = 0 <0.000003>
  724. 5355  22:34:07.096887 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/properties", O_RDONLY) = 5 <0.000005>
  725. 5355  22:34:07.096936 openat(AT_FDCWD, "/dev/dri/renderD128", O_RDWR|O_CLOEXEC) = 7 <0.000029>
  726. 5355  22:34:07.096989 stat("/sys/dev/char/226:128/device/drm", {st_mode=S_IFDIR|0755, st_size=0, ...}) = 0 <0.000012>
  727. 5355  22:34:07.097017 ioctl(7, DRM_IOCTL_VERSION, 0x11233f0) = 0 <0.000006>
  728. 5355  22:34:07.097034 ioctl(7, DRM_IOCTL_VERSION, 0x11233f0) = 0 <0.000003>
  729. 5355  22:34:07.097055 ioctl(8, DRM_IOCTL_AMDGPU_INFO or DRM_IOCTL_SIS_FB_FREE, 0x7ffd164f69e0) = 0 <0.000004>
  730. 5355  22:34:07.097069 ioctl(8, DRM_IOCTL_AMDGPU_INFO or DRM_IOCTL_SIS_FB_FREE, 0x7ffd164f69b0) = 0 <0.000343>
  731. 5355  22:34:07.097422 ioctl(8, DRM_IOCTL_AMDGPU_INFO or DRM_IOCTL_SIS_FB_FREE, 0x7ffd164f69b0) = 0 <0.000010>
  732. 5355  22:34:07.097444 openat(AT_FDCWD, "/opt/amdgpu/share/libdrm/amdgpu.ids", O_RDONLY) = 9 <0.000008>
  733. 5355  22:34:07.097527 close(9)          = 0 <0.000003>
  734. 5355  22:34:07.097541 close(8)          = 0 <0.000004>
  735. 5355  22:34:07.097568 close(7)          = 0 <0.000016>
  736. 5355  22:34:07.097592 close(5)          = 0 <0.000003>
  737. 5355  22:34:07.097605 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/mem_banks/0/properties", O_RDONLY) = 5 <0.000009>
  738. 5355  22:34:07.097653 close(5)          = 0 <0.000004>
  739. 5355  22:34:07.097666 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/0/properties", O_RDONLY) = 5 <0.000006>
  740. 5355  22:34:07.097735 close(5)          = 0 <0.000005>
  741. 5355  22:34:07.097751 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/1/properties", O_RDONLY) = 5 <0.000007>
  742. 5355  22:34:07.097823 close(5)          = 0 <0.000004>
  743. 5355  22:34:07.097835 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/2/properties", O_RDONLY) = 5 <0.000006>
  744. 5355  22:34:07.097903 close(5)          = 0 <0.000006>
  745. 5355  22:34:07.097920 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/3/properties", O_RDONLY) = 5 <0.000007>
  746. 5355  22:34:07.097991 close(5)          = 0 <0.000003>
  747. 5355  22:34:07.098003 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/4/properties", O_RDONLY) = 5 <0.000006>
  748. 5355  22:34:07.098070 close(5)          = 0 <0.000005>
  749. 5355  22:34:07.098086 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/5/properties", O_RDONLY) = 5 <0.000006>
  750. 5355  22:34:07.098154 close(5)          = 0 <0.000005>
  751. 5355  22:34:07.098170 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/6/properties", O_RDONLY) = 5 <0.000007>
  752. 5355  22:34:07.098241 close(5)          = 0 <0.000003>
  753. 5355  22:34:07.098254 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/7/properties", O_RDONLY) = 5 <0.000006>
  754. 5355  22:34:07.098321 close(5)          = 0 <0.000005>
  755. 5355  22:34:07.098338 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/8/properties", O_RDONLY) = 5 <0.000006>
  756. 5355  22:34:07.098406 close(5)          = 0 <0.000003>
  757. 5355  22:34:07.098419 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/9/properties", O_RDONLY) = 5 <0.000006>
  758. 5355  22:34:07.098488 close(5)          = 0 <0.000005>
  759. 5355  22:34:07.098504 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/10/properties", O_RDONLY) = 5 <0.000007>
  760. 5355  22:34:07.098576 close(5)          = 0 <0.000003>
  761. 5355  22:34:07.098588 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/11/properties", O_RDONLY) = 5 <0.000006>
  762. 5355  22:34:07.098656 close(5)          = 0 <0.000004>
  763. 5355  22:34:07.098668 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/12/properties", O_RDONLY) = 5 <0.000006>
  764. 5355  22:34:07.098736 close(5)          = 0 <0.000005>
  765. 5355  22:34:07.098752 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/caches/13/properties", O_RDONLY) = 5 <0.000007>
  766. 5355  22:34:07.098822 close(5)          = 0 <0.000003>
  767. 5355  22:34:07.098835 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/1/io_links/0/properties", O_RDONLY) = 5 <0.000006>
  768. 5355  22:34:07.098875 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/nodes/0/gpu_id", O_RDONLY) = 7 <0.000005>
  769. 5355  22:34:07.098903 close(7)          = 0 <0.000003>
  770. 5355  22:34:07.098917 close(5)          = 0 <0.000003>
  771. 5355  22:34:07.098928 openat(AT_FDCWD, "/sys/devices/virtual/kfd/kfd/topology/generation_id", O_RDONLY) = 5 <0.000006>
  772. 5355  22:34:07.098959 close(5)          = 0 <0.000003>
  773. 5355  22:34:07.098986 ioctl(3, _IOC(_IOC_READ|_IOC_WRITE, 0x4b, 0x21, 0x4), 0x7ffd164f6f24) = 0 <0.000004>
  774. 5355  22:34:07.099000 ioctl(3, AMDKFD_IOC_GET_CLOCK_COUNTERS, 0x7ffd164f6dd0) = 0 <0.000006>
  775. 5355  22:34:07.099024 ioctl(3, AMDKFD_IOC_GET_CLOCK_COUNTERS, 0x7ffd164f71c0) = 0 <0.000004>
  776. 5355  22:34:07.099070 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6f20) = 0 <0.000012>
  777. 5355  22:34:07.099119 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6ff0) = 0 <0.000212>
  778. 5355  22:34:07.099343 ioctl(3, AMDKFD_IOC_CREATE_EVENT, 0x7ffd164f7140) = 0 <0.000013>
  779. 5355  22:34:07.099424 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6e60) = 0 <0.000023>
  780. 5355  22:34:07.099458 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6e90) = 0 <0.000029>
  781. 5355  22:34:07.099499 ioctl(3, AMDKFD_IOC_CREATE_EVENT, 0x7ffd164f7030) = 0 <0.000004>
  782. 5355  22:34:07.099513 openat(AT_FDCWD, "/sys/devices/system/cpu", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 5 <0.000006>
  783. 5355  22:34:07.099556 close(5)          = 0 <0.000003>
  784. 5355  22:34:07.099668 ioctl(3, AMDKFD_IOC_SET_SCRATCH_BACKING_VA, 0x7ffd164f70d0) = 0 <0.000003>
  785. 5355  22:34:07.099735 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6ae0) = 0 <0.000015>
  786. 5355  22:34:07.099762 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b10) = 0 <0.000056>
  787. 5355  22:34:07.099829 ioctl(3, AMDKFD_IOC_SET_TRAP_HANDLER, 0x7ffd164f71a0) = 0 <0.000004>
  788. 5355  22:34:07.099909 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6c50) = 0 <0.000008>
  789. 5355  22:34:07.099926 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6c80) = 0 <0.000033>
  790. 5358  22:34:07.099980 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  791. 5355  22:34:07.100017 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6c00) = 0 <0.000007>
  792. 5355  22:34:07.100033 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6c30) = 0 <0.000028>
  793. 5355  22:34:07.100071 ioctl(3, AMDKFD_IOC_CREATE_EVENT, 0x7ffd164f6e70) = 0 <0.000005>
  794. 5355  22:34:07.100130 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f69b0) = 0 <0.000010>
  795. 5355  22:34:07.100148 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6a20) = 0 <0.000024>
  796. 5355  22:34:07.100212 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6970) = 0 <0.000006>
  797. 5355  22:34:07.100243 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6a20) = 0 <0.000022>
  798. 5355  22:34:07.100317 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f69b0) = 0 <0.000294>
  799. 5355  22:34:07.100621 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6a20) = 0 <0.000092>
  800. 5355  22:34:07.100724 ioctl(3, AMDKFD_IOC_CREATE_QUEUE, 0x7ffd164f6b90) = 0 <0.000531>
  801. 5355  22:34:07.101297 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6a30) = 0 <0.000006>
  802. 5355  22:34:07.101324 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6aa0) = 0 <0.000025>
  803. 5355  22:34:07.101363 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f6e80) = 0 <0.000005>
  804. 5358  22:34:07.101374 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.001391>
  805. 5355  22:34:07.101379 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f6e80) = 0 <0.000002>
  806. 5355  22:34:07.101445 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6c80) = 0 <0.000008>
  807. 5355  22:34:07.101463 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6cb0) = 0 <0.000028>
  808. 5355  22:34:07.101546 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d60) = 0 <0.000008>
  809. 5355  22:34:07.101563 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6d90) = 0 <0.000032>
  810. 5358  22:34:07.101610 ioctl(3, AMDKFD_IOC_WAIT_EVENTS, 0x7f0a22a66ba0) = 0 <0.000004>
  811. 5358  22:34:07.101626 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  812. 5355  22:34:07.101655 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d10) = 0 <0.000042>
  813. 5355  22:34:07.101706 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6d40) = 0 <0.000024>
  814. 5355  22:34:07.101792 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6ac0) = 0 <0.000008>
  815. 5355  22:34:07.101809 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000027>
  816. 5355  22:34:07.101868 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6a80) = 0 <0.000006>
  817. 5355  22:34:07.101898 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000023>
  818. 5355  22:34:07.101974 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6ac0) = 0 <0.000309>
  819. 5355  22:34:07.102294 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000114>
  820. 5355  22:34:07.102419 ioctl(3, AMDKFD_IOC_CREATE_QUEUE, 0x7ffd164f6ca0) = 0 <0.000064>
  821. 5355  22:34:07.102495 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f6f90) = 0 <0.000006>
  822. 5358  22:34:07.102507 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000878>
  823. 5355  22:34:07.102512 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f6f90) = 0 <0.000002>
  824. 5355  22:34:07.102581 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d90) = 0 <0.000008>
  825. 5355  22:34:07.102599 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6dc0) = 0 <0.000023>
  826. 5355  22:34:07.102679 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d60) = 0 <0.000007>
  827. 5355  22:34:07.102694 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6d90) = 0 <0.000023>
  828. 5358  22:34:07.102744 ioctl(3, AMDKFD_IOC_WAIT_EVENTS, 0x7f0a22a66ba0) = 0 <0.000006>
  829. 5358  22:34:07.102760 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  830. 5355  22:34:07.102774 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d10) = 0 <0.000041>
  831. 5355  22:34:07.102826 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6d40) = 0 <0.000024>
  832. 5355  22:34:07.102910 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6ac0) = 0 <0.000008>
  833. 5355  22:34:07.102926 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000029>
  834. 5355  22:34:07.102988 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6a80) = 0 <0.000006>
  835. 5355  22:34:07.103018 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000022>
  836. 5355  22:34:07.103092 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6ac0) = 0 <0.000327>
  837. 5355  22:34:07.103429 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000115>
  838. 5355  22:34:07.103556 ioctl(3, AMDKFD_IOC_CREATE_QUEUE, 0x7ffd164f6ca0) = 0 <0.000064>
  839. 5355  22:34:07.103632 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f6f90) = 0 <0.000006>
  840. 5358  22:34:07.103645 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000881>
  841. 5355  22:34:07.103649 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f6f90) = 0 <0.000002>
  842. 5355  22:34:07.103720 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d90) = 0 <0.000008>
  843. 5355  22:34:07.103738 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6dc0) = 0 <0.000023>
  844. 5355  22:34:07.103816 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d60) = 0 <0.000007>
  845. 5355  22:34:07.103832 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6d90) = 0 <0.000023>
  846. 5358  22:34:07.103884 ioctl(3, AMDKFD_IOC_WAIT_EVENTS, 0x7f0a22a66ba0) = 0 <0.000006>
  847. 5358  22:34:07.103901 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  848. 5355  22:34:07.103912 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d10) = 0 <0.000041>
  849. 5355  22:34:07.103967 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6d40) = 0 <0.000024>
  850. 5355  22:34:07.104052 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6ac0) = 0 <0.000008>
  851. 5355  22:34:07.104069 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000023>
  852. 5355  22:34:07.104125 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6a80) = 0 <0.000005>
  853. 5355  22:34:07.104154 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000022>
  854. 5355  22:34:07.104228 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6ac0) = 0 <0.000321>
  855. 5355  22:34:07.104560 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000092>
  856. 5355  22:34:07.104664 ioctl(3, AMDKFD_IOC_CREATE_QUEUE, 0x7ffd164f6ca0) = 0 <0.000066>
  857. 5355  22:34:07.104741 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f6f90) = 0 <0.000006>
  858. 5358  22:34:07.104754 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000850>
  859. 5355  22:34:07.104758 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f6f90) = 0 <0.000002>
  860. 5355  22:34:07.104825 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d90) = 0 <0.000008>
  861. 5355  22:34:07.104842 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6dc0) = 0 <0.000027>
  862. 5355  22:34:07.104925 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d60) = 0 <0.000007>
  863. 5355  22:34:07.104940 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6d90) = 0 <0.000023>
  864. 5358  22:34:07.104989 ioctl(3, AMDKFD_IOC_WAIT_EVENTS, 0x7f0a22a66ba0) = 0 <0.000005>
  865. 5358  22:34:07.105005 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  866. 5355  22:34:07.105019 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d10) = 0 <0.000040>
  867. 5355  22:34:07.105070 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6d40) = 0 <0.000024>
  868. 5355  22:34:07.105196 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6ac0) = 0 <0.000012>
  869. 5355  22:34:07.105235 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000023>
  870. 5355  22:34:07.105298 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6a80) = 0 <0.000007>
  871. 5355  22:34:07.105333 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000031>
  872. 5355  22:34:07.105425 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6ac0) = 0 <0.000357>
  873. 5355  22:34:07.105803 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6b30) = 0 <0.000108>
  874. 5355  22:34:07.105938 ioctl(3, AMDKFD_IOC_CREATE_QUEUE, 0x7ffd164f6ca0) = 0 <0.000067>
  875. 5355  22:34:07.106022 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f6f90) = 0 <0.000008>
  876. 5358  22:34:07.106039 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.001030>
  877. 5355  22:34:07.106045 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f6f90) = 0 <0.000003>
  878. 5355  22:34:07.106129 ioctl(3, AMDKFD_IOC_ALLOC_MEMORY_OF_GPU, 0x7ffd164f6d90) = 0 <0.000009>
  879. 5355  22:34:07.106149 ioctl(3, AMDKFD_IOC_MAP_MEMORY_TO_GPU, 0x7ffd164f6dc0) = 0 <0.000023>
  880. 5355  22:34:07.106278 stat("fixme.so",  <unfinished ...>
  881. 5358  22:34:07.106288 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  882. 5355  22:34:07.106294 <... stat resumed>0x7ffd164f7a68) = -1 ENOENT (没有那个文件或目录) <0.000007>
  883. 5358  22:34:07.106302 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000009>
  884. 5358  22:34:07.106309 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  885. 5355  22:34:07.106321 openat(AT_FDCWD, "/sys/bus/pci/devices", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 5 <0.000010>
  886. 5355  22:34:07.106392 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:03:00.0/uevent", O_RDONLY) = 7 <0.000010>
  887. 5355  22:34:07.106455 close(7)          = 0 <0.000005>
  888. 5355  22:34:07.106476 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:08.0/uevent", O_RDONLY) = 7 <0.000008>
  889. 5355  22:34:07.106517 close(7)          = 0 <0.000004>
  890. 5355  22:34:07.106532 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.3/uevent", O_RDONLY) = 7 <0.000007>
  891. 5355  22:34:07.106570 close(7)          = 0 <0.000004>
  892. 5355  22:34:07.106585 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.3/uevent", O_RDONLY) = 7 <0.000006>
  893. 5355  22:34:07.106621 close(7)          = 0 <0.000004>
  894. 5355  22:34:07.106635 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.1/uevent", O_RDONLY) = 7 <0.000007>
  895. 5355  22:34:07.106672 close(7)          = 0 <0.000004>
  896. 5355  22:34:07.106692 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.1/uevent", O_RDONLY) = 7 <0.000007>
  897. 5355  22:34:07.106730 close(7)          = 0 <0.000004>
  898. 5355  22:34:07.106744 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:01.0/uevent", O_RDONLY) = 7 <0.000006>
  899. 5355  22:34:07.106781 close(7)          = 0 <0.000005>
  900. 5355  22:34:07.106797 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:01:00.2/uevent", O_RDONLY) = 7 <0.000008>
  901. 5355  22:34:07.106838 close(7)          = 0 <0.000004>
  902. 5355  22:34:07.106853 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:14.3/uevent", O_RDONLY) = 7 <0.000006>
  903. 5355  22:34:07.106890 close(7)          = 0 <0.000004>
  904. 5355  22:34:07.106904 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:01:00.0/uevent", O_RDONLY) = 7 <0.000006>
  905. 5355  22:34:07.106940 close(7)          = 0 <0.000004>
  906. 5355  22:34:07.106955 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:02.1/uevent", O_RDONLY) = 7 <0.000006>
  907. 5355  22:34:07.106991 close(7)          = 0 <0.000004>
  908. 5355  22:34:07.107005 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.6/uevent", O_RDONLY) = 7 <0.000006>
  909. 5355  22:34:07.107041 close(7)          = 0 <0.000004>
  910. 5355  22:34:07.107056 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.6/uevent", O_RDONLY) = 7 <0.000007>
  911. 5355  22:34:07.107092 close(7)          = 0 <0.000004>
  912. 5355  22:34:07.107107 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:00.0/uevent", O_RDONLY) = 7 <0.000006>
  913. 5355  22:34:07.107143 close(7)          = 0 <0.000005>
  914. 5355  22:34:07.107159 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:08.1/uevent", O_RDONLY) = 7 <0.000007>
  915. 5355  22:34:07.107200 close(7)          = 0 <0.000004>
  916. 5355  22:34:07.107214 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.4/uevent", O_RDONLY) = 7 <0.000007>
  917. 5355  22:34:07.107257 close(7)          = 0 <0.000004>
  918. 5355  22:34:07.107272 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.4/uevent", O_RDONLY) = 7 <0.000006>
  919. 5355  22:34:07.107309 close(7)          = 0 <0.000004>
  920. 5355  22:34:07.107324 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:02:02.0/uevent", O_RDONLY) = 7 <0.000007>
  921. 5355  22:34:07.107361 close(7)          = 0 <0.000004>
  922. 5355  22:34:07.107375 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.2/uevent", O_RDONLY) = 7 <0.000010>
  923. 5355  22:34:07.107428 close(7)          = 0 <0.000004>
  924. 5355  22:34:07.107443 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.2/uevent", O_RDONLY) = 7 <0.000008>
  925. 5355  22:34:07.107485 close(7)          = 0 <0.000004>
  926. 5355  22:34:07.107499 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.0/uevent", O_RDONLY) = 7 <0.000008>
  927. 5355  22:34:07.107540 close(7)          = 0 <0.000004>
  928. 5355  22:34:07.107554 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.0/uevent", O_RDONLY) = 7 <0.000008>
  929. 5355  22:34:07.107596 close(7)          = 0 <0.000004>
  930. 5355  22:34:07.107611 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:01:00.1/uevent", O_RDONLY) = 7 <0.000008>
  931. 5355  22:34:07.107651 close(7)          = 0 <0.000004>
  932. 5355  22:34:07.107666 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:02.2/uevent", O_RDONLY) = 7 <0.000007>
  933. 5355  22:34:07.107707 close(7)          = 0 <0.000004>
  934. 5355  22:34:07.107722 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:04:00.0/uevent", O_RDONLY) = 7 <0.000008>
  935. 5355  22:34:07.107762 close(7)          = 0 <0.000004>
  936. 5355  22:34:07.107777 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:02.0/uevent", O_RDONLY) = 7 <0.000007>
  937. 5355  22:34:07.107816 close(7)          = 0 <0.000004>
  938. 5355  22:34:07.107831 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.7/uevent", O_RDONLY) = 7 <0.000008>
  939. 5355  22:34:07.107871 close(7)          = 0 <0.000004>
  940. 5355  22:34:07.107886 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:14.0/uevent", O_RDONLY) = 7 <0.000007>
  941. 5355  22:34:07.107926 close(7)          = 0 <0.000004>
  942. 5355  22:34:07.107940 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.5/uevent", O_RDONLY) = 7 <0.000007>
  943. 5355  22:34:07.107981 close(7)          = 0 <0.000004>
  944. 5355  22:34:07.108004 close(5)          = 0 <0.000005>
  945. 5355  22:34:07.108019 openat(AT_FDCWD, "/sys/bus/pci/devices", O_RDONLY|O_NONBLOCK|O_CLOEXEC|O_DIRECTORY) = 5 <0.000006>
  946. 5355  22:34:07.108059 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:03:00.0/uevent", O_RDONLY) = 7 <0.000008>
  947. 5355  22:34:07.108102 close(7)          = 0 <0.000004>
  948. 5355  22:34:07.108118 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:08.0/uevent", O_RDONLY) = 7 <0.000006>
  949. 5355  22:34:07.108152 close(7)          = 0 <0.000004>
  950. 5355  22:34:07.108166 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.3/uevent", O_RDONLY) = 7 <0.000006>
  951. 5355  22:34:07.108201 close(7)          = 0 <0.000004>
  952. 5355  22:34:07.108216 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.3/uevent", O_RDONLY) = 7 <0.000005>
  953. 5355  22:34:07.108250 close(7)          = 0 <0.000004>
  954. 5355  22:34:07.108264 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.1/uevent", O_RDONLY) = 7 <0.000005>
  955. 5355  22:34:07.108298 close(7)          = 0 <0.000004>
  956. 5355  22:34:07.108313 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.1/uevent", O_RDONLY) = 7 <0.000005>
  957. 5355  22:34:07.108347 close(7)          = 0 <0.000004>
  958. 5355  22:34:07.108361 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:01.0/uevent", O_RDONLY) = 7 <0.000005>
  959. 5355  22:34:07.108395 close(7)          = 0 <0.000004>
  960. 5355  22:34:07.108409 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:01:00.2/uevent", O_RDONLY) = 7 <0.000005>
  961. 5355  22:34:07.108443 close(7)          = 0 <0.000004>
  962. 5355  22:34:07.108457 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:14.3/uevent", O_RDONLY) = 7 <0.000006>
  963. 5355  22:34:07.108491 close(7)          = 0 <0.000004>
  964. 5355  22:34:07.108506 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:01:00.0/uevent", O_RDONLY) = 7 <0.000006>
  965. 5355  22:34:07.108541 close(7)          = 0 <0.000004>
  966. 5355  22:34:07.108555 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:02.1/uevent", O_RDONLY) = 7 <0.000009>
  967. 5355  22:34:07.108598 close(7)          = 0 <0.000004>
  968. 5355  22:34:07.108613 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.6/uevent", O_RDONLY) = 7 <0.000006>
  969. 5355  22:34:07.108648 close(7)          = 0 <0.000004>
  970. 5355  22:34:07.108663 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.6/uevent", O_RDONLY) = 7 <0.000006>
  971. 5355  22:34:07.108697 close(7)          = 0 <0.000004>
  972. 5355  22:34:07.108711 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:00.0/uevent", O_RDONLY) = 7 <0.000006>
  973. 5355  22:34:07.108746 close(7)          = 0 <0.000004>
  974. 5355  22:34:07.108760 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:08.1/uevent", O_RDONLY) = 7 <0.000005>
  975. 5355  22:34:07.108794 close(7)          = 0 <0.000005>
  976. 5355  22:34:07.108810 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.4/uevent", O_RDONLY) = 7 <0.000007>
  977. 5355  22:34:07.108851 close(7)          = 0 <0.000004>
  978. 5355  22:34:07.108866 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.4/uevent", O_RDONLY) = 7 <0.000006>
  979. 5355  22:34:07.108900 close(7)          = 0 <0.000004>
  980. 5355  22:34:07.108914 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:02:02.0/uevent", O_RDONLY) = 7 <0.000006>
  981. 5355  22:34:07.108949 close(7)          = 0 <0.000004>
  982. 5355  22:34:07.108964 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.2/uevent", O_RDONLY) = 7 <0.000006>
  983. 5355  22:34:07.109010 close(7)          = 0 <0.000004>
  984. 5355  22:34:07.109025 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.2/uevent", O_RDONLY) = 7 <0.000006>
  985. 5355  22:34:07.109059 close(7)          = 0 <0.000004>
  986. 5355  22:34:07.109074 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:05:00.0/uevent", O_RDONLY) = 7 <0.000006>
  987. 5355  22:34:07.109108 close(7)          = 0 <0.000005>
  988. 5355  22:34:07.109123 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.0/uevent", O_RDONLY) = 7 <0.000007>
  989. 5355  22:34:07.109164 close(7)          = 0 <0.000004>
  990. 5355  22:34:07.109179 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:01:00.1/uevent", O_RDONLY) = 7 <0.000006>
  991. 5355  22:34:07.109213 close(7)          = 0 <0.000004>
  992. 5355  22:34:07.109227 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:02.2/uevent", O_RDONLY) = 7 <0.000005>
  993. 5355  22:34:07.109261 close(7)          = 0 <0.000004>
  994. 5355  22:34:07.109275 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:04:00.0/uevent", O_RDONLY) = 7 <0.000006>
  995. 5355  22:34:07.109309 close(7)          = 0 <0.000004>
  996. 5355  22:34:07.109324 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:02.0/uevent", O_RDONLY) = 7 <0.000006>
  997. 5355  22:34:07.109372 close(7)          = 0 <0.000004>
  998. 5355  22:34:07.109388 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.7/uevent", O_RDONLY) = 7 <0.000008>
  999. 5355  22:34:07.109450 close(7)          = 0 <0.000006>
  1000. 5355  22:34:07.109475 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:14.0/uevent", O_RDONLY) = 7 <0.000008>
  1001. 5355  22:34:07.109537 close(7)          = 0 <0.000006>
  1002. 5355  22:34:07.109562 openat(AT_FDCWD, "/sys/bus/pci/devices/0000:00:18.5/uevent", O_RDONLY) = 7 <0.000007>
  1003. 5355  22:34:07.109619 close(7)          = 0 <0.000004>
  1004. 5355  22:34:07.109665 close(5)          = 0 <0.000004>
  1005. 5355  22:34:07.109693 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/libhsa-runtime64.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000010>
  1006. 5355  22:34:07.109719 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../lib/libhsa-runtime64.so", O_RDONLY|O_CLOEXEC) = -1 ENOENT (没有那个文件或目录) <0.000006>
  1007. 5355  22:34:07.109740 openat(AT_FDCWD, "/opt/rocm-5.1.0/llvm/bin/../lib/../../lib/libhsa-runtime64.so", O_RDONLY|O_CLOEXEC) = 5 <0.000009>
  1008. 5355  22:34:07.109781 close(5)          = 0 <0.000004>
  1009. 5355  22:34:07.109815 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000007>
  1010. 5355  22:34:07.109852 close(5)          = 0 <0.000007>
  1011. 5355  22:34:07.109872 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000005>
  1012. 5355  22:34:07.109896 close(5)          = 0 <0.000003>
  1013. 5355  22:34:07.109909 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000005>
  1014. 5355  22:34:07.109932 close(5)          = 0 <0.000009>
  1015. 5355  22:34:07.109955 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000004>
  1016. 5355  22:34:07.109982 close(5)          = 0 <0.000005>
  1017. 5355  22:34:07.109998 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000007>
  1018. 5355  22:34:07.110022 close(5)          = 0 <0.000003>
  1019. 5355  22:34:07.110034 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000004>
  1020. 5355  22:34:07.110055 close(5)          = 0 <0.000003>
  1021. 5355  22:34:07.110067 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000004>
  1022. 5355  22:34:07.110087 close(5)          = 0 <0.000003>
  1023. 5355  22:34:07.110099 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000004>
  1024. 5355  22:34:07.110118 close(5)          = 0 <0.000003>
  1025. 5355  22:34:07.110129 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000004>
  1026. 5355  22:34:07.110149 close(5)          = 0 <0.000003>
  1027. 5355  22:34:07.110160 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000009>
  1028. 5355  22:34:07.110193 close(5)          = 0 <0.000004>
  1029. 5355  22:34:07.110206 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000004>
  1030. 5355  22:34:07.110226 close(5)          = 0 <0.000003>
  1031. 5355  22:34:07.110238 openat(AT_FDCWD, "/dev/random", O_WRONLY) = 5 <0.000004>
  1032. 5355  22:34:07.110258 close(5)          = 0 <0.000003>
  1033. 5355  22:34:07.111651 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f7a90) = 0 <0.000011>
  1034. 5358  22:34:07.111683 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.005370>
  1035. 5358  22:34:07.111710 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7f0a22a66d20) = 0 <0.000020>
  1036. 5355  22:34:07.111752 ioctl(3, AMDKFD_IOC_DESTROY_QUEUE <unfinished ...>
  1037. 5358  22:34:07.111761 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7f0a22a66d70) = 0 <0.000018>
  1038. 5355  22:34:07.111992 <... ioctl resumed>, 0x7ffd164f7a90) = 0 <0.000236>
  1039. 5358  22:34:07.112005 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  1040. 5355  22:34:07.112013 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU <unfinished ...>
  1041. 5358  22:34:07.112030 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000021>
  1042. 5355  22:34:07.112038 <... ioctl resumed>, 0x7ffd164f79b0) = 0 <0.000022>
  1043. 5358  22:34:07.112051 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  1044. 5355  22:34:07.112060 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7a00) = 0 <0.000015>
  1045. 5355  22:34:07.112149 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f79b0) = 0 <0.000016>
  1046. 5355  22:34:07.112188 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7a00) = 0 <0.000016>
  1047. 5355  22:34:07.112401 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f79d0) = 0 <0.000011>
  1048. 5355  22:34:07.112431 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7a20) = 0 <0.000011>
  1049. 5355  22:34:07.112513 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7920) = 0 <0.000009>
  1050. 5355  22:34:07.112541 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7970) = 0 <0.000009>
  1051. 5355  22:34:07.112639 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7940) = 0 <0.000016>
  1052. 5355  22:34:07.112674 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7990) = 0 <0.000015>
  1053. 5355  22:34:07.112759 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7940) = 0 <0.000011>
  1054. 5355  22:34:07.112794 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7990) = 0 <0.000012>
  1055. 5355  22:34:07.112878 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f7a90) = 0 <0.000011>
  1056. 5358  22:34:07.112902 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000847>
  1057. 5358  22:34:07.112928 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7f0a22a66d20) = 0 <0.000017>
  1058. 5355  22:34:07.112960 ioctl(3, AMDKFD_IOC_DESTROY_QUEUE <unfinished ...>
  1059. 5358  22:34:07.112979 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7f0a22a66d70) = 0 <0.000018>
  1060. 5355  22:34:07.113106 <... ioctl resumed>, 0x7ffd164f7a90) = 0 <0.000142>
  1061. 5355  22:34:07.113120 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f79b0) = 0 <0.000009>
  1062. 5355  22:34:07.113149 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7a00) = 0 <0.000012>
  1063. 5358  22:34:07.113225 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  1064. 5355  22:34:07.113234 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU <unfinished ...>
  1065. 5358  22:34:07.113252 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000021>
  1066. 5355  22:34:07.113260 <... ioctl resumed>, 0x7ffd164f79b0) = 0 <0.000022>
  1067. 5358  22:34:07.113276 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  1068. 5355  22:34:07.113283 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7a00) = 0 <0.000014>
  1069. 5355  22:34:07.113470 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f79d0) = 0 <0.000014>
  1070. 5355  22:34:07.113502 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7a20) = 0 <0.000011>
  1071. 5355  22:34:07.113586 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7920) = 0 <0.000010>
  1072. 5355  22:34:07.113618 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7970) = 0 <0.000012>
  1073. 5355  22:34:07.113711 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7940) = 0 <0.000009>
  1074. 5355  22:34:07.113741 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7990) = 0 <0.000011>
  1075. 5355  22:34:07.113815 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7940) = 0 <0.000011>
  1076. 5355  22:34:07.113840 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7990) = 0 <0.000015>
  1077. 5355  22:34:07.113913 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f7a90) = 0 <0.000016>
  1078. 5358  22:34:07.113947 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000667>
  1079. 5358  22:34:07.113975 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7f0a22a66d20) = 0 <0.000019>
  1080. 5355  22:34:07.114014 ioctl(3, AMDKFD_IOC_DESTROY_QUEUE <unfinished ...>
  1081. 5358  22:34:07.114024 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7f0a22a66d70) = 0 <0.000018>
  1082. 5355  22:34:07.114100 <... ioctl resumed>, 0x7ffd164f7a90) = 0 <0.000083>
  1083. 5355  22:34:07.114115 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f79b0) = 0 <0.000012>
  1084. 5355  22:34:07.114140 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7a00) = 0 <0.000014>
  1085. 5355  22:34:07.114222 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f79b0) = 0 <0.000018>
  1086. 5355  22:34:07.114258 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU <unfinished ...>
  1087. 5358  22:34:07.114271 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  1088. 5355  22:34:07.114285 <... ioctl resumed>, 0x7ffd164f7a00) = 0 <0.000022>
  1089. 5358  22:34:07.114306 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000031>
  1090. 5358  22:34:07.114329 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  1091. 5355  22:34:07.114504 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f79d0) = 0 <0.000009>
  1092. 5355  22:34:07.114533 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7a20) = 0 <0.000011>
  1093. 5355  22:34:07.114607 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7920) = 0 <0.000010>
  1094. 5355  22:34:07.114632 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7970) = 0 <0.000013>
  1095. 5355  22:34:07.114727 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7940) = 0 <0.000017>
  1096. 5355  22:34:07.114760 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7990) = 0 <0.000009>
  1097. 5355  22:34:07.114843 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7940) = 0 <0.000015>
  1098. 5355  22:34:07.114872 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7990) = 0 <0.000013>
  1099. 5355  22:34:07.114953 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7ffd164f7a90) = 0 <0.000014>
  1100. 5358  22:34:07.114989 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000656>
  1101. 5358  22:34:07.115015 ioctl(3, AMDKFD_IOC_SET_EVENT, 0x7f0a22a66d20) = 0 <0.000019>
  1102. 5358  22:34:07.115056 ioctl(3, AMDKFD_IOC_SET_EVENT <unfinished ...>
  1103. 5355  22:34:07.115062 ioctl(3, AMDKFD_IOC_DESTROY_QUEUE <unfinished ...>
  1104. 5358  22:34:07.115088 <... ioctl resumed>, 0x7f0a22a66d70) = 0 <0.000027>
  1105. 5355  22:34:07.115157 <... ioctl resumed>, 0x7ffd164f7a90) = 0 <0.000090>
  1106. 5355  22:34:07.115171 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f79b0) = 0 <0.000012>
  1107. 5355  22:34:07.115206 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7a00) = 0 <0.000013>
  1108. 5355  22:34:07.115302 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU <unfinished ...>
  1109. 5358  22:34:07.115316 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  1110. 5355  22:34:07.115326 <... ioctl resumed>, 0x7ffd164f79b0) = 0 <0.000019>
  1111. 5358  22:34:07.115343 <... ioctl resumed>, 0x7f0a22a66ba0) = 0 <0.000024>
  1112. 5355  22:34:07.115351 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU <unfinished ...>
  1113. 5358  22:34:07.115370 ioctl(3, AMDKFD_IOC_WAIT_EVENTS <unfinished ...>
  1114. 5355  22:34:07.115376 <... ioctl resumed>, 0x7ffd164f7a00) = 0 <0.000022>
  1115. 5355  22:34:07.115584 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f79d0) = 0 <0.000014>
  1116. 5355  22:34:07.115622 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7a20) = 0 <0.000016>
  1117. 5355  22:34:07.115705 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7920) = 0 <0.000015>
  1118. 5355  22:34:07.115734 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7970) = 0 <0.000013>
  1119. 5355  22:34:07.115830 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7940) = 0 <0.000014>
  1120. 5355  22:34:07.115862 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7990) = 0 <0.000013>
  1121. 5355  22:34:07.115944 ioctl(3, AMDKFD_IOC_UNMAP_MEMORY_FROM_GPU, 0x7ffd164f7940) = 0 <0.000011>
  1122. 5355  22:34:07.115977 ioctl(3, AMDKFD_IOC_FREE_MEMORY_OF_GPU, 0x7ffd164f7990) = 0 <0.000011>
  1123. 5355  22:34:07.116137 openat(AT_FDCWD, "/dev/shm/__KMP_REGISTERED_LIB_5355_0", O_RDONLY|O_NOFOLLOW|O_CLOEXEC) = 5 <0.000010>
  1124. 5355  22:34:07.116231 close(5)          = 0 <0.000012>
  1125. 5355  22:34:07.116259 unlink("/dev/shm/__KMP_REGISTERED_LIB_5355_0") = 0 <0.000019>
  1126. 5369  22:34:07.116369 +++ exited with 0 +++
  1127. 5368  22:34:07.116374 +++ exited with 0 +++
  1128. 5367  22:34:07.116376 +++ exited with 0 +++
  1129. 5365  22:34:07.116380 +++ exited with 0 +++
  1130. 5366  22:34:07.116393 +++ exited with 0 +++
  1131. 5363  22:34:07.116399 +++ exited with 0 +++
  1132. 5364  22:34:07.116401 +++ exited with 0 +++
  1133. 5360  22:34:07.116405 +++ exited with 0 +++
  1134. 5362  22:34:07.116411 +++ exited with 0 +++
  1135. 5361  22:34:07.116414 +++ exited with 0 +++
  1136. 5359  22:34:07.116416 +++ exited with 0 +++
  1137. 5358  22:34:07.116722 <... ioctl resumed> <unfinished ...>) = ?
  1138. 5358  22:34:07.116762 +++ exited with 0 +++
  1139. 5355  22:34:07.133444 +++ exited with 0 +++
参考资料

https://raw.githubusercontent.com/RadeonOpenCompute/ROCm/rocm-4.5.2/AMD_HIP_Programming_Guide.pdf

使用UMR读取system memory_umr only和-CSDN博客

https://github.com/RadeonOpenCompute/ROCT-Thunk-Interface.git

AMD ROCm软件栈组件介绍_rocm中-CSDN博客

AMD HSA 异构计算架构和AMD-KFD内核驱动&NVIDIA内核驱动-CSDN博客

百度安全验证

AMD的ROCM平台是什么？ - 知乎

https://cgmb-rocm-docs.readthedocs.io/_/downloads/en/latest/pdf/

OpenCL编程详细解析与实例 - 知乎

第1章 简介异构计算 - OpenCL 2.0 异构计算 - 开发文档 - 文江博客

HIP-ROCM架构概述 - 知乎

ROCm兼容cuda方案和验证 - 知乎

ROCm API libraries — ROCm Documentation

源码编译安装ROCm以运行tensorflow-rocm（适用于Ubuntu 23.04） - 小蓝博客

AMD 推出 HIP SDK：拓展 ROCm 方案，为 CUDA 应用程序提供支持_腾讯新闻

https://dev.to/shawonashraf/setting-up-your-amd-gpu-for-tensorflow-in-ubuntu-20-04-31f5

GPU memory — ROCm Documentation

Index of /amdgpu-install/

https://www.cnblogs.com/lllzhuang/articles/16083003.html

结束
声明：本文内容由网友自发贡献，不代表【wpsshop博客】立场，版权归原作者所有，本站不承担相应法律责任。如您发现有侵权的内容，请联系我们。转载请注明出处：https://www.wpsshop.cn/w/小惠珠哦/article/detail/946344
推荐阅读
相关标签

Copyright © 2003-2013 www.wpsshop.cn 版权所有，并保留所有权利。

  

闽ICP备14008679号