05 - rocrtst 功能测试详解

本文档深入介绍rocrtst功能测试套件suites/functional/中的各个测试模块帮助你理解每个测试验证的 HSA API 功能。1. 功能测试概览功能测试注册在rocrtstFunc测试套件下共 26 个源码模块涵盖 ROCr Runtime 的核心 API。运行所有功能测试sudorocrtst64--gtest_filterrocrtstFunc.*按功能领域可分为以下 6 类功能测试 (rocrtstFunc) ├── 内存管理 ─── memory_basic / memory_allocation / memory_access │ memory_alignment / memory_atomics / metadata_prefetch │ svm_memory / virtual_memory ├── 队列与信号 ─ counted_queues / aql_barrier_bit │ signal_kernel / signal_concurrent ├── 设备管理 ─── agent_props / filter_devices / cu_masking / cuid ├── 生命周期 ─── concurrent_init / concurrent_shutdown │ concurrent_init_shutdown / reference_count ├── 进程与调试 ─ ipc / debug_basic / gpu_coredump └── 其他 ─────── deallocation_notifier / time_stamp / test_fault_example2. 内存管理类测试2.1 memory_basic — 基本内存操作源文件memory_basic.h/memory_basic.cc验证 HSA 内存池的基本查询和分配能力。测试用例说明Memory_Max_Mem测试单次最大内存分配量Memory_Available查询可用内存量sudorocrtst64--gtest_filterrocrtstFunc.Memory_Max_Mem:rocrtstFunc.Memory_Available涉及 APIhsa_amd_memory_pool_get_info()、hsa_amd_memory_pool_allocate()2.2 memory_allocation — 内存分配策略源文件memory_allocation.h/memory_allocation.cc测试不同内存分配场景。测试用例说明GroupMemoryAllocationTest动态组内存分配LDSMemoryAllocateAndFreeTest基本分配与释放MemoryAllocateContiguousTest连续内存分配sudorocrtst64--gtest_filterrocrtstFunc.*MemoryAllocat*:rocrtstFunc.*GroupMemory*涉及 APIhsa_amd_memory_pool_allocate()、hsa_amd_memory_pool_free()2.3 memory_access — 内存访问源文件memory_access.h/memory_access.cc验证 CPU 和 GPU 之间的交叉内存访问。测试用例说明MemoryAccessTestsCPU 访问 GPU 内存 GPU 访问 CPU 内存MemoryAccessCoherent一致性内存访问测试sudorocrtst64--gtest_filterrocrtstFunc.MemoryAccess*涉及 APIhsa_amd_agents_allow_access()、hsa_amd_memory_pool_allocate()2.4 memory_alignment — 内存对齐源文件memory_alignment.h/memory_alignment.cc测试用例说明Memory_Alignment_Test验证各内存池返回的对齐要求涉及 APIhsa_amd_memory_pool_get_info(HSA_AMD_MEMORY_POOL_INFO_RUNTIME_ALLOC_ALIGNMENT)2.5 memory_atomics — 内存原子操作源文件memory_atomics.h/memory_atomics.cc通过 GPU kernel 验证各种原子操作的正确性。测试用例原子操作Memory_Atomic_Add_Test原子加Memory_Atomic_Sub_Test原子减Memory_Atomic_And_Test原子与Memory_Atomic_Or_Test原子或Memory_Atomic_Xor_Test原子异或Memory_Atomic_Min_Test原子最小值Memory_Atomic_Max_Test原子最大值Memory_Atomic_Inc_Test原子自增Memory_Atomic_Dec_Test原子自减Memory_Atomic_Xchg_Test原子交换# 运行所有原子操作测试sudorocrtst64--gtest_filterrocrtstFunc.Memory_Atomic_*涉及 KernelatomicOperations_kernels.cl2.6 metadata_prefetch — 内存预取源文件metadata_prefetch.h/metadata_prefetch.cc测试用例说明Test_MetadataPrefetchPacket测试元数据预取 AQL 包涉及 APIAQL Vendor Specific 包提交2.7 svm_memory — 共享虚拟内存 (SVM)源文件svm_memory.h/svm_memory.cc验证 SVMShared Virtual Memory功能CPU 和 GPU 共享同一虚拟地址空间。测试用例说明SvmMemory_Basic_TestSVM 创建/销毁、预取、批量丢弃SvmMemory_Negative_TestSVM 丢弃操作的负面测试sudorocrtst64--gtest_filterrocrtstFunc.SvmMemory*涉及 APIhsa_amd_svm_attributes_set()、hsa_amd_svm_prefetch_async()⚠️ SVM 功能需要 GPU 和驱动支持通常 gfx90a 及 XNACK 模式。2.8 virtual_memory — 虚拟内存管理源文件virtual_memory.h/virtual_memory.cc测试 HSA 虚拟内存管理 API地址预留、物理内存映射等。测试用例说明VirtMemory_Basic_Test创建/销毁、引用计数、部分映射VirtMemory_Access_TestCPU↔GPU、GPU↔GPU 虚拟内存访问VirtMemory_Accounting_Test内存计量测试VirtMemory_Aliasing_Test虚拟地址别名多个VA映射同一物理页VirtMemory_Interprocess_Test虚拟内存跨进程共享sudorocrtst64--gtest_filterrocrtstFunc.VirtMemory_*涉及 APIhsa_amd_vmem_address_reserve()、hsa_amd_vmem_map()、hsa_amd_vmem_set_access()3. 队列与信号类测试3.1 counted_queues — 计数队列源文件counted_queues.h/counted_queues.cc测试 AMD 扩展的计数队列Counted QueueAPI。测试用例说明Counted_Queue_Basic_Test基本 API 创建/销毁Counted_Queue_Same_Priority_Max_Limit_Test同优先级最大队列数限制Counted_Queue_Invalid_Args_Test无效参数处理Counted_Queue_Multiple_Priorities_Limit_Test多优先级队列限制Counted_Queue_Set_Priority_Nack_Test设置优先级XNACK 模式Counted_Queue_Set_CUMask_Nack_Test设置 CU 掩码XNACK 模式Counted_Queue_Dispatch_Test队列任务分发Counted_Queue_Multithreaded_Dispatch_Test多线程分发Counted_Queue_Overflow_And_Wraparound_Test队列溢出与回绕sudorocrtst64--gtest_filterrocrtstFunc.Counted_Queue_*3.2 signal_concurrent — 信号并发操作源文件signal_concurrent.h/signal_concurrent.cc测试用例说明Signal_Destroy_Concurrently并发销毁信号Signal_Max_Consumer最大消费者数量Signal_Create_Concurrently并发创建信号sudorocrtst64--gtest_filterrocrtstFunc.Signal_*涉及 APIhsa_signal_create()、hsa_signal_destroy()3.3 signal_kernel — 信号与 Kernel 交互源文件signal_kernel.h/signal_kernel.cc测试 GPU kernel 中的信号操作目前为 DISABLED 状态。测试用例说明DISABLED_Signal_Kernel_SetKernel 中设置信号DISABLED_Signal_Kernel_Multi_SetKernel 中多次设置DISABLED_Signal_Kernel_WaitKernel 中等待信号DISABLED_Signal_Kernel_Multi_WaitKernel 中多重等待3.4 aql_barrier_bit — AQL 屏障位源文件aql_barrier_bit.h/aql_barrier_bit.cc测试 AQL 包中的 Barrier 位功能目前为 DISABLED 状态。测试用例说明DISABLED_Aql_Barrier_Bit_Set设置屏障位的行为验证DISABLED_Aql_Barrier_Bit_Not_Set未设置屏障位的行为验证4. 设备管理类测试4.1 agent_props — Agent 属性查询源文件agent_props.h/agent_props.cc测试用例说明AgentPropertiesTests查询 GPU 的 UUID 和时钟计数器sudorocrtst64--gtest_filterrocrtstFunc.AgentPropertiesTests涉及 APIhsa_agent_get_info()4.2 filter_devices — 设备过滤源文件filter_devices.h/filter_devices.cc测试用例说明Filter_Devices_Test验证ROCR_VISIBLE_DEVICES环境变量的过滤功能4.3 cu_masking — CU 掩码源文件cu_masking.h/cu_masking.cc测试用例说明DISABLED_CU_Masking设置计算单元掩码限制 kernel 使用的 CU 数量涉及 APIhsa_amd_queue_cu_set_mask()涉及 Kernelcu_mask_kernels.cl⚠️ 当前为 DISABLED 状态等待修复。4.4 cuid — CU 标识源文件cuid.h/cuid.cc测试用例说明Cuid_GPU_Validation_Test验证 GPU CU ID 功能需要编译时定义HSA_ENABLE_AMDCUID_SUPPORT宏。5. 生命周期类测试5.1 concurrent_init — 并发初始化源文件concurrent_init.h/concurrent_init.cc测试用例说明Concurrent_Init_Test多线程同时调用hsa_init()5.2 concurrent_shutdown — 并发关闭源文件concurrent_shutdown.h/concurrent_shutdown.cc测试用例说明Concurrent_Shutdown多线程同时调用hsa_shut_down()5.3 concurrent_init_shutdown — 并发初始化与关闭源文件concurrent_init_shutdown.h/concurrent_init_shutdown.cc测试用例说明Concurrent_Init_Shutdown_Test多线程交替执行 init 和 shutdown5.4 reference_count — 引用计数源文件reference_count.h/reference_count.cc测试用例说明Reference_Count验证hsa_init()/hsa_shut_down()的引用计数机制Max_Reference_Count测试最大引用计数sudorocrtst64--gtest_filterrocrtstFunc.Reference_Count:rocrtstFunc.Max_Reference_Count涉及 APIhsa_init()、hsa_shut_down()6. 进程与调试类测试6.1 ipc — 进程间通信源文件ipc.h/ipc.cc测试用例说明IPC测试跨进程的 GPU 内存共享涉及 APIhsa_amd_ipc_memory_create()、hsa_amd_ipc_memory_attach()6.2 debug_basic — 调试基础源文件debug_basic.h/debug_basic.cc测试用例说明DISABLED_DebugBasicTests使用 debug trap 指令的向量加法测试涉及 Kernelvector_add_debug_trap_kernel.cl6.3 gpu_coredump — GPU 核心转储源文件gpu_coredump.h/gpu_coredump.cc测试 GPU 发生故障时的核心转储功能。测试用例说明GpuCoreDump_DefaultPattern默认转储路径模式GpuCoreDump_CustomPattern自定义路径模式GpuCoreDump_DisableFlag禁用标志GpuCoreDump_PatternSubstitution路径模式中的变量替换GpuCoreDump_InvalidPath无效路径处理GpuCoreDump_ContentIntegrity转储内容完整性GpuCoreDump_PipePattern管道模式转储sudorocrtst64--gtest_filterrocrtstFunc.GpuCoreDump_*7. 其他功能测试7.1 deallocation_notifier — 内存释放通知源文件deallocation_notifier.h/deallocation_notifier.cc测试用例说明Deallocation_Notifier_Test注册和触发内存释放回调涉及 APIhsa_amd_register_deallocation_callback()7.2 time_stamp — 时间戳源文件time_stamp.h/time_stamp.cc测试用例说明Time_Stamp验证 HSA 系统时间戳的正确性涉及 APIhsa_system_get_info(HSA_SYSTEM_INFO_TIMESTAMP)7.3 test_fault_example — 故障处理示例源文件test_fault_example.h/test_fault_example.cc通用测试模板示例也作为新测试用例的参考。测试用例说明Test_Example标准测试流程示例Test_Example_InterruptDisabled禁用中断模式的测试示例8. 功能测试速查表筛选命令说明--gtest_filterrocrtstFunc.*全部功能测试--gtest_filterrocrtstFunc.*Memory*所有内存相关测试--gtest_filterrocrtstFunc.*Svm*SVM 测试--gtest_filterrocrtstFunc.*VirtMemory*虚拟内存测试--gtest_filterrocrtstFunc.*Signal*信号测试--gtest_filterrocrtstFunc.Counted_Queue_*计数队列测试--gtest_filterrocrtstFunc.*Concurrent*并发生命周期测试--gtest_filterrocrtstFunc.GpuCoreDump_*GPU 核心转储测试--gtest_filterrocrtstFunc.Memory_Atomic_*原子操作测试9. DISABLED 测试汇总以下测试默认不运行需要--gtest_also_run_disabled_tests参数测试禁用原因DISABLED_CU_Masking等待修复DISABLED_Signal_Kernel_*(4 个)信号 kernel 交互待完善DISABLED_Aql_Barrier_Bit_*(2 个)屏障位功能待完善DISABLED_DebugBasicTests调试功能依赖特定环境上一篇04-运行第一个测试下一篇06-性能测试详解 — 性能测试模块与数据解读