src/dev/arm/NoMali.py

   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
  10 # unmodified and in its entirety in all distributions of the software,
  11 # modified or unmodified, in source code or in binary form.
  12 #
  13 # Redistribution and use in source and binary forms, with or without
  14 # modification, are permitted provided that the following conditions are
  15 # met: redistributions of source code must retain the above copyright
  16 # notice, this list of conditions and the following disclaimer;
  17 # redistributions in binary form must reproduce the above copyright
  18 # notice, this list of conditions and the following disclaimer in the
  19 # documentation and/or other materials provided with the distribution;
  20 # neither the name of the copyright holders nor the names of its
  21 # contributors may be used to endorse or promote products derived from
  22 # this software without specific prior written permission.
  23 #
  24 # THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS
  25 # "AS IS" AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT
  26 # LIMITED TO, THE IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR
  27 # A PARTICULAR PURPOSE ARE DISCLAIMED. IN NO EVENT SHALL THE COPYRIGHT
  28 # OWNER OR CONTRIBUTORS BE LIABLE FOR ANY DIRECT, INDIRECT, INCIDENTAL,
  29 # SPECIAL, EXEMPLARY, OR CONSEQUENTIAL DAMAGES (INCLUDING, BUT NOT
  30 # LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE,
  31 # DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY
  32 # THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT
  33 # (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE
  34 # OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
  35 #
  36 # Authors: Andreas Sandberg
  37
  38 from m5.params import *
  39 from Device import BasicPioDevice
  40 from Gic import *
  41
  42 class NoMaliGpuType(Enum): vals = [
  43     'T60x',
  44     'T62x',
  45     'T760',
  46     ]
  47
  48 class NoMaliGpu(PioDevice):
  49     type = 'NoMaliGpu'
  50     cxx_header = "dev/arm/gpu_nomali.hh"
  51
  52     pio_addr = Param.Addr("Device base address")
  53
  54     platform = Param.RealView(Parent.any, "Platform this device is part of.")
  55
  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
  65 class 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
  94 class 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