Lines Matching refs:gpu_info
93 ptdev->gpu_info.gpu_id = gpu_read(ptdev, GPU_ID); in panthor_gpu_init_info()
94 ptdev->gpu_info.csf_id = gpu_read(ptdev, GPU_CSF_ID); in panthor_gpu_init_info()
95 ptdev->gpu_info.gpu_rev = gpu_read(ptdev, GPU_REVID); in panthor_gpu_init_info()
96 ptdev->gpu_info.core_features = gpu_read(ptdev, GPU_CORE_FEATURES); in panthor_gpu_init_info()
97 ptdev->gpu_info.l2_features = gpu_read(ptdev, GPU_L2_FEATURES); in panthor_gpu_init_info()
98 ptdev->gpu_info.tiler_features = gpu_read(ptdev, GPU_TILER_FEATURES); in panthor_gpu_init_info()
99 ptdev->gpu_info.mem_features = gpu_read(ptdev, GPU_MEM_FEATURES); in panthor_gpu_init_info()
100 ptdev->gpu_info.mmu_features = gpu_read(ptdev, GPU_MMU_FEATURES); in panthor_gpu_init_info()
101 ptdev->gpu_info.thread_features = gpu_read(ptdev, GPU_THREAD_FEATURES); in panthor_gpu_init_info()
102 ptdev->gpu_info.max_threads = gpu_read(ptdev, GPU_THREAD_MAX_THREADS); in panthor_gpu_init_info()
103 ptdev->gpu_info.thread_max_workgroup_size = gpu_read(ptdev, GPU_THREAD_MAX_WORKGROUP_SIZE); in panthor_gpu_init_info()
104 ptdev->gpu_info.thread_max_barrier_size = gpu_read(ptdev, GPU_THREAD_MAX_BARRIER_SIZE); in panthor_gpu_init_info()
105 ptdev->gpu_info.coherency_features = gpu_read(ptdev, GPU_COHERENCY_FEATURES); in panthor_gpu_init_info()
107 ptdev->gpu_info.texture_features[i] = gpu_read(ptdev, GPU_TEXTURE_FEATURES(i)); in panthor_gpu_init_info()
109 ptdev->gpu_info.as_present = gpu_read(ptdev, GPU_AS_PRESENT); in panthor_gpu_init_info()
111 ptdev->gpu_info.shader_present = gpu_read64(ptdev, GPU_SHADER_PRESENT); in panthor_gpu_init_info()
112 ptdev->gpu_info.tiler_present = gpu_read64(ptdev, GPU_TILER_PRESENT); in panthor_gpu_init_info()
113 ptdev->gpu_info.l2_present = gpu_read64(ptdev, GPU_L2_PRESENT); in panthor_gpu_init_info()
115 arch_major = GPU_ARCH_MAJOR(ptdev->gpu_info.gpu_id); in panthor_gpu_init_info()
116 product_major = GPU_PROD_MAJOR(ptdev->gpu_info.gpu_id); in panthor_gpu_init_info()
117 major = GPU_VER_MAJOR(ptdev->gpu_info.gpu_id); in panthor_gpu_init_info()
118 minor = GPU_VER_MINOR(ptdev->gpu_info.gpu_id); in panthor_gpu_init_info()
119 status = GPU_VER_STATUS(ptdev->gpu_info.gpu_id); in panthor_gpu_init_info()
129 model->name ?: "unknown", ptdev->gpu_info.gpu_id >> 16, in panthor_gpu_init_info()
134 ptdev->gpu_info.l2_features, in panthor_gpu_init_info()
135 ptdev->gpu_info.tiler_features, in panthor_gpu_init_info()
136 ptdev->gpu_info.mem_features, in panthor_gpu_init_info()
137 ptdev->gpu_info.mmu_features, in panthor_gpu_init_info()
138 ptdev->gpu_info.as_present); in panthor_gpu_init_info()
142 ptdev->gpu_info.shader_present, ptdev->gpu_info.l2_present, in panthor_gpu_init_info()
143 ptdev->gpu_info.tiler_present); in panthor_gpu_init_info()
211 pa_bits = GPU_MMU_FEATURES_PA_BITS(ptdev->gpu_info.mmu_features); in panthor_gpu_init()
320 if (ptdev->gpu_info.l2_present != 1) { in panthor_gpu_l2_power_on()
328 u64 core_mask = ~(ptdev->gpu_info.l2_present - 1) & in panthor_gpu_l2_power_on()
329 (ptdev->gpu_info.l2_present - 2); in panthor_gpu_l2_power_on()
332 hweight64(ptdev->gpu_info.shader_present)); in panthor_gpu_l2_power_on()