87 	ptdev->gpu_info.gpu_id = gpu_read(ptdev, GPU_ID);  in panthor_gpu_init_info()
88 	ptdev->gpu_info.csf_id = gpu_read(ptdev, GPU_CSF_ID);  in panthor_gpu_init_info()
89 	ptdev->gpu_info.gpu_rev = gpu_read(ptdev, GPU_REVID);  in panthor_gpu_init_info()
90 	ptdev->gpu_info.core_features = gpu_read(ptdev, GPU_CORE_FEATURES);  in panthor_gpu_init_info()
91 	ptdev->gpu_info.l2_features = gpu_read(ptdev, GPU_L2_FEATURES);  in panthor_gpu_init_info()
92 	ptdev->gpu_info.tiler_features = gpu_read(ptdev, GPU_TILER_FEATURES);  in panthor_gpu_init_info()
93 	ptdev->gpu_info.mem_features = gpu_read(ptdev, GPU_MEM_FEATURES);  in panthor_gpu_init_info()
94 	ptdev->gpu_info.mmu_features = gpu_read(ptdev, GPU_MMU_FEATURES);  in panthor_gpu_init_info()
95 	ptdev->gpu_info.thread_features = gpu_read(ptdev, GPU_THREAD_FEATURES);  in panthor_gpu_init_info()
96 	ptdev->gpu_info.max_threads = gpu_read(ptdev, GPU_THREAD_MAX_THREADS);  in panthor_gpu_init_info()
97 	ptdev->gpu_info.thread_max_workgroup_size = gpu_read(ptdev, GPU_THREAD_MAX_WORKGROUP_SIZE);  in panthor_gpu_init_info()
98 	ptdev->gpu_info.thread_max_barrier_size = gpu_read(ptdev, GPU_THREAD_MAX_BARRIER_SIZE);  in panthor_gpu_init_info()
99 	ptdev->gpu_info.coherency_features = gpu_read(ptdev, GPU_COHERENCY_FEATURES);  in panthor_gpu_init_info()
101 		ptdev->gpu_info.texture_features[i] = gpu_read(ptdev, GPU_TEXTURE_FEATURES(i));  in panthor_gpu_init_info()
103 	ptdev->gpu_info.as_present = gpu_read(ptdev, GPU_AS_PRESENT);  in panthor_gpu_init_info()
105 	ptdev->gpu_info.shader_present = gpu_read(ptdev, GPU_SHADER_PRESENT_LO);  in panthor_gpu_init_info()
106 	ptdev->gpu_info.shader_present |= (u64)gpu_read(ptdev, GPU_SHADER_PRESENT_HI) << 32;  in panthor_gpu_init_info()
108 	ptdev->gpu_info.tiler_present = gpu_read(ptdev, GPU_TILER_PRESENT_LO);  in panthor_gpu_init_info()
109 	ptdev->gpu_info.tiler_present |= (u64)gpu_read(ptdev, GPU_TILER_PRESENT_HI) << 32;  in panthor_gpu_init_info()
111 	ptdev->gpu_info.l2_present = gpu_read(ptdev, GPU_L2_PRESENT_LO);  in panthor_gpu_init_info()
112 	ptdev->gpu_info.l2_present |= (u64)gpu_read(ptdev, GPU_L2_PRESENT_HI) << 32;  in panthor_gpu_init_info()
148 		u32 fault_status = gpu_read(ptdev, GPU_FAULT_STATUS);  in panthor_gpu_irq_handler()
149 		u64 address = ((u64)gpu_read(ptdev, GPU_FAULT_ADDR_HI) << 32) |  in panthor_gpu_irq_handler()
150 			      gpu_read(ptdev, GPU_FAULT_ADDR_LO);  in panthor_gpu_irq_handler()
399 		    !(gpu_read(ptdev, GPU_INT_RAWSTAT) & GPU_IRQ_CLEAN_CACHES_COMPLETED))  in panthor_gpu_flush_caches()
439 		    !(gpu_read(ptdev, GPU_INT_RAWSTAT) & GPU_IRQ_RESET_COMPLETED))  in panthor_gpu_soft_reset()