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_gpu.h"
8#include "panthor_hw.h"
9#include "panthor_pwr.h"
10#include "panthor_regs.h"
11
12#define GPU_PROD_ID_MAKE(arch_major, prod_major) \
13 (((arch_major) << 24) | (prod_major))
14
15/** struct panthor_hw_entry - HW arch major to panthor_hw binding entry */
16struct panthor_hw_entry {
17 /** @arch_min: Minimum supported architecture major value (inclusive) */
18 u8 arch_min;
19
20 /** @arch_max: Maximum supported architecture major value (inclusive) */
21 u8 arch_max;
22
23 /** @hwdev: Pointer to panthor_hw structure */
24 struct panthor_hw *hwdev;
25};
26
27static struct panthor_hw panthor_hw_arch_v10 = {
28 .ops = {
29 .soft_reset = panthor_gpu_soft_reset,
30 .l2_power_off = panthor_gpu_l2_power_off,
31 .l2_power_on = panthor_gpu_l2_power_on,
32 },
33};
34
35static struct panthor_hw panthor_hw_arch_v14 = {
36 .ops = {
37 .soft_reset = panthor_pwr_reset_soft,
38 .l2_power_off = panthor_pwr_l2_power_off,
39 .l2_power_on = panthor_pwr_l2_power_on,
40 },
41};
42
43static struct panthor_hw_entry panthor_hw_match[] = {
44 {
45 .arch_min = 10,
46 .arch_max = 13,
47 .hwdev = &panthor_hw_arch_v10,
48 },
49 {
50 .arch_min = 14,
51 .arch_max = 14,
52 .hwdev = &panthor_hw_arch_v14,
53 },
54};
55
56static char *get_gpu_model_name(struct panthor_device *ptdev)
57{
58 const u32 gpu_id = ptdev->gpu_info.gpu_id;
59 const u32 product_id = GPU_PROD_ID_MAKE(GPU_ARCH_MAJOR(gpu_id),
60 GPU_PROD_MAJOR(gpu_id));
61 const bool ray_intersection = !!(ptdev->gpu_info.gpu_features &
62 GPU_FEATURES_RAY_INTERSECTION);
63 const u8 shader_core_count = hweight64(ptdev->gpu_info.shader_present);
64
65 switch (product_id) {
66 case GPU_PROD_ID_MAKE(10, 2):
67 return "Mali-G710";
68 case GPU_PROD_ID_MAKE(10, 3):
69 return "Mali-G510";
70 case GPU_PROD_ID_MAKE(10, 4):
71 return "Mali-G310";
72 case GPU_PROD_ID_MAKE(10, 7):
73 return "Mali-G610";
74 case GPU_PROD_ID_MAKE(11, 2):
75 if (shader_core_count > 10 && ray_intersection)
76 return "Mali-G715-Immortalis";
77 else if (shader_core_count >= 7)
78 return "Mali-G715";
79
80 fallthrough;
81 case GPU_PROD_ID_MAKE(11, 3):
82 return "Mali-G615";
83 case GPU_PROD_ID_MAKE(12, 0):
84 if (shader_core_count >= 10 && ray_intersection)
85 return "Mali-G720-Immortalis";
86 else if (shader_core_count >= 6)
87 return "Mali-G720";
88
89 fallthrough;
90 case GPU_PROD_ID_MAKE(12, 1):
91 return "Mali-G620";
92 case GPU_PROD_ID_MAKE(13, 0):
93 if (shader_core_count >= 10 && ray_intersection)
94 return "Mali-G925-Immortalis";
95 else if (shader_core_count >= 6)
96 return "Mali-G725";
97
98 fallthrough;
99 case GPU_PROD_ID_MAKE(13, 1):
100 return "Mali-G625";
101 case GPU_PROD_ID_MAKE(14, 0):
102 return "Mali-G1-Ultra";
103 case GPU_PROD_ID_MAKE(14, 1):
104 return "Mali-G1-Premium";
105 case GPU_PROD_ID_MAKE(14, 3):
106 return "Mali-G1-Pro";
107 }
108
109 return "(Unknown Mali GPU)";
110}
111
112static void panthor_gpu_info_init(struct panthor_device *ptdev)
113{
114 unsigned int i;
115
116 ptdev->gpu_info.csf_id = gpu_read(ptdev, GPU_CSF_ID);
117 ptdev->gpu_info.gpu_rev = gpu_read(ptdev, GPU_REVID);
118 ptdev->gpu_info.core_features = gpu_read(ptdev, GPU_CORE_FEATURES);
119 ptdev->gpu_info.l2_features = gpu_read(ptdev, GPU_L2_FEATURES);
120 ptdev->gpu_info.tiler_features = gpu_read(ptdev, GPU_TILER_FEATURES);
121 ptdev->gpu_info.mem_features = gpu_read(ptdev, GPU_MEM_FEATURES);
122 ptdev->gpu_info.mmu_features = gpu_read(ptdev, GPU_MMU_FEATURES);
123 ptdev->gpu_info.thread_features = gpu_read(ptdev, GPU_THREAD_FEATURES);
124 ptdev->gpu_info.max_threads = gpu_read(ptdev, GPU_THREAD_MAX_THREADS);
125 ptdev->gpu_info.thread_max_workgroup_size = gpu_read(ptdev, GPU_THREAD_MAX_WORKGROUP_SIZE);
126 ptdev->gpu_info.thread_max_barrier_size = gpu_read(ptdev, GPU_THREAD_MAX_BARRIER_SIZE);
127 ptdev->gpu_info.coherency_features = gpu_read(ptdev, GPU_COHERENCY_FEATURES);
128 for (i = 0; i < 4; i++)
129 ptdev->gpu_info.texture_features[i] = gpu_read(ptdev, GPU_TEXTURE_FEATURES(i));
130
131 ptdev->gpu_info.as_present = gpu_read(ptdev, GPU_AS_PRESENT);
132
133 /* Introduced in arch 11.x */
134 ptdev->gpu_info.gpu_features = gpu_read64(ptdev, GPU_FEATURES);
135
136 if (panthor_hw_has_pwr_ctrl(ptdev)) {
137 /* Introduced in arch 14.x */
138 ptdev->gpu_info.l2_present = gpu_read64(ptdev, PWR_L2_PRESENT);
139 ptdev->gpu_info.tiler_present = gpu_read64(ptdev, PWR_TILER_PRESENT);
140 ptdev->gpu_info.shader_present = gpu_read64(ptdev, PWR_SHADER_PRESENT);
141 } else {
142 ptdev->gpu_info.shader_present = gpu_read64(ptdev, GPU_SHADER_PRESENT);
143 ptdev->gpu_info.tiler_present = gpu_read64(ptdev, GPU_TILER_PRESENT);
144 ptdev->gpu_info.l2_present = gpu_read64(ptdev, GPU_L2_PRESENT);
145 }
146}
147
148static void panthor_hw_info_init(struct panthor_device *ptdev)
149{
150 u32 major, minor, status;
151
152 panthor_gpu_info_init(ptdev);
153
154 major = GPU_VER_MAJOR(ptdev->gpu_info.gpu_id);
155 minor = GPU_VER_MINOR(ptdev->gpu_info.gpu_id);
156 status = GPU_VER_STATUS(ptdev->gpu_info.gpu_id);
157
158 drm_info(&ptdev->base,
159 "%s id 0x%x major 0x%x minor 0x%x status 0x%x",
160 get_gpu_model_name(ptdev), ptdev->gpu_info.gpu_id >> 16,
161 major, minor, status);
162
163 drm_info(&ptdev->base,
164 "Features: L2:%#x Tiler:%#x Mem:%#x MMU:%#x AS:%#x",
165 ptdev->gpu_info.l2_features,
166 ptdev->gpu_info.tiler_features,
167 ptdev->gpu_info.mem_features,
168 ptdev->gpu_info.mmu_features,
169 ptdev->gpu_info.as_present);
170
171 drm_info(&ptdev->base,
172 "shader_present=0x%0llx l2_present=0x%0llx tiler_present=0x%0llx",
173 ptdev->gpu_info.shader_present, ptdev->gpu_info.l2_present,
174 ptdev->gpu_info.tiler_present);
175}
176
177static int panthor_hw_bind_device(struct panthor_device *ptdev)
178{
179 struct panthor_hw *hdev = NULL;
180 const u32 arch_major = GPU_ARCH_MAJOR(ptdev->gpu_info.gpu_id);
181 int i = 0;
182
183 for (i = 0; i < ARRAY_SIZE(panthor_hw_match); i++) {
184 struct panthor_hw_entry *entry = &panthor_hw_match[i];
185
186 if (arch_major >= entry->arch_min && arch_major <= entry->arch_max) {
187 hdev = entry->hwdev;
188 break;
189 }
190 }
191
192 if (!hdev)
193 return -EOPNOTSUPP;
194
195 ptdev->hw = hdev;
196
197 return 0;
198}
199
200static int panthor_hw_gpu_id_init(struct panthor_device *ptdev)
201{
202 ptdev->gpu_info.gpu_id = gpu_read(ptdev, GPU_ID);
203 if (!ptdev->gpu_info.gpu_id)
204 return -ENXIO;
205
206 return 0;
207}
208
209int panthor_hw_init(struct panthor_device *ptdev)
210{
211 int ret = 0;
212
213 ret = panthor_hw_gpu_id_init(ptdev);
214 if (ret)
215 return ret;
216
217 ret = panthor_hw_bind_device(ptdev);
218 if (ret)
219 return ret;
220
221 panthor_hw_info_init(ptdev);
222
223 return 0;
224}
225

source code of linux/drivers/gpu/drm/panthor/panthor_hw.c