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