CoCalc -- GECommandTable.cpp

CoCalc provides the best real-time collaborative environment for Jupyter Notebooks, LaTeX documents, and SageMath, scalable from individual users to large groups and classes!

GitHub Repository: hrydgard/ppsspp
Path: blob/master/GPU/Debugger/GECommandTable.cpp
Views: ¹⁴⁰¹
1
// Copyright (c) 2022- PPSSPP Project.
2

3
// This program is free software: you can redistribute it and/or modify
4
// it under the terms of the GNU General Public License as published by
5
// the Free Software Foundation, version 2.0 or later versions.
6

7
// This program is distributed in the hope that it will be useful,
8
// but WITHOUT ANY WARRANTY; without even the implied warranty of
9
// MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
10
// GNU General Public License 2.0 for more details.
11

12
// A copy of the GPL 2.0 should have been included with the program.
13
// If not, see http://www.gnu.org/licenses/
14

15
// Official git repository and contact information can be found at
16
// https://github.com/hrydgard/ppsspp and http://www.ppsspp.org/.
17

18
#include <cstring>
19
#include "Common/Common.h"
20
#include "Common/Log.h"
21
#include "GPU/Debugger/GECommandTable.h"
22
#include "GPU/ge_constants.h"
23

24
struct GECmdAlias {
25
	GECommand reg;
26
	const char *aliases[3];
27
};
28

29
static constexpr GECmdInfo geCmdInfo[] = {
30
	{ GE_CMD_NOP, "nop", GECmdFormat::NONE },
31
	{ GE_CMD_VADDR, "setvaddr", GECmdFormat::RELATIVE_ADDR },
32
	{ GE_CMD_IADDR, "setiaddr", GECmdFormat::RELATIVE_ADDR },
33
	{ GE_CMD_UNKNOWN_03, "unknown03", GECmdFormat::NONE },
34
	{ GE_CMD_PRIM, "prim", GECmdFormat::PRIM },
35
	{ GE_CMD_BEZIER, "bezier", GECmdFormat::BEZIER },
36
	{ GE_CMD_SPLINE, "spline", GECmdFormat::SPLINE },
37
	{ GE_CMD_BOUNDINGBOX, "btest", GECmdFormat::PRIM },
38
	{ GE_CMD_JUMP, "jump", GECmdFormat::JUMP },
39
	{ GE_CMD_BJUMP, "bjump", GECmdFormat::JUMP },
40
	{ GE_CMD_CALL, "call", GECmdFormat::JUMP },
41
	{ GE_CMD_RET, "ret", GECmdFormat::NONE },
42
	{ GE_CMD_END, "end", GECmdFormat::DATA16 },
43
	{ GE_CMD_UNKNOWN_0D, "unknown0d", GECmdFormat::NONE },
44
	{ GE_CMD_SIGNAL, "signal", GECmdFormat::SIGNAL },
45
	{ GE_CMD_FINISH, "finish", GECmdFormat::NONE },
46
	{ GE_CMD_BASE, "base", GECmdFormat::HIGH_ADDR_ONLY },
47
	{ GE_CMD_UNKNOWN_11, "unknown11", GECmdFormat::NONE },
48
	{ GE_CMD_VERTEXTYPE, "vtype", GECmdFormat::VERTEX_TYPE },
49
	{ GE_CMD_OFFSETADDR, "setoffset", GECmdFormat::OFFSET_ADDR },
50
	{ GE_CMD_ORIGIN, "origin", GECmdFormat::NONE },
51
	{ GE_CMD_REGION1, "regionrate", GECmdFormat::X10_Y10 },
52
	{ GE_CMD_REGION2, "regionstop", GECmdFormat::X10_Y10 },
53
	{ GE_CMD_LIGHTINGENABLE, "lighting_on", GECmdFormat::FLAG },
54
	{ GE_CMD_LIGHTENABLE0, "light0_on", GECmdFormat::FLAG },
55
	{ GE_CMD_LIGHTENABLE1, "light1_on", GECmdFormat::FLAG },
56
	{ GE_CMD_LIGHTENABLE2, "light2_on", GECmdFormat::FLAG },
57
	{ GE_CMD_LIGHTENABLE3, "light3_on", GECmdFormat::FLAG },
58
	{ GE_CMD_DEPTHCLAMPENABLE, "zclamp_on", GECmdFormat::FLAG },
59
	{ GE_CMD_CULLFACEENABLE, "cull_on", GECmdFormat::FLAG },
60
	{ GE_CMD_TEXTUREMAPENABLE, "tex_on", GECmdFormat::FLAG },
61
	{ GE_CMD_FOGENABLE, "fog_on", GECmdFormat::FLAG },
62
	{ GE_CMD_DITHERENABLE, "dither_on", GECmdFormat::FLAG },
63
	{ GE_CMD_ALPHABLENDENABLE, "ablend_on", GECmdFormat::FLAG },
64
	{ GE_CMD_ALPHABLENDENABLE, "atest_on", GECmdFormat::FLAG },
65
	{ GE_CMD_ZTESTENABLE, "ztest_on", GECmdFormat::FLAG },
66
	{ GE_CMD_STENCILTESTENABLE, "stest_on", GECmdFormat::FLAG },
67
	{ GE_CMD_ANTIALIASENABLE, "antialias_on", GECmdFormat::FLAG },
68
	{ GE_CMD_PATCHCULLENABLE, "patchcull_on", GECmdFormat::FLAG },
69
	{ GE_CMD_COLORTESTENABLE, "ctest_on", GECmdFormat::FLAG },
70
	{ GE_CMD_LOGICOPENABLE, "logicop_on", GECmdFormat::FLAG },
71
	{ GE_CMD_UNKNOWN_29, "unknown29", GECmdFormat::NONE },
72
	{ GE_CMD_BONEMATRIXNUMBER, "bonemtxnum", GECmdFormat::BONE_NUM },
73
	{ GE_CMD_BONEMATRIXDATA, "bonemtxdata", GECmdFormat::FLOAT },
74
	{ GE_CMD_MORPHWEIGHT0, "morph0", GECmdFormat::FLOAT },
75
	{ GE_CMD_MORPHWEIGHT1, "morph1", GECmdFormat::FLOAT },
76
	{ GE_CMD_MORPHWEIGHT2, "morph2", GECmdFormat::FLOAT },
77
	{ GE_CMD_MORPHWEIGHT3, "morph3", GECmdFormat::FLOAT },
78
	{ GE_CMD_MORPHWEIGHT4, "morph4", GECmdFormat::FLOAT },
79
	{ GE_CMD_MORPHWEIGHT5, "morph5", GECmdFormat::FLOAT },
80
	{ GE_CMD_MORPHWEIGHT6, "morph6", GECmdFormat::FLOAT },
81
	{ GE_CMD_MORPHWEIGHT7, "morph7", GECmdFormat::FLOAT },
82
	{ GE_CMD_UNKNOWN_34, "unknown34", GECmdFormat::NONE },
83
	{ GE_CMD_UNKNOWN_35, "unknown35", GECmdFormat::NONE },
84
	{ GE_CMD_PATCHDIVISION, "patchdivision", GECmdFormat::PATCH_DIVISION },
85
	{ GE_CMD_PATCHPRIMITIVE, "patchprim", GECmdFormat::PATCH_PRIM },
86
	{ GE_CMD_PATCHFACING, "patchreversenormals", GECmdFormat::FLAG },
87
	{ GE_CMD_UNKNOWN_39, "unknown39", GECmdFormat::NONE },
88
	{ GE_CMD_WORLDMATRIXNUMBER, "worldmtxnum", GECmdFormat::MATRIX_NUM },
89
	{ GE_CMD_WORLDMATRIXDATA, "worldmtxdata", GECmdFormat::FLOAT },
90
	{ GE_CMD_VIEWMATRIXNUMBER, "viewmtxnum", GECmdFormat::MATRIX_NUM },
91
	{ GE_CMD_VIEWMATRIXDATA, "viewmtxdata", GECmdFormat::FLOAT },
92
	{ GE_CMD_PROJMATRIXNUMBER, "projmtxnum", GECmdFormat::MATRIX_NUM },
93
	{ GE_CMD_PROJMATRIXDATA, "projmtxdata", GECmdFormat::FLOAT },
94
	{ GE_CMD_TGENMATRIXNUMBER, "texgenmtxnum", GECmdFormat::MATRIX_NUM },
95
	{ GE_CMD_TGENMATRIXDATA, "texgenmtxdata", GECmdFormat::FLOAT },
96
	{ GE_CMD_VIEWPORTXSCALE, "vpxscale", GECmdFormat::FLOAT },
97
	{ GE_CMD_VIEWPORTYSCALE, "vpyscale", GECmdFormat::FLOAT },
98
	{ GE_CMD_VIEWPORTZSCALE, "vpzscale", GECmdFormat::FLOAT },
99
	{ GE_CMD_VIEWPORTXCENTER, "vpxcenter", GECmdFormat::FLOAT },
100
	{ GE_CMD_VIEWPORTYCENTER, "vpycenter", GECmdFormat::FLOAT },
101
	{ GE_CMD_VIEWPORTZCENTER, "vpzcenter", GECmdFormat::FLOAT },
102
	{ GE_CMD_TEXSCALEU, "texscaleu", GECmdFormat::FLOAT },
103
	{ GE_CMD_TEXSCALEV, "texscalev", GECmdFormat::FLOAT },
104
	{ GE_CMD_TEXOFFSETU, "texoffsetu", GECmdFormat::FLOAT },
105
	{ GE_CMD_TEXOFFSETV, "texoffsetv", GECmdFormat::FLOAT },
106
	{ GE_CMD_OFFSETX, "offsetx", GECmdFormat::SUBPIXEL_COORD },
107
	{ GE_CMD_OFFSETY, "offsety", GECmdFormat::SUBPIXEL_COORD },
108
	{ GE_CMD_UNKNOWN_4E, "unknown4e", GECmdFormat::NONE },
109
	{ GE_CMD_UNKNOWN_4F, "unknown4f", GECmdFormat::NONE },
110
	// Really shade mode, but using gouraud as the default so it can be 1/0.
111
	{ GE_CMD_SHADEMODE, "gouraud", GECmdFormat::FLAG },
112
	{ GE_CMD_REVERSENORMAL, "reversenormals", GECmdFormat::FLAG },
113
	{ GE_CMD_UNKNOWN_52, "unknown52", GECmdFormat::NONE },
114
	{ GE_CMD_MATERIALUPDATE, "materialupdate", GECmdFormat::MATERIAL_UPDATE },
115
	{ GE_CMD_MATERIALEMISSIVE, "materialemissive", GECmdFormat::RGB },
116
	{ GE_CMD_MATERIALAMBIENT, "materialambient", GECmdFormat::RGB },
117
	{ GE_CMD_MATERIALDIFFUSE, "materialdiffuse", GECmdFormat::RGB },
118
	{ GE_CMD_MATERIALSPECULAR, "materialspecular", GECmdFormat::RGB },
119
	{ GE_CMD_MATERIALALPHA, "materialambienta", GECmdFormat::DATA8 },
120
	{ GE_CMD_UNKNOWN_59, "unknown59", GECmdFormat::NONE },
121
	{ GE_CMD_UNKNOWN_5A, "unknown5a", GECmdFormat::NONE },
122
	{ GE_CMD_MATERIALSPECULARCOEF, "specularcoef", GECmdFormat::FLOAT },
123
	{ GE_CMD_AMBIENTCOLOR, "ambient", GECmdFormat::RGB },
124
	{ GE_CMD_AMBIENTALPHA, "ambienta", GECmdFormat::DATA8 },
125
	{ GE_CMD_LIGHTMODE, "lightseparate", GECmdFormat::FLAG },
126
	{ GE_CMD_LIGHTTYPE0, "ltype0", GECmdFormat::LIGHT_TYPE },
127
	{ GE_CMD_LIGHTTYPE1, "ltype1", GECmdFormat::LIGHT_TYPE },
128
	{ GE_CMD_LIGHTTYPE2, "ltype2", GECmdFormat::LIGHT_TYPE },
129
	{ GE_CMD_LIGHTTYPE3, "ltype3", GECmdFormat::LIGHT_TYPE },
130
	{ GE_CMD_LX0, "light0posx", GECmdFormat::FLOAT },
131
	{ GE_CMD_LY0, "light0posy", GECmdFormat::FLOAT },
132
	{ GE_CMD_LZ0, "light0posz", GECmdFormat::FLOAT },
133
	{ GE_CMD_LX1, "light1posx", GECmdFormat::FLOAT },
134
	{ GE_CMD_LY1, "light1posy", GECmdFormat::FLOAT },
135
	{ GE_CMD_LZ1, "light1posz", GECmdFormat::FLOAT },
136
	{ GE_CMD_LX2, "light2posx", GECmdFormat::FLOAT },
137
	{ GE_CMD_LY2, "light2posy", GECmdFormat::FLOAT },
138
	{ GE_CMD_LZ2, "light2posz", GECmdFormat::FLOAT },
139
	{ GE_CMD_LX3, "light3posx", GECmdFormat::FLOAT },
140
	{ GE_CMD_LY3, "light3posy", GECmdFormat::FLOAT },
141
	{ GE_CMD_LZ3, "light3posz", GECmdFormat::FLOAT },
142
	{ GE_CMD_LDX0, "light0dirx", GECmdFormat::FLOAT },
143
	{ GE_CMD_LDY0, "light0diry", GECmdFormat::FLOAT },
144
	{ GE_CMD_LDZ0, "light0dirz", GECmdFormat::FLOAT },
145
	{ GE_CMD_LDX1, "light1dirx", GECmdFormat::FLOAT },
146
	{ GE_CMD_LDY1, "light1diry", GECmdFormat::FLOAT },
147
	{ GE_CMD_LDZ1, "light1dirz", GECmdFormat::FLOAT },
148
	{ GE_CMD_LDX2, "light2dirx", GECmdFormat::FLOAT },
149
	{ GE_CMD_LDY2, "light2diry", GECmdFormat::FLOAT },
150
	{ GE_CMD_LDZ2, "light2dirz", GECmdFormat::FLOAT },
151
	{ GE_CMD_LDX3, "light3dirx", GECmdFormat::FLOAT },
152
	{ GE_CMD_LDY3, "light3diry", GECmdFormat::FLOAT },
153
	{ GE_CMD_LDZ3, "light3dirz", GECmdFormat::FLOAT },
154
	{ GE_CMD_LKA0, "light0attpow0", GECmdFormat::FLOAT },
155
	{ GE_CMD_LKB0, "light0attpow1", GECmdFormat::FLOAT },
156
	{ GE_CMD_LKC0, "light0attpow2", GECmdFormat::FLOAT },
157
	{ GE_CMD_LKA1, "light1attpow0", GECmdFormat::FLOAT },
158
	{ GE_CMD_LKB1, "light1attpow1", GECmdFormat::FLOAT },
159
	{ GE_CMD_LKC1, "light1attpow2", GECmdFormat::FLOAT },
160
	{ GE_CMD_LKA2, "light2attpow0", GECmdFormat::FLOAT },
161
	{ GE_CMD_LKB2, "light2attpow1", GECmdFormat::FLOAT },
162
	{ GE_CMD_LKC2, "light2attpow2", GECmdFormat::FLOAT },
163
	{ GE_CMD_LKA3, "light3attpow0", GECmdFormat::FLOAT },
164
	{ GE_CMD_LKB3, "light3attpow1", GECmdFormat::FLOAT },
165
	{ GE_CMD_LKC3, "light3attpow2", GECmdFormat::FLOAT },
166
	{ GE_CMD_LKS0, "light0spotexp", GECmdFormat::FLOAT },
167
	{ GE_CMD_LKS1, "light1spotexp", GECmdFormat::FLOAT },
168
	{ GE_CMD_LKS2, "light2spotexp", GECmdFormat::FLOAT },
169
	{ GE_CMD_LKS3, "light3spotexp", GECmdFormat::FLOAT },
170
	{ GE_CMD_LKO0, "light0spotcutoff", GECmdFormat::FLOAT },
171
	{ GE_CMD_LKO1, "light1spotcutoff", GECmdFormat::FLOAT },
172
	{ GE_CMD_LKO2, "light2spotcutoff", GECmdFormat::FLOAT },
173
	{ GE_CMD_LKO3, "light3spotcutoff", GECmdFormat::FLOAT },
174
	{ GE_CMD_LAC0, "light0ambient", GECmdFormat::RGB },
175
	{ GE_CMD_LDC0, "light0diffuse", GECmdFormat::RGB },
176
	{ GE_CMD_LSC0, "light0specular", GECmdFormat::RGB },
177
	{ GE_CMD_LAC1, "light1ambient", GECmdFormat::RGB },
178
	{ GE_CMD_LDC1, "light1diffuse", GECmdFormat::RGB },
179
	{ GE_CMD_LSC1, "light1specular", GECmdFormat::RGB },
180
	{ GE_CMD_LAC2, "light2ambient", GECmdFormat::RGB },
181
	{ GE_CMD_LDC2, "light2diffuse", GECmdFormat::RGB },
182
	{ GE_CMD_LSC2, "light2specular", GECmdFormat::RGB },
183
	{ GE_CMD_LAC3, "light3ambient", GECmdFormat::RGB },
184
	{ GE_CMD_LDC3, "light3diffuse", GECmdFormat::RGB },
185
	{ GE_CMD_LSC3, "light3specular", GECmdFormat::RGB },
186
	{ GE_CMD_CULL, "cullccw", GECmdFormat::FLAG },
187
	{ GE_CMD_FRAMEBUFPTR, "fbptr", GECmdFormat::LOW_ADDR_ONLY },
188
	{ GE_CMD_FRAMEBUFWIDTH, "fbstride", GECmdFormat::STRIDE },
189
	{ GE_CMD_ZBUFPTR, "zbptr", GECmdFormat::LOW_ADDR_ONLY },
190
	{ GE_CMD_ZBUFWIDTH, "zbstride", GECmdFormat::STRIDE },
191
	{ GE_CMD_TEXADDR0, "texaddr0low", GECmdFormat::LOW_ADDR },
192
	{ GE_CMD_TEXADDR1, "texaddr1low", GECmdFormat::LOW_ADDR },
193
	{ GE_CMD_TEXADDR2, "texaddr2low", GECmdFormat::LOW_ADDR },
194
	{ GE_CMD_TEXADDR3, "texaddr3low", GECmdFormat::LOW_ADDR },
195
	{ GE_CMD_TEXADDR4, "texaddr4low", GECmdFormat::LOW_ADDR },
196
	{ GE_CMD_TEXADDR5, "texaddr5low", GECmdFormat::LOW_ADDR },
197
	{ GE_CMD_TEXADDR6, "texaddr6low", GECmdFormat::LOW_ADDR },
198
	{ GE_CMD_TEXADDR7, "texaddr7low", GECmdFormat::LOW_ADDR },
199
	{ GE_CMD_TEXBUFWIDTH0, "texbufw0", GECmdFormat::STRIDE_HIGH_ADDR },
200
	{ GE_CMD_TEXBUFWIDTH1, "texbufw1", GECmdFormat::STRIDE_HIGH_ADDR },
201
	{ GE_CMD_TEXBUFWIDTH2, "texbufw2", GECmdFormat::STRIDE_HIGH_ADDR },
202
	{ GE_CMD_TEXBUFWIDTH3, "texbufw3", GECmdFormat::STRIDE_HIGH_ADDR },
203
	{ GE_CMD_TEXBUFWIDTH4, "texbufw4", GECmdFormat::STRIDE_HIGH_ADDR },
204
	{ GE_CMD_TEXBUFWIDTH5, "texbufw5", GECmdFormat::STRIDE_HIGH_ADDR },
205
	{ GE_CMD_TEXBUFWIDTH6, "texbufw6", GECmdFormat::STRIDE_HIGH_ADDR },
206
	{ GE_CMD_TEXBUFWIDTH7, "texbufw7", GECmdFormat::STRIDE_HIGH_ADDR },
207
	{ GE_CMD_CLUTADDR, "clutaddrlow", GECmdFormat::LOW_ADDR },
208
	{ GE_CMD_CLUTADDRUPPER, "clutaddrhigh", GECmdFormat::HIGH_ADDR },
209
	{ GE_CMD_TRANSFERSRC, "transfersrclow", GECmdFormat::LOW_ADDR },
210
	{ GE_CMD_TRANSFERSRCW, "transfersrcstride", GECmdFormat::STRIDE_HIGH_ADDR },
211
	{ GE_CMD_TRANSFERDST, "transferdstlow", GECmdFormat::LOW_ADDR },
212
	{ GE_CMD_TRANSFERDSTW, "transferdststride", GECmdFormat::STRIDE_HIGH_ADDR },
213
	{ GE_CMD_UNKNOWN_B6, "unknownb6", GECmdFormat::NONE },
214
	{ GE_CMD_UNKNOWN_B7, "unknownb7", GECmdFormat::NONE },
215
	{ GE_CMD_TEXSIZE0, "texsize0", GECmdFormat::TEX_SIZE },
216
	{ GE_CMD_TEXSIZE1, "texsize1", GECmdFormat::TEX_SIZE },
217
	{ GE_CMD_TEXSIZE2, "texsize2", GECmdFormat::TEX_SIZE },
218
	{ GE_CMD_TEXSIZE3, "texsize3", GECmdFormat::TEX_SIZE },
219
	{ GE_CMD_TEXSIZE4, "texsize4", GECmdFormat::TEX_SIZE },
220
	{ GE_CMD_TEXSIZE5, "texsize5", GECmdFormat::TEX_SIZE },
221
	{ GE_CMD_TEXSIZE6, "texsize6", GECmdFormat::TEX_SIZE },
222
	{ GE_CMD_TEXSIZE7, "texsize7", GECmdFormat::TEX_SIZE },
223
	{ GE_CMD_TEXMAPMODE, "texmapmode", GECmdFormat::TEX_MAP_MODE },
224
	{ GE_CMD_TEXSHADELS, "texlightsrc", GECmdFormat::TEX_LIGHT_SRC },
225
	{ GE_CMD_TEXMODE, "texmode", GECmdFormat::TEX_MODE },
226
	{ GE_CMD_TEXFORMAT, "texformat", GECmdFormat::TEX_FORMAT },
227
	{ GE_CMD_LOADCLUT, "loadclut", GECmdFormat::CLUT_BLOCKS },
228
	{ GE_CMD_CLUTFORMAT, "clutformat", GECmdFormat::CLUT_FORMAT },
229
	{ GE_CMD_TEXFILTER, "texfilter", GECmdFormat::TEX_FILTER },
230
	{ GE_CMD_TEXWRAP, "texclamp", GECmdFormat::TEX_CLAMP },
231
	{ GE_CMD_TEXLEVEL, "texlevelmode", GECmdFormat::TEX_LEVEL_MODE },
232
	{ GE_CMD_TEXFUNC, "texfunc", GECmdFormat::TEX_FUNC },
233
	{ GE_CMD_TEXENVCOLOR, "texenv", GECmdFormat::RGB },
234
	{ GE_CMD_TEXFLUSH, "texflush", GECmdFormat::NONE },
235
	{ GE_CMD_TEXSYNC, "texsync", GECmdFormat::NONE },
236
	{ GE_CMD_FOG1, "fogend", GECmdFormat::FLOAT },
237
	{ GE_CMD_FOG2, "fogslope", GECmdFormat::FLOAT },
238
	{ GE_CMD_FOGCOLOR, "fogcolor", GECmdFormat::RGB },
239
	{ GE_CMD_TEXLODSLOPE, "texlodslope", GECmdFormat::FLOAT },
240
	{ GE_CMD_UNKNOWN_D1, "unknownd1", GECmdFormat::NONE },
241
	{ GE_CMD_FRAMEBUFPIXFORMAT, "fbformat", GECmdFormat::TEX_FORMAT },
242
	{ GE_CMD_CLEARMODE, "clearmode", GECmdFormat::CLEAR_MODE },
243
	{ GE_CMD_SCISSOR1, "scissor1", GECmdFormat::X10_Y10 },
244
	{ GE_CMD_SCISSOR2, "scissor2", GECmdFormat::X10_Y10 },
245
	{ GE_CMD_MINZ, "minz", GECmdFormat::DATA16 },
246
	{ GE_CMD_MAXZ, "maxz", GECmdFormat::DATA16 },
247
	{ GE_CMD_COLORTEST, "ctestfunc", GECmdFormat::COLOR_TEST_FUNC },
248
	{ GE_CMD_COLORREF, "ctestref", GECmdFormat::RGB },
249
	{ GE_CMD_COLORTESTMASK, "ctestmask", GECmdFormat::RGB },
250
	{ GE_CMD_ALPHATEST, "atest", GECmdFormat::ALPHA_TEST },
251
	{ GE_CMD_STENCILTEST, "stest", GECmdFormat::ALPHA_TEST },
252
	{ GE_CMD_STENCILOP, "stencilop", GECmdFormat::STENCIL_OP },
253
	{ GE_CMD_ZTEST, "ztest", GECmdFormat::DEPTH_TEST_FUNC },
254
	{ GE_CMD_BLENDMODE, "blendmode", GECmdFormat::BLEND_MODE },
255
	{ GE_CMD_BLENDFIXEDA, "blendfixa", GECmdFormat::RGB },
256
	{ GE_CMD_BLENDFIXEDB, "blendfixb", GECmdFormat::RGB },
257
	{ GE_CMD_DITH0, "dither0", GECmdFormat::DITHER_ROW },
258
	{ GE_CMD_DITH1, "dither1", GECmdFormat::DITHER_ROW },
259
	{ GE_CMD_DITH2, "dither2", GECmdFormat::DITHER_ROW },
260
	{ GE_CMD_DITH3, "dither3", GECmdFormat::DITHER_ROW },
261
	{ GE_CMD_LOGICOP, "logicop", GECmdFormat::LOGIC_OP },
262
	{ GE_CMD_ZWRITEDISABLE, "zwrite_off", GECmdFormat::FLAG },
263
	{ GE_CMD_MASKRGB, "rgbmask_block", GECmdFormat::RGB },
264
	{ GE_CMD_MASKALPHA, "swritemask_block", GECmdFormat::DATA8 },
265
	{ GE_CMD_TRANSFERSTART, "transferstart_bpp", GECmdFormat::FLAG },
266
	{ GE_CMD_TRANSFERSRCPOS, "transfersrcpos", GECmdFormat::X10_Y10 },
267
	{ GE_CMD_TRANSFERDSTPOS, "transferdstpos", GECmdFormat::X10_Y10 },
268
	{ GE_CMD_UNKNOWN_ED, "unknowned", GECmdFormat::NONE },
269
	{ GE_CMD_TRANSFERSIZE, "transfersize", GECmdFormat::X10_Y10 },
270
	{ GE_CMD_UNKNOWN_EF, "unknownef", GECmdFormat::NONE },
271
	{ GE_CMD_VSCX, "immx", GECmdFormat::SUBPIXEL_COORD },
272
	{ GE_CMD_VSCY, "immy", GECmdFormat::SUBPIXEL_COORD },
273
	{ GE_CMD_VSCZ, "immz", GECmdFormat::DATA16 },
274
	{ GE_CMD_VTCS, "imms", GECmdFormat::FLOAT },
275
	{ GE_CMD_VTCT, "immt", GECmdFormat::FLOAT },
276
	{ GE_CMD_VTCQ, "immq", GECmdFormat::FLOAT },
277
	{ GE_CMD_VCV, "immrgb", GECmdFormat::RGB },
278
	{ GE_CMD_VAP, "imma_prim", GECmdFormat::ALPHA_PRIM },
279
	{ GE_CMD_VFC, "immfog", GECmdFormat::DATA8 },
280
	{ GE_CMD_VSCV, "immrgb1", GECmdFormat::RGB },
281
	{ GE_CMD_UNKNOWN_FA, "unknownfa", GECmdFormat::NONE },
282
	{ GE_CMD_UNKNOWN_FB, "unknownfb", GECmdFormat::NONE },
283
	{ GE_CMD_UNKNOWN_FC, "unknownfc", GECmdFormat::NONE },
284
	{ GE_CMD_UNKNOWN_FD, "unknownfd", GECmdFormat::NONE },
285
	{ GE_CMD_UNKNOWN_FE, "unknownfe", GECmdFormat::NONE },
286
	{ GE_CMD_NOP_FF, "nopff", GECmdFormat::NONE },
287
};
288

289
static constexpr GECmdAlias geCmdAliases[] = {
290
	{ GE_CMD_VADDR, { "vertexaddr" } },
291
	{ GE_CMD_IADDR, { "indexaddr" } },
292
	{ GE_CMD_BOUNDINGBOX, { "boundingbox", "boundtest" } },
293
	{ GE_CMD_BJUMP, { "boundjump" } },
294
	{ GE_CMD_BASE, { "baseaddr" } },
295
	{ GE_CMD_VERTEXTYPE, { "vertextype" } },
296
	{ GE_CMD_OFFSETADDR, { "offsetaddr" } },
297
	{ GE_CMD_REGION2, { "region2" } },
298
	{ GE_CMD_LIGHTINGENABLE, { "lightingenable", "lighting" } },
299
	{ GE_CMD_LIGHTENABLE0, { "light0enable" } },
300
	{ GE_CMD_LIGHTENABLE1, { "light1enable" } },
301
	{ GE_CMD_LIGHTENABLE2, { "light2enable" } },
302
	{ GE_CMD_LIGHTENABLE3, { "light3enable" } },
303
	{ GE_CMD_DEPTHCLAMPENABLE, { "zclampenable", "depthclamp_on", "depthclampenable" } },
304
	{ GE_CMD_CULLFACEENABLE, { "cullenable", "cullface_on", "cullfaceenable" } },
305
	{ GE_CMD_TEXTUREMAPENABLE, { "texenable", "texture_on", "textureenable" } },
306
	{ GE_CMD_FOGENABLE, { "fogenable" } },
307
	{ GE_CMD_DITHERENABLE, { "ditherenable" } },
308
	{ GE_CMD_ALPHABLENDENABLE, { "ablendenable", "alphablend_on", "alphablendenable" } },
309
	{ GE_CMD_ALPHABLENDENABLE, { "atestenable", "alphatest_on", "alphatestenable" } },
310
	{ GE_CMD_ZTESTENABLE, { "ztestenable", "depthtest_on", "depthtest_enable" } },
311
	{ GE_CMD_STENCILTESTENABLE, { "stestenable", "stenciltest_on", "stenciltestenable" } },
312
	{ GE_CMD_ANTIALIASENABLE, { "antialiasenable", "antialias" } },
313
	{ GE_CMD_PATCHCULLENABLE, { "patchcullenable" } },
314
	{ GE_CMD_COLORTESTENABLE, { "ctestenable", "colortest_on", "colortestenable" } },
315
	{ GE_CMD_LOGICOPENABLE, { "logicopenable" } },
316
	{ GE_CMD_BONEMATRIXNUMBER, { "bonematrixnum" } },
317
	{ GE_CMD_BONEMATRIXDATA, { "bonematrixdata" } },
318
	{ GE_CMD_MORPHWEIGHT0, { "morphweight0" } },
319
	{ GE_CMD_MORPHWEIGHT1, { "morphweight1" } },
320
	{ GE_CMD_MORPHWEIGHT2, { "morphweight2" } },
321
	{ GE_CMD_MORPHWEIGHT3, { "morphweight3" } },
322
	{ GE_CMD_MORPHWEIGHT4, { "morphweight4" } },
323
	{ GE_CMD_MORPHWEIGHT5, { "morphweight5" } },
324
	{ GE_CMD_MORPHWEIGHT6, { "morphweight6" } },
325
	{ GE_CMD_MORPHWEIGHT7, { "morphweight7" } },
326
	{ GE_CMD_PATCHDIVISION, { "patchdiv" } },
327
	{ GE_CMD_PATCHFACING, { "patchreversenormal" } },
328
	{ GE_CMD_WORLDMATRIXNUMBER, { "worldmatrixnum" } },
329
	{ GE_CMD_WORLDMATRIXDATA, { "worldmatrixdata" } },
330
	{ GE_CMD_VIEWMATRIXNUMBER, { "viewmatrixnum" } },
331
	{ GE_CMD_VIEWMATRIXDATA, { "viewmatrixdata" } },
332
	{ GE_CMD_PROJMATRIXNUMBER, { "projmatrixnum" } },
333
	{ GE_CMD_PROJMATRIXDATA, { "projmatrixdata" } },
334
	{ GE_CMD_TGENMATRIXNUMBER, { "texgenmatrixnum", "tgenmtxnum", "tgenmatrixnum" } },
335
	{ GE_CMD_TGENMATRIXDATA, { "texgenmatrixdata", "tgenmtxdata", "tgenmatrixdata" } },
336
	{ GE_CMD_VIEWPORTXSCALE, { "viewportxscale" } },
337
	{ GE_CMD_VIEWPORTYSCALE, { "viewportyscale" } },
338
	{ GE_CMD_VIEWPORTZSCALE, { "viewportzscale" } },
339
	{ GE_CMD_VIEWPORTXCENTER, { "viewportxcenter" } },
340
	{ GE_CMD_VIEWPORTYCENTER, { "viewportycenter" } },
341
	{ GE_CMD_VIEWPORTZCENTER, { "viewportzcenter" } },
342
	{ GE_CMD_SHADEMODE, { "shademode", "shading" } },
343
	{ GE_CMD_REVERSENORMAL, { "reversenormal" } },
344
	{ GE_CMD_MATERIALAMBIENT, { "materialambientrgb" } },
345
	{ GE_CMD_MATERIALALPHA, { "materialambientalpha" } },
346
	{ GE_CMD_MATERIALSPECULARCOEF, { "materialspecularcoef" } },
347
	{ GE_CMD_AMBIENTCOLOR, { "ambientrgb" } },
348
	{ GE_CMD_AMBIENTALPHA, { "ambientalpha" } },
349
	{ GE_CMD_LIGHTMODE, { "lmode", "secondarycolor" } },
350
	{ GE_CMD_LIGHTTYPE0, { "lighttype0" } },
351
	{ GE_CMD_LIGHTTYPE1, { "lighttype1" } },
352
	{ GE_CMD_LIGHTTYPE2, { "lighttype2" } },
353
	{ GE_CMD_LIGHTTYPE3, { "lighttype3" } },
354
	{ GE_CMD_FRAMEBUFPTR, { "framebufptr" } },
355
	{ GE_CMD_FRAMEBUFWIDTH, { "fbwidth", "framebufstride", "framebufwidth" } },
356
	{ GE_CMD_ZBUFPTR, { "depthbufptr" } },
357
	{ GE_CMD_ZBUFWIDTH, { "zbwidth", "depthbufstride", "depthbufwidth" } },
358
	{ GE_CMD_TEXBUFWIDTH0, { "texbufwidth0", "texstride0" } },
359
	{ GE_CMD_TEXBUFWIDTH1, { "texbufwidth1", "texstride1" } },
360
	{ GE_CMD_TEXBUFWIDTH2, { "texbufwidth2", "texstride2" } },
361
	{ GE_CMD_TEXBUFWIDTH3, { "texbufwidth3", "texstride3" } },
362
	{ GE_CMD_TEXBUFWIDTH4, { "texbufwidth4", "texstride4" } },
363
	{ GE_CMD_TEXBUFWIDTH5, { "texbufwidth5", "texstride5" } },
364
	{ GE_CMD_TEXBUFWIDTH6, { "texbufwidth6", "texstride6" } },
365
	{ GE_CMD_TEXBUFWIDTH7, { "texbufwidth7", "texstride7" } },
366
	{ GE_CMD_CLUTADDRUPPER, { "clutaddrupper" } },
367
	{ GE_CMD_TEXSHADELS, { "texshadels" } },
368
	{ GE_CMD_TEXWRAP, { "texwrap" } },
369
	{ GE_CMD_FOGCOLOR, { "fogrgb" } },
370
	{ GE_CMD_FRAMEBUFPIXFORMAT, { "framebufformat" } },
371
	{ GE_CMD_CLEARMODE, { "clear" } },
372
	{ GE_CMD_SCISSOR1, { "scissortl" } },
373
	{ GE_CMD_SCISSOR2, { "scissorbr" } },
374
	{ GE_CMD_COLORTEST, { "colortestfunc" } },
375
	{ GE_CMD_COLORREF, { "colortestref" } },
376
	{ GE_CMD_COLORTESTMASK, { "colortestmask" } },
377
	{ GE_CMD_ALPHATEST, { "alphatest" } },
378
	{ GE_CMD_STENCILTEST, { "stenciltest" } },
379
	{ GE_CMD_ZTEST, { "depthtest" } },
380
	{ GE_CMD_BLENDFIXEDA, { "blendfixsrc" } },
381
	{ GE_CMD_BLENDFIXEDB, { "blendfixdst" } },
382
	{ GE_CMD_ZWRITEDISABLE, { "depthwrite_off", "zwritedisable", "depthwritedisable" } },
383
	{ GE_CMD_MASKRGB, { "rgbmask" } },
384
	{ GE_CMD_MASKALPHA, { "swritemask", "amask", "amask_block" } },
385
	{ GE_CMD_TRANSFERSTART, { "transferstart" } },
386
	{ GE_CMD_VCV, { "immrgb0" } },
387
	{ GE_CMD_VSCV, { "immsecondaryrgb" } },
388
};
389

390
bool GECmdInfoByName(const char *name, GECmdInfo &result) {
391
	for (const GECmdInfo &info : geCmdInfo) {
392
		if (strcasecmp(info.name, name) == 0) {
393
			result = info;
394
			return true;
395
		}
396
	}
397

398
	for (const GECmdAlias &entry : geCmdAliases) {
399
		for (const char *alias : entry.aliases) {
400
			if (alias && strcasecmp(alias, name) == 0) {
401
				result = GECmdInfoByCmd(entry.reg);
402
				return true;
403
			}
404
		}
405
	}
406

407
	return false;
408
}
409

410
GECmdInfo GECmdInfoByCmd(GECommand reg) {
411
	_assert_msg_((reg & 0xFF) == reg, "Invalid reg");
412
	return geCmdInfo[reg & 0xFF];
413
}
414

415
CoCalc provides the best real-time collaborative environment for Jupyter Notebooks, LaTeX documents, and SageMath, scalable from individual users to large groups and classes!

Product

Resources

Company
