NoMali.py (10916:5c76426fd9ee) NoMali.py (11619:8bc53d5565ba)
1# Copyright (c) 2014-2015 ARM Limited
1# Copyright (c) 2014-2016 ARM Limited
2# All rights reserved.
3#
4# The license below extends only to copyright in the software and shall
5# not be construed as granting a license to any other intellectual
6# property including but not limited to intellectual property relating
7# to a hardware implementation of the functionality of the software
8# licensed hereunder. You may use the software subject to the license
9# terms below provided that you ensure that this notice is replicated

--- 46 unchanged lines hidden (view full) ---

56 gpu_type = Param.NoMaliGpuType("T760", "GPU type")
57 ver_maj = Param.UInt32(0, "GPU Version (Major)")
58 ver_min = Param.UInt32(0, "GPU Version (Minor)")
59 ver_status = Param.UInt32(0, "GPU Version (Status)")
60
61 int_gpu = Param.UInt32("Interrupt number for GPU interrupts")
62 int_job = Param.UInt32("Interrupt number for JOB interrupts")
63 int_mmu = Param.UInt32("Interrupt number for MMU interrupts")
2# All rights reserved.
3#
4# The license below extends only to copyright in the software and shall
5# not be construed as granting a license to any other intellectual
6# property including but not limited to intellectual property relating
7# to a hardware implementation of the functionality of the software
8# licensed hereunder. You may use the software subject to the license
9# terms below provided that you ensure that this notice is replicated

--- 46 unchanged lines hidden (view full) ---

56 gpu_type = Param.NoMaliGpuType("T760", "GPU type")
57 ver_maj = Param.UInt32(0, "GPU Version (Major)")
58 ver_min = Param.UInt32(0, "GPU Version (Minor)")
59 ver_status = Param.UInt32(0, "GPU Version (Status)")
60
61 int_gpu = Param.UInt32("Interrupt number for GPU interrupts")
62 int_job = Param.UInt32("Interrupt number for JOB interrupts")
63 int_mmu = Param.UInt32("Interrupt number for MMU interrupts")
64
65class CustomNoMaliGpu(NoMaliGpu):
66 """Base class for custom NoMali implementation that need to override
67 configuration registers. See CustomNoMaliT760 for a usage example.
68
69 """
70
71 type = 'CustomNoMaliGpu'
72 cxx_header = "dev/arm/gpu_nomali.hh"
73
74 gpu_id = Param.UInt32("")
75 l2_features = Param.UInt32("")
76 tiler_features = Param.UInt32("")
77 mem_features = Param.UInt32("")
78 mmu_features = Param.UInt32("")
79 as_present = Param.UInt32("")
80 js_present = Param.UInt32("")
81
82 thread_max_threads = Param.UInt32("")
83 thread_max_workgroup_size = Param.UInt32("")
84 thread_max_barrier_size = Param.UInt32("")
85 thread_features = Param.UInt32("")
86
87 texture_features = VectorParam.UInt32("")
88 js_features = VectorParam.UInt32("")
89
90 shader_present = Param.UInt64("")
91 tiler_present = Param.UInt64("")
92 l2_present = Param.UInt64("")
93
94class CustomNoMaliT760(CustomNoMaliGpu):
95 """Example NoMali T760 r0p0-0 configuration using the defaults from
96 the NoMali library.
97
98 """
99
100 gpu_id = 0x07500000
101
102 l2_features = 0x07130206
103 tiler_features = 0x00000809
104 mem_features = 0x00000001
105 mmu_features = 0x00002830
106 as_present = 0x000000ff
107 js_present = 0x00000007
108
109 thread_max_threads = 0x00000100
110 thread_max_workgroup_size = 0x00000100
111 thread_max_barrier_size = 0x00000100
112 thread_features = 0x0a040400
113
114 texture_features = [
115 0x00fe001e,
116 0x0000ffff,
117 0x9f81ffff,
118 ]
119 js_features = [
120 0x0000020e,
121 0x000001fe,
122 0x0000007e,
123 ]
124
125 shader_present = 0x0000000f
126 tiler_present = 0x00000001
127 l2_present = 0x00000001