From bca6272f79877458413f316b63d829e82bb4cbc5 Mon Sep 17 00:00:00 2001 From: Wookey Date: Fri, 16 Feb 2018 01:58:08 +0000 Subject: Use upstream source layout --- .../gpu/arm/midgard/mali_kbase_gpuprops_types.h | 94 ++++++++++++++++++++++ 1 file changed, 94 insertions(+) create mode 100755 driver/product/kernel/drivers/gpu/arm/midgard/mali_kbase_gpuprops_types.h (limited to 'driver/product/kernel/drivers/gpu/arm/midgard/mali_kbase_gpuprops_types.h') diff --git a/driver/product/kernel/drivers/gpu/arm/midgard/mali_kbase_gpuprops_types.h b/driver/product/kernel/drivers/gpu/arm/midgard/mali_kbase_gpuprops_types.h new file mode 100755 index 0000000..920cf77 --- /dev/null +++ b/driver/product/kernel/drivers/gpu/arm/midgard/mali_kbase_gpuprops_types.h @@ -0,0 +1,94 @@ +/* + * + * (C) COPYRIGHT 2011-2016 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 licence. + * + * A copy of the licence is included with the program, and can also be obtained + * from Free Software Foundation, Inc., 51 Franklin Street, Fifth Floor, + * Boston, MA 02110-1301, USA. + * + */ + + + + + +/** + * @file mali_kbase_gpuprops_types.h + * Base kernel property query APIs + */ + +#ifndef _KBASE_GPUPROPS_TYPES_H_ +#define _KBASE_GPUPROPS_TYPES_H_ + +#include "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 suspend_size; /* API 8.2+ */ + 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 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; +}; + +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 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; + + /** + * Implementation specific irq throttle value (us), should be adjusted during integration. + */ + int irq_throttle_time_us; + + /* Properties shared with userspace */ + base_gpu_props props; +}; + +#endif /* _KBASE_GPUPROPS_TYPES_H_ */ -- cgit v1.2.3