blob: 67a4d7da03ff79d4c0fab7a3644d390124c11fca (
plain)
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
108
109
110
111
112
113
114
115
116
117
118
119
120
121
122
123
124
125
126
127
128
129
130
131
132
133
134
135
136
137
138
139
140
141
142
143
144
145
146
147
148
149
150
151
152
153
154
155
156
157
158
159
160
161
162
163
164
165
166
167
168
169
170
|
/* SPDX-License-Identifier: GPL-2.0 WITH Linux-syscall-note */
/*
*
* (C) COPYRIGHT 2011-2018, 2020-2021 ARM Limited. All rights reserved.
*
* This program is free software and is provided to you under the terms of the
* GNU General Public License version 2 as published by the Free Software
* Foundation, and any use by you of this program is subject to the terms
* of such GNU license.
*
* This program is distributed in the hope that it will be useful,
* but WITHOUT ANY WARRANTY; without even the implied warranty of
* MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the
* GNU General Public License for more details.
*
* You should have received a copy of the GNU General Public License
* along with this program; if not, you can access it online at
* http://www.gnu.org/licenses/gpl-2.0.html.
*
*/
/**
* DOC: Base kernel property query APIs
*/
#ifndef _KBASE_GPUPROPS_TYPES_H_
#define _KBASE_GPUPROPS_TYPES_H_
#include <uapi/gpu/arm/midgard/mali_base_kernel.h>
#define KBASE_GPU_SPEED_MHZ 123
#define KBASE_GPU_PC_SIZE_LOG2 24U
struct kbase_gpuprops_regdump {
u32 gpu_id;
u32 l2_features;
u32 l2_config;
u32 l2_asn_hash[ASN_HASH_COUNT];
u32 core_features;
u32 tiler_features;
u32 mem_features;
u32 mmu_features;
u32 as_present;
u32 js_present;
u32 thread_max_threads;
u32 thread_max_workgroup_size;
u32 thread_max_barrier_size;
u32 thread_features;
u32 thread_tls_alloc;
u32 texture_features[BASE_GPU_NUM_TEXTURE_FEATURES_REGISTERS];
u32 js_features[GPU_MAX_JOB_SLOTS];
u32 shader_present_lo;
u32 shader_present_hi;
u32 tiler_present_lo;
u32 tiler_present_hi;
u32 l2_present_lo;
u32 l2_present_hi;
u32 stack_present_lo;
u32 stack_present_hi;
u32 coherency_features;
u32 gpu_features_lo;
u32 gpu_features_hi;
};
/**
* struct kbase_current_config_regdump - Register dump for current resources
* allocated to the GPU.
* @mem_features: Memory system features. Contains information about the
* features of the memory system. Used here to get the L2 slice
* count.
* @shader_present_lo: Shader core present bitmap. Low word.
* @shader_present_hi: Shader core present bitmap. High word.
* @l2_present_lo: L2 cache present bitmap. Low word.
* @l2_present_hi: L2 cache present bitmap. High word.
*
* Register dump structure used to store the resgisters data realated to the
* current resources allocated to the GPU.
*/
struct kbase_current_config_regdump {
u32 mem_features;
u32 shader_present_lo;
u32 shader_present_hi;
u32 l2_present_lo;
u32 l2_present_hi;
};
struct kbase_gpu_cache_props {
u8 associativity;
u8 external_bus_width;
};
struct kbase_gpu_mem_props {
u8 core_group;
};
struct kbase_gpu_mmu_props {
u8 va_bits;
u8 pa_bits;
};
/**
* struct max_config_props - Properties based on the maximum resources
* available.
* @l2_slices: Maximum number of L2 slices that can be assinged to the GPU
* during runtime.
* @padding: Padding to a multiple of 64 bits.
* @core_mask: Largest core mask bitmap that can be assigned to the GPU during
* runtime.
*
* Properties based on the maximum resources available (not necessarly
* allocated at that moment). Used to provide the maximum configuration to the
* userspace allowing the applications to allocate enough resources in case the
* real allocated resources change.
*/
struct max_config_props {
u8 l2_slices;
u8 padding[3];
u32 core_mask;
};
/**
* struct curr_config_props - Properties based on the current resources
* allocated to the GPU.
* @l2_present: Current L2 present bitmap that is allocated to the GPU.
* @shader_present: Current shader present bitmap that is allocated to the GPU.
* @num_cores: Current number of shader cores allocated to the GPU.
* @l2_slices: Current number of L2 slices allocated to the GPU.
* @update_needed: Defines if it is necessary to re-read the registers to
* update the current allocated resources.
* @padding: Padding to a multiple of 64 bits.
*
* Properties based on the current resource available. Used for operations with
* hardware interactions to avoid using userspace data that can be based on
* the maximum resource available.
*/
struct curr_config_props {
u64 l2_present;
u64 shader_present;
u16 num_cores;
u8 l2_slices;
bool update_needed;
u8 padding[4];
};
struct kbase_gpu_props {
/* kernel-only properties */
u8 num_cores;
u8 num_core_groups;
u8 num_address_spaces;
u8 num_job_slots;
struct kbase_gpu_cache_props l2_props;
struct kbase_gpu_mem_props mem;
struct kbase_gpu_mmu_props mmu;
/* Properties based on the current resource available */
struct curr_config_props curr_config;
/* Properties based on the maximum resource available */
struct max_config_props max_config;
/* Properties shared with userspace */
struct base_gpu_props props;
u32 prop_buffer_size;
void *prop_buffer;
};
#endif /* _KBASE_GPUPROPS_TYPES_H_ */
|
