1 // SPDX-License-Identifier: GPL-2.0 or MIT 2 /* Copyright 2025 ARM Limited. All rights reserved. */ 3 4 #include "panthor_device.h" 5 #include "panthor_hw.h" 6 #include "panthor_regs.h" 7 8 #define GPU_PROD_ID_MAKE(arch_major, prod_major) \ 9 (((arch_major) << 24) | (prod_major)) 10 11 static char *get_gpu_model_name(struct panthor_device *ptdev) 12 { 13 const u32 gpu_id = ptdev->gpu_info.gpu_id; 14 const u32 product_id = GPU_PROD_ID_MAKE(GPU_ARCH_MAJOR(gpu_id), 15 GPU_PROD_MAJOR(gpu_id)); 16 const bool ray_intersection = !!(ptdev->gpu_info.gpu_features & 17 GPU_FEATURES_RAY_INTERSECTION); 18 const u8 shader_core_count = hweight64(ptdev->gpu_info.shader_present); 19 20 switch (product_id) { 21 case GPU_PROD_ID_MAKE(10, 2): 22 return "Mali-G710"; 23 case GPU_PROD_ID_MAKE(10, 3): 24 return "Mali-G510"; 25 case GPU_PROD_ID_MAKE(10, 4): 26 return "Mali-G310"; 27 case GPU_PROD_ID_MAKE(10, 7): 28 return "Mali-G610"; 29 case GPU_PROD_ID_MAKE(11, 2): 30 if (shader_core_count > 10 && ray_intersection) 31 return "Mali-G715-Immortalis"; 32 else if (shader_core_count >= 7) 33 return "Mali-G715"; 34 35 fallthrough; 36 case GPU_PROD_ID_MAKE(11, 3): 37 return "Mali-G615"; 38 case GPU_PROD_ID_MAKE(12, 0): 39 if (shader_core_count >= 10 && ray_intersection) 40 return "Mali-G720-Immortalis"; 41 else if (shader_core_count >= 6) 42 return "Mali-G720"; 43 44 fallthrough; 45 case GPU_PROD_ID_MAKE(12, 1): 46 return "Mali-G620"; 47 case GPU_PROD_ID_MAKE(13, 0): 48 if (shader_core_count >= 10 && ray_intersection) 49 return "Mali-G925-Immortalis"; 50 else if (shader_core_count >= 6) 51 return "Mali-G725"; 52 53 fallthrough; 54 case GPU_PROD_ID_MAKE(13, 1): 55 return "Mali-G625"; 56 } 57 58 return "(Unknown Mali GPU)"; 59 } 60 61 static void panthor_gpu_info_init(struct panthor_device *ptdev) 62 { 63 unsigned int i; 64 65 ptdev->gpu_info.gpu_id = gpu_read(ptdev, GPU_ID); 66 ptdev->gpu_info.csf_id = gpu_read(ptdev, GPU_CSF_ID); 67 ptdev->gpu_info.gpu_rev = gpu_read(ptdev, GPU_REVID); 68 ptdev->gpu_info.core_features = gpu_read(ptdev, GPU_CORE_FEATURES); 69 ptdev->gpu_info.l2_features = gpu_read(ptdev, GPU_L2_FEATURES); 70 ptdev->gpu_info.tiler_features = gpu_read(ptdev, GPU_TILER_FEATURES); 71 ptdev->gpu_info.mem_features = gpu_read(ptdev, GPU_MEM_FEATURES); 72 ptdev->gpu_info.mmu_features = gpu_read(ptdev, GPU_MMU_FEATURES); 73 ptdev->gpu_info.thread_features = gpu_read(ptdev, GPU_THREAD_FEATURES); 74 ptdev->gpu_info.max_threads = gpu_read(ptdev, GPU_THREAD_MAX_THREADS); 75 ptdev->gpu_info.thread_max_workgroup_size = gpu_read(ptdev, GPU_THREAD_MAX_WORKGROUP_SIZE); 76 ptdev->gpu_info.thread_max_barrier_size = gpu_read(ptdev, GPU_THREAD_MAX_BARRIER_SIZE); 77 ptdev->gpu_info.coherency_features = gpu_read(ptdev, GPU_COHERENCY_FEATURES); 78 for (i = 0; i < 4; i++) 79 ptdev->gpu_info.texture_features[i] = gpu_read(ptdev, GPU_TEXTURE_FEATURES(i)); 80 81 ptdev->gpu_info.as_present = gpu_read(ptdev, GPU_AS_PRESENT); 82 83 ptdev->gpu_info.shader_present = gpu_read64(ptdev, GPU_SHADER_PRESENT); 84 ptdev->gpu_info.tiler_present = gpu_read64(ptdev, GPU_TILER_PRESENT); 85 ptdev->gpu_info.l2_present = gpu_read64(ptdev, GPU_L2_PRESENT); 86 87 /* Introduced in arch 11.x */ 88 ptdev->gpu_info.gpu_features = gpu_read64(ptdev, GPU_FEATURES); 89 } 90 91 static void panthor_hw_info_init(struct panthor_device *ptdev) 92 { 93 u32 major, minor, status; 94 95 panthor_gpu_info_init(ptdev); 96 97 major = GPU_VER_MAJOR(ptdev->gpu_info.gpu_id); 98 minor = GPU_VER_MINOR(ptdev->gpu_info.gpu_id); 99 status = GPU_VER_STATUS(ptdev->gpu_info.gpu_id); 100 101 drm_info(&ptdev->base, 102 "%s id 0x%x major 0x%x minor 0x%x status 0x%x", 103 get_gpu_model_name(ptdev), ptdev->gpu_info.gpu_id >> 16, 104 major, minor, status); 105 106 drm_info(&ptdev->base, 107 "Features: L2:%#x Tiler:%#x Mem:%#x MMU:%#x AS:%#x", 108 ptdev->gpu_info.l2_features, 109 ptdev->gpu_info.tiler_features, 110 ptdev->gpu_info.mem_features, 111 ptdev->gpu_info.mmu_features, 112 ptdev->gpu_info.as_present); 113 114 drm_info(&ptdev->base, 115 "shader_present=0x%0llx l2_present=0x%0llx tiler_present=0x%0llx", 116 ptdev->gpu_info.shader_present, ptdev->gpu_info.l2_present, 117 ptdev->gpu_info.tiler_present); 118 } 119 120 int panthor_hw_init(struct panthor_device *ptdev) 121 { 122 panthor_hw_info_init(ptdev); 123 124 return 0; 125 } 126