source/gles2glide64/src/Glide64/rdp.h

   1 /*
   2 * Glide64 - Glide video plugin for Nintendo 64 emulators.
   3 * Copyright (c) 2002  Dave2001
   4 * Copyright (c) 2003-2009  Sergey 'Gonetz' Lipski
   5 *
   6 * This program is free software; you can redistribute it and/or modify
   7 * it under the terms of the GNU General Public License as published by
   8 * the Free Software Foundation; either version 2 of the License, or
   9 * any later version.
  10 *
  11 * This program is distributed in the hope that it will be useful,
  12 * but WITHOUT ANY WARRANTY; without even the implied warranty of
  13 * MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE.  See the
  14 * GNU General Public License for more details.
  15 *
  16 * You should have received a copy of the GNU General Public License
  17 * along with this program; if not, write to the Free Software
  18 * Foundation, Inc., 59 Temple Place, Suite 330, Boston, MA  02111-1307  USA
  19 */
  20
  21 //****************************************************************
  22 //
  23 // Glide64 - Glide Plugin for Nintendo 64 emulators
  24 // Project started on December 29th, 2001
  25 //
  26 // Authors:
  27 // Dave2001, original author, founded the project in 2001, left it in 2002
  28 // Gugaman, joined the project in 2002, left it in 2002
  29 // Sergey 'Gonetz' Lipski, joined the project in 2002, main author since fall of 2002
  30 // Hiroshi 'KoolSmoky' Morii, joined the project in 2007
  31 //
  32 //****************************************************************
  33 //
  34 // To modify Glide64:
  35 // * Write your name and (optional)email, commented by your work, so I know who did it, and so that you can find which parts you modified when it comes time to send it to me.
  36 // * Do NOT send me the whole project or file that you modified.  Take out your modified code sections, and tell me where to put them.  If people sent the whole thing, I would have many different versions, but no idea how to combine them all.
  37 //
  38 //****************************************************************
  39
  40 #ifndef RDP_H
  41 #define RDP_H
  42
  43 extern char out_buf[2048];
  44
  45 extern wxUint32 frame_count; // frame counter
  46
  47 //GlideHQ support
  48 #ifdef TEXTURE_FILTER
  49 #include "../GlideHQ/Ext_TxFilter.h"
  50 #endif
  51
  52 #define MAX_CACHE   1024*4
  53 #define MAX_TRI_CACHE 768 // this is actually # of vertices, not triangles
  54 #define MAX_VTX     256
  55
  56 #define MAX_TMU     2
  57
  58 #define TEXMEM_2MB_EDGE 2097152
  59
  60 // Supported flags
  61 #define SUP_TEXMIRROR 0x00000001
  62
  63 // Clipping flags
  64 #define CLIP_XMAX 0x00000001
  65 #define CLIP_XMIN 0x00000002
  66 #define CLIP_YMAX 0x00000004
  67 #define CLIP_YMIN 0x00000008
  68 #define CLIP_WMIN 0x00000010
  69 #define CLIP_ZMAX 0x00000020
  70 #define CLIP_ZMIN 0x00000040
  71
  72 // Flags
  73 #define ZBUF_ENABLED  0x00000001
  74 #define ZBUF_DECAL    0x00000002
  75 #define ZBUF_COMPARE  0x00000004
  76 #define ZBUF_UPDATE   0x00000008
  77 #define ALPHA_COMPARE 0x00000010
  78 #define FORCE_BL      0x00000020
  79 #define CULL_FRONT    0x00001000  // * must be here
  80 #define CULL_BACK     0x00002000  // * must be here
  81 #define FOG_ENABLED   0x00010000
  82
  83 #define CULLMASK    0x00003000
  84 #define CULLSHIFT   12
  85
  86 // Update flags
  87 #define UPDATE_ZBUF_ENABLED 0x00000001
  88
  89 #define UPDATE_TEXTURE    0x00000002  // \ Same thing!
  90 #define UPDATE_COMBINE    0x00000002  // /
  91
  92 #define UPDATE_CULL_MODE  0x00000004
  93 #define UPDATE_LIGHTS     0x00000010
  94 #define UPDATE_BIASLEVEL  0x00000020
  95 #define UPDATE_ALPHA_COMPARE  0x00000040
  96 #define UPDATE_VIEWPORT   0x00000080
  97 #define UPDATE_MULT_MAT   0x00000100
  98 #define UPDATE_SCISSOR    0x00000200
  99 #define UPDATE_FOG_ENABLED  0x00010000
 100
 101 #define CMB_MULT    0x00000001
 102 #define CMB_SET     0x00000002
 103 #define CMB_SUB     0x00000004
 104 #define CMB_ADD     0x00000008
 105 #define CMB_A_MULT  0x00000010
 106 #define CMB_A_SET   0x00000020
 107 #define CMB_A_SUB   0x00000040
 108 #define CMB_A_ADD   0x00000080
 109 #define CMB_SETSHADE_SHADEALPHA 0x00000100
 110 #define CMB_INTER   0x00000200
 111 #define CMB_MULT_OWN_ALPHA  0x00000400
 112 #define CMB_COL_SUB_OWN  0x00000800
 113
 114 #define uc(x) coord[x<<1]
 115 #define vc(x) coord[(x<<1)+1]
 116
 117 #if defined(_MSC_VER)
 118 #define DECLAREALIGN16VAR(var) __declspec(align(16)) float var
 119 #elif defined(__GNUG__)
 120 #define DECLAREALIGN16VAR(var) float (var) __attribute__ ((aligned(16)))
 121 #endif
 122
 123 #ifdef __ARM_NEON__
 124 #include "arm_neon.h"
 125 #endif
 126
 127 // Vertex structure
 128 typedef struct
 129 {
 130   float x, y, z, q;
 131   float u0, v0, u1, v1;
 132   float coord[4];
 133   float w;
 134   wxUint16  flags;
 135
 136   wxUint8  b;  // These values are arranged like this so that *(wxUint32*)(VERTEX+?) is
 137   wxUint8  g;  // ARGB format that glide can use.
 138   wxUint8  r;
 139   wxUint8  a;
 140
 141   float f; //fog
 142
 143   float vec[3]; // normal vector
 144
 145   float sx, sy, sz;
 146   float x_w, y_w, z_w, u0_w, v0_w, u1_w, v1_w, oow;
 147   wxUint8  not_zclipped;
 148   wxUint8  screen_translated;
 149   wxUint8  uv_scaled;
 150   wxUint32 uv_calculated;  // like crc
 151   wxUint32 shade_mod;
 152   wxUint32 color_backup;
 153
 154   float ou, ov;
 155
 156   int   number;   // way to identify it
 157   int   scr_off, z_off; // off the screen?
 158 } VERTEX;
 159
 160 // Clipping (scissors)
 161 typedef struct {
 162   wxUint32 ul_x;
 163   wxUint32 ul_y;
 164   wxUint32 lr_x;
 165   wxUint32 lr_y;
 166 } SCISSOR;
 167
 168 #ifdef TEXTURE_FILTER
 169 extern wxUint32 texfltr[];
 170 extern wxUint32 texenht[];
 171 extern wxUint32 texcmpr[];
 172 extern wxUint32 texhirs[];
 173
 174 typedef struct {
 175   wxUint16 tile_ul_s;
 176   wxUint16 tile_ul_t;
 177   wxUint16 tile_width;
 178   wxUint16 tile_height;
 179   wxUint16 tex_width;
 180   wxUint16 tex_size;
 181   wxUint32 dxt;
 182 } LOAD_TILE_INFO;
 183 #endif
 184
 185 // #warning no screenshot support
 186 /*
 187 typedef struct {
 188   const wxChar * format;
 189   const wxChar * extension;
 190   wxBitmapType type;
 191 } SCREEN_SHOT_FORMAT;
 192
 193 extern const int NumOfFormats;
 194 extern SCREEN_SHOT_FORMAT ScreenShotFormats[];
 195 */
 196 typedef struct {
 197   int card_id;
 198   int lang_id;
 199
 200   wxUint32 res_x, scr_res_x;
 201   wxUint32 res_y, scr_res_y;
 202   wxUint32 res_data, res_data_org;
 203
 204   int advanced_options;
 205   int texenh_options;
 206   int ssformat;
 207   int vsync;
 208
 209   int show_fps;
 210   int clock;
 211   int clock_24_hr;
 212
 213   int filtering;
 214   int fog;
 215   int buff_clear;
 216   int swapmode;
 217   int lodmode;
 218 #ifdef PAULSCODE
 219   int autoframeskip;
 220   int maxframeskip;
 221 #endif
 222   int aspectmode;
 223   int use_hotkeys;
 224
 225   //Frame buffer emulation options
 226   #define  fb_emulation            (1<<0)   //frame buffer emulation
 227   #define  fb_hwfbe                (1<<1)   //hardware frame buffer emualtion
 228   #define  fb_motionblur           (1<<2)   //emulate motion blur
 229   #define  fb_ref                  (1<<3)   //read every frame
 230   #define  fb_read_alpha           (1<<4)   //read alpha
 231   #define  fb_hwfbe_buf_clear      (1<<5)   //clear auxiliary texture frame buffers
 232   #define  fb_depth_render         (1<<6)   //enable software depth render
 233   #define  fb_optimize_texrect     (1<<7)   //fast texrect rendering with hwfbe
 234   #define  fb_ignore_aux_copy      (1<<8)   //do not copy auxiliary frame buffers
 235   #define  fb_useless_is_useless   (1<<10)  //
 236   #define  fb_get_info             (1<<11)  //get frame buffer info
 237   #define  fb_read_back_to_screen  (1<<12)  //render N64 frame buffer to screen
 238   #define  fb_read_back_to_screen2 (1<<13)  //render N64 frame buffer to screen
 239   #define  fb_cpu_write_hack       (1<<14)  //show images writed directly by CPU
 240
 241   #define fb_emulation_enabled ((settings.frame_buffer&fb_emulation)>0)
 242   #define fb_hwfbe_enabled ((settings.frame_buffer&(fb_emulation|fb_hwfbe))==(fb_emulation|fb_hwfbe))
 243   #define fb_depth_render_enabled ((settings.frame_buffer&fb_depth_render)>0)
 244
 245   wxUint32 frame_buffer;
 246   enum FBCRCMODE {
 247     fbcrcNone = 0,
 248     fbcrcFast = 1,
 249     fbcrcSafe = 2} fb_crc_mode;
 250
 251 #ifdef TEXTURE_FILTER
 252   //Texture filtering options
 253   int ghq_fltr;
 254   int ghq_enht;
 255   int ghq_cmpr;
 256   int ghq_hirs;
 257   int ghq_use;
 258   int ghq_enht_cmpr;
 259   int ghq_enht_tile;
 260   int ghq_enht_f16bpp;
 261   int ghq_enht_gz;
 262   int ghq_enht_nobg;
 263   int ghq_hirs_cmpr;
 264   int ghq_hirs_tile;
 265   int ghq_hirs_f16bpp;
 266   int ghq_hirs_gz;
 267   int ghq_hirs_altcrc;
 268   int ghq_cache_save;
 269   int ghq_cache_size;
 270   int ghq_hirs_let_texartists_fly;
 271   int ghq_hirs_dump;
 272 #endif
 273
 274   //Debug
 275   int autodetect_ucode;
 276   int ucode;
 277   int logging;
 278   int elogging;
 279   int log_clear;
 280   int run_in_window;
 281   int filter_cache;
 282   int unk_as_red;
 283   int log_unk;
 284   int unk_clear;
 285   int wireframe;
 286   int wfmode;
 287
 288   // Special fixes
 289   int offset_x, offset_y;
 290   int scale_x, scale_y;
 291   int fast_crc;
 292   int alt_tex_size;
 293   int use_sts1_only;
 294   int flame_corona; //hack for zeldas flame's corona
 295   int increase_texrect_edge; // add 1 to lower right corner coordinates of texrect
 296   int decrease_fillrect_edge; // sub 1 from lower right corner coordinates of fillrect
 297   int texture_correction; // enable perspective texture correction emulation. is on by default
 298   int stipple_mode;  //used for dithered alpha emulation
 299   wxUint32 stipple_pattern; //used for dithered alpha emulation
 300   int force_microcheck; //check microcode each frame, for mixed F3DEX-S2DEX games
 301   int force_quad3d; //force 0xb5 command to be quad, not line 3d
 302   int clip_zmin; //enable near z clipping
 303   int clip_zmax; //enable far plane clipping;
 304   int adjust_aspect; //adjust screen aspect for wide screen mode
 305   int force_calc_sphere; //use spheric mapping only, Ridge Racer 64
 306   int pal230;    //set special scale for PAL games
 307   int correct_viewport; //correct viewport values
 308   int zmode_compare_less; //force GR_CMP_LESS for zmode=0 (opaque)and zmode=1 (interpenetrating)
 309   int old_style_adither; //apply alpha dither regardless of alpha_dither_mode
 310   int n64_z_scale; //scale vertex z value before writing to depth buffer, as N64 does.
 311
 312   //Special game hacks
 313   #define  hack_ASB         (1<<0)   //All-Star Baseball games
 314   #define  hack_Banjo2      (1<<1)   //Banjo Tooie
 315   #define  hack_BAR         (1<<2)   //Beetle Adventure Racing
 316   #define  hack_Chopper     (1<<3)   //Chopper Attack
 317   #define  hack_Diddy       (1<<4)   //diddy kong racing
 318   #define  hack_Fifa98      (1<<5)   //FIFA - Road to World Cup 98
 319   #define  hack_Fzero       (1<<6)   //F-Zero
 320   #define  hack_GoldenEye   (1<<7)   //Golden Eye
 321   #define  hack_Hyperbike   (1<<8)   //Top Gear Hyper Bike
 322   #define  hack_ISS64       (1<<9)   //International Superstar Soccer 64
 323   #define  hack_KI          (1<<10)  //Killer Instinct
 324   #define  hack_Knockout    (1<<11)  //Knockout Kings 2000
 325   #define  hack_Lego        (1<<12)  //LEGO Racers
 326   #define  hack_MK64        (1<<13)  //Mario Kart
 327   #define  hack_Megaman     (1<<14)  //Megaman64
 328   #define  hack_Makers      (1<<15)  //Mischief-makers
 329   #define  hack_WCWnitro    (1<<16)  //WCW Nitro
 330   #define  hack_Ogre64      (1<<17)  //Ogre Battle 64
 331   #define  hack_Pilotwings  (1<<18)  //Pilotwings
 332   #define  hack_PMario      (1<<19)  //Paper Mario
 333   #define  hack_PPL         (1<<20)  //pokemon puzzle league requires many special fixes
 334   #define  hack_RE2         (1<<21)  //Resident Evil 2
 335   #define  hack_Starcraft   (1<<22)  //StarCraft64
 336   #define  hack_Supercross  (1<<23)  //Supercross 2000
 337   #define  hack_TGR         (1<<24)  //Top Gear Rally
 338   #define  hack_TGR2        (1<<25)  //Top Gear Rally 2
 339   #define  hack_Tonic       (1<<26)  //tonic trouble
 340   #define  hack_Yoshi       (1<<27)  //Yoshi Story
 341   #define  hack_Zelda       (1<<28)  //zeldas hacks
 342   wxUint32 hacks;
 343
 344   //wrapper settings
 345   int wrpResolution;
 346   int wrpVRAM;
 347   int wrpFBO;
 348   int wrpAnisotropic;
 349
 350 } SETTINGS;
 351
 352 typedef struct
 353 {
 354   wxUint8 hk_ref;
 355   wxUint8 hk_motionblur;
 356   wxUint8 hk_filtering;
 357 } HOTKEY_INFO;
 358
 359 typedef struct
 360 {
 361   int num_tmu;
 362   int max_tex_size;
 363   int sup_large_tex;
 364   int sup_mirroring;
 365   int sup_32bit_tex;
 366   int has_2mb_tex_boundary;
 367   int tex_UMA;
 368   int gamma_correction;
 369   FxI32 gamma_table_size;
 370   FxU32 *gamma_table_r;
 371   FxU32 *gamma_table_g;
 372   FxU32 *gamma_table_b;
 373   wxUint32 tmem_ptr[MAX_TMU];
 374   wxUint32 tex_min_addr[MAX_TMU];
 375   wxUint32 tex_max_addr[MAX_TMU];
 376 } VOODOO;
 377
 378 // This structure is what is passed in by rdp:settextureimage
 379 typedef struct {
 380   wxUint8 format;  // format: ARGB, IA, ...
 381   wxUint8 size;    // size: 4,8,16, or 32 bit
 382   wxUint16 width;   // used in settextureimage
 383   wxUint32 addr;   // address in RDRAM to load the texture from
 384   int set_by;  // 0-loadblock 1-loadtile
 385 } TEXTURE_IMAGE;
 386
 387 // This structure is a tile descriptor (as used by rdp:settile and rdp:settilesize)
 388 typedef struct
 389 {
 390   // rdp:settile
 391   wxUint8 format;  // format: ARGB, IA, ...
 392   wxUint8 size;    // size: 4,8,16, or 32 bit
 393   wxUint16 line;    // size of one row (x axis) in 64 bit words
 394   wxUint16 t_mem;   // location in texture memory (in 64 bit words, max 512 (4MB))
 395   wxUint8 palette; // palette # to use
 396   wxUint8 clamp_t; // clamp or wrap (y axis)?
 397   wxUint8 mirror_t;  // mirroring on (y axis)?
 398   wxUint8 mask_t;  // mask to wrap around (ex: 5 would wrap around 32) (y axis)
 399   wxUint8 shift_t; // ??? (scaling)
 400   wxUint8 clamp_s; // clamp or wrap (x axis)?
 401   wxUint8 mirror_s;  // mirroring on (x axis)?
 402   wxUint8 mask_s;  // mask to wrap around (x axis)
 403   wxUint8 shift_s; // ??? (scaling)
 404
 405     // rdp:settilesize
 406   wxUint16 ul_s;    // upper left s coordinate
 407   wxUint16 ul_t;    // upper left t coordinate
 408   wxUint16 lr_s;    // lower right s coordinate
 409   wxUint16 lr_t;    // lower right t coordinate
 410
 411   float f_ul_s;
 412   float f_ul_t;
 413
 414   // these are set by loadtile
 415   wxUint16 t_ul_s;    // upper left s coordinate
 416   wxUint16 t_ul_t;    // upper left t coordinate
 417   wxUint16 t_lr_s;    // lower right s coordinate
 418   wxUint16 t_lr_t;    // lower right t coordinate
 419
 420   wxUint32 width;
 421   wxUint32 height;
 422
 423   // uc0:texture
 424   wxUint8 on;
 425   float s_scale;
 426   float t_scale;
 427
 428   wxUint16 org_s_scale;
 429   wxUint16 org_t_scale;
 430 } TILE;
 431
 432 // This structure forms the lookup table for cached textures
 433 typedef struct {
 434   wxUint32 addr;     // address in RDRAM
 435   wxUint32 crc;      // CRC check
 436   wxUint32 palette;    // Palette #
 437   wxUint32 width;    // width
 438   wxUint32 height;   // height
 439   wxUint32 format;   // format
 440   wxUint32 size;     // size
 441   wxUint32 last_used;  // what frame # was this texture last used (used for replacing)
 442
 443   wxUint32 line;
 444
 445   wxUint32 flags;    // clamp/wrap/mirror flags
 446
 447   wxUint32 realwidth;  // width of actual texture
 448   wxUint32 realheight; // height of actual texture
 449   wxUint32 lod;
 450   wxUint32 aspect;
 451
 452   wxUint8 set_by;
 453   wxUint8 texrecting;
 454
 455   int f_mirror_s;
 456   int f_mirror_t;
 457   int f_wrap_s;
 458   int f_wrap_t;
 459
 460   float scale_x;    // texture scaling
 461   float scale_y;
 462   float scale;    // general scale to 256
 463
 464   GrTexInfo t_info; // texture info (glide)
 465   wxUint32 tmem_addr;  // addres in texture memory (glide)
 466
 467   int uses;   // 1 triangle that uses this texture
 468
 469   int splits;   // number of splits
 470   int splitheight;
 471
 472   float c_off;  // ul center texel offset (both x and y)
 473   float c_scl_x;  // scale to lower-right center-texel x
 474   float c_scl_y;  // scale to lower-right center-texel y
 475
 476   wxUint32 mod, mod_color, mod_color1, mod_color2, mod_factor;
 477 #ifdef TEXTURE_FILTER
 478   uint64 ricecrc;
 479   int is_hires_tex;
 480 #endif
 481 } CACHE_LUT;
 482
 483 // Lights
 484 typedef struct {
 485   float r, g, b, a;       // color
 486   float dir_x, dir_y, dir_z;  // direction towards the light source
 487   float x, y, z, w;  // light position
 488   float ca, la, qa;
 489   wxUint32 nonblack;
 490   wxUint32 nonzero;
 491 } LIGHT;
 492
 493 typedef enum {
 494   ci_main,      //0, main color image
 495   ci_zimg,      //1, depth image
 496   ci_unknown,   //2, status is unknown
 497   ci_useless,   //3, status is unclear
 498   ci_old_copy,  //4, auxiliary color image, copy of last color image from previous frame
 499   ci_copy,      //5, auxiliary color image, copy of previous color image
 500   ci_copy_self, //6, main color image, it's content will be used to draw into itself
 501   ci_zcopy,     //7, auxiliary color image, copy of depth image
 502   ci_aux,       //8, auxiliary color image
 503   ci_aux_copy   //9, auxiliary color image, partial copy of previous color image
 504 } CI_STATUS;
 505
 506 // Frame buffers
 507 typedef struct
 508 {
 509         wxUint32 addr;   //color image address
 510         wxUint8 format;
 511         wxUint8 size;
 512         wxUint16 width;
 513         wxUint16 height;
 514         CI_STATUS status;
 515         int   changed;
 516 } COLOR_IMAGE;
 517
 518 typedef struct
 519 {
 520   GrChipID_t tmu;
 521         wxUint32 addr;  //address of color image
 522         wxUint32 end_addr;
 523         wxUint32 tex_addr; //address in video memory
 524         wxUint32 width;    //width of color image
 525         wxUint32 height;   //height of color image
 526         wxUint8  format;   //format of color image
 527         wxUint8  size;   //format of color image
 528         wxUint8  clear;  //flag. texture buffer must be cleared
 529         wxUint8  drawn;  //flag. if equal to 1, this image was already drawn in current frame
 530         wxUint32 crc; //checksum of the color image
 531         float scr_width; //width of rendered image
 532         float scr_height; //height of rendered image
 533         wxUint32 tex_width;  //width of texture buffer
 534         wxUint32 tex_height; //height of texture buffer
 535         int   tile;     //
 536         wxUint16  tile_uls; //shift from left bound of the texture
 537         wxUint16  tile_ult; //shift from top of the texture
 538         wxUint32 v_shift; //shift from top of the texture
 539         wxUint32 u_shift; //shift from left of the texture
 540         float lr_u;
 541         float lr_v;
 542         float u_scale; //used to map vertex u,v coordinates into hires texture
 543         float v_scale; //used to map vertex u,v coordinates into hires texture
 544         CACHE_LUT * cache; //pointer to texture cache item
 545         GrTexInfo info;
 546   wxUint16 t_mem;
 547 } TBUFF_COLOR_IMAGE;
 548
 549 typedef struct
 550 {
 551         GrChipID_t tmu;
 552         wxUint32 begin; //start of the block in video memory
 553         wxUint32 end;   //end of the block in video memory
 554         wxUint8 count;  //number of allocated texture buffers
 555         int clear_allowed; //stack of buffers can be cleared
 556         TBUFF_COLOR_IMAGE images[256];
 557 } TEXTURE_BUFFER;
 558
 559 #define NUMTEXBUF 92
 560
 561 struct RDP_Base{
 562   float vi_width;
 563   float vi_height;
 564
 565   int window_changed;
 566
 567   float offset_x, offset_y, offset_x_bak, offset_y_bak;
 568
 569   float scale_x, scale_1024, scale_x_bak;
 570   float scale_y, scale_768, scale_y_bak;
 571
 572   float view_scale[3];
 573   float view_trans[3];
 574   float clip_min_x, clip_max_x, clip_min_y, clip_max_y;
 575   float clip_ratio;
 576
 577   int updatescreen;
 578
 579   wxUint32 tri_n;  // triangle counter
 580   wxUint32 debug_n;
 581
 582   // Program counter
 583   wxUint32 pc[10]; // DList PC stack
 584   wxUint32 pc_i;   // current PC index in the stack
 585   int dl_count; // number of instructions before returning
 586   int LLE;
 587
 588   // Segments
 589   wxUint32 segment[16];  // Segment pointer
 590
 591   // Marks the end of DList execution (done in uc?:enddl)
 592   int halt;
 593
 594   // Next command
 595   wxUint32 cmd0;
 596   wxUint32 cmd1;
 597   wxUint32 cmd2;
 598   wxUint32 cmd3;
 599
 600   // Clipping
 601   SCISSOR scissor_o;
 602   SCISSOR scissor;
 603   int scissor_set;
 604
 605   // Colors
 606   wxUint32 fog_color;
 607   wxUint32 fill_color;
 608   wxUint32 prim_color;
 609   wxUint32 blend_color;
 610   wxUint32 env_color;
 611   wxUint32 SCALE;
 612   wxUint32 CENTER;
 613   wxUint32 prim_lodmin, prim_lodfrac;
 614   wxUint16 prim_depth;
 615   wxUint16 prim_dz;
 616   wxUint8 K4;
 617   wxUint8 K5;
 618   enum {
 619   noise_none,
 620   noise_combine,
 621   noise_texture
 622   } noise;
 623
 624   float col[4];   // color multiplier
 625   float coladd[4];  // color add/subtract
 626   float shade_factor;
 627
 628   float col_2[4];
 629
 630   wxUint32 cmb_flags, cmb_flags_2;
 631
 632   // othermode_l flags
 633   int acmp; // 0 = none, 1 = threshold, 2 = dither
 634   int zsrc; // 0 = pixel, 1 = prim
 635   wxUint8 alpha_dither_mode;
 636
 637   // Matrices
 638   DECLAREALIGN16VAR(model[4][4]);
 639   DECLAREALIGN16VAR(proj[4][4]);
 640   DECLAREALIGN16VAR(combined[4][4]);
 641   DECLAREALIGN16VAR(dkrproj[3][4][4]);
 642
 643   DECLAREALIGN16VAR(model_stack[32][4][4]);  // 32 deep, will warn if overflow
 644   int model_i;          // index in the model matrix stack
 645   int model_stack_size;
 646
 647   // Textures
 648   TEXTURE_IMAGE timg;       // 1 for each tmem address
 649   TILE tiles[8];          // 8 tile descriptors
 650   wxUint8 tmem[4096];        // 4k tmem
 651   wxUint32 addr[512];        // 512 addresses (used to determine address loaded from)
 652 #ifdef TEXTURE_FILTER
 653   LOAD_TILE_INFO load_info[512];    // 512 addresses. inforamation about tile loading.
 654 #endif
 655
 656   int     cur_tile;   // current tile
 657   int     mipmap_level;
 658   int     last_tile;   // last tile set
 659   int     last_tile_size;   // last tile size set
 660
 661   int     t0, t1;
 662   int     best_tex; // if no 2-tmus, which texture? (0 or 1)
 663   int     tex;
 664   int     filter_mode;
 665
 666   // Texture palette
 667   wxUint16 pal_8[256];
 668   wxUint32 pal_8_crc[16];
 669   wxUint32 pal_256_crc;
 670   wxUint8 tlut_mode;
 671   int LOD_en;
 672   int Persp_en;
 673   int persp_supported;
 674   int force_wrap;
 675 #ifdef TEXTURE_FILTER
 676   wxUint16 pal_8_rice[512];
 677 #endif
 678
 679   // Lighting
 680   wxUint32 num_lights;
 681   LIGHT light[12];
 682   float light_vector[12][3];
 683   float lookat[2][3];
 684   int  use_lookat;
 685
 686   // Combine modes
 687   wxUint32 cycle1, cycle2, cycle_mode;
 688   wxUint8 c_a0, c_b0, c_c0, c_d0, c_Aa0, c_Ab0, c_Ac0, c_Ad0;
 689   wxUint8 c_a1, c_b1, c_c1, c_d1, c_Aa1, c_Ab1, c_Ac1, c_Ad1;
 690
 691   wxUint8 fbl_a0, fbl_b0, fbl_c0, fbl_d0;
 692   wxUint8 fbl_a1, fbl_b1, fbl_c1, fbl_d1;
 693
 694   wxUint8 uncombined;  // which is uncombined: 0x01=color 0x02=alpha 0x03=both
 695
 696 //  float YUV_C0, YUV_C1, YUV_C2, YUV_C3, YUV_C4; //YUV textures conversion coefficients
 697
 698   // What needs updating
 699   wxUint32 update;
 700   wxUint32 flags;
 701
 702   int first;
 703
 704   wxUint32 tex_ctr;    // incremented every time textures are updated
 705
 706   int allow_combine; // allow combine updating?
 707
 708   int s2dex_tex_loaded;
 709   wxUint16 bg_image_height;
 710
 711   // Debug stuff
 712   wxUint32 rm; // use othermode_l instead, this just as a check for changes
 713   wxUint32 render_mode_changed;
 714   wxUint32 geom_mode;
 715
 716   wxUint32 othermode_h;
 717   wxUint32 othermode_l;
 718
 719   // used to check if in texrect while loading texture
 720   wxUint8 texrecting;
 721
 722   //frame buffer related slots. Added by Gonetz
 723   wxUint32 cimg, ocimg, zimg, tmpzimg, vi_org_reg;
 724   COLOR_IMAGE maincimg[2];
 725   wxUint32 last_drawn_ci_addr;
 726   wxUint32 main_ci, main_ci_end, main_ci_bg, main_ci_last_tex_addr, zimg_end, last_bg;
 727   wxUint32 ci_width, ci_height, ci_size, ci_end;
 728   wxUint32 zi_width;
 729   int zi_lrx, zi_lry;
 730   wxUint8  ci_count, num_of_ci, main_ci_index, copy_ci_index, copy_zi_index;
 731   int swap_ci_index, black_ci_index;
 732   wxUint32 ci_upper_bound, ci_lower_bound;
 733   int  motionblur, fb_drawn, fb_drawn_front, read_previous_ci, read_whole_frame;
 734   CI_STATUS ci_status;
 735   TBUFF_COLOR_IMAGE * cur_image;  //image currently being drawn
 736   TBUFF_COLOR_IMAGE * tbuff_tex;  //image, which corresponds to currently selected texture
 737   TBUFF_COLOR_IMAGE * aTBuffTex[2];
 738   wxUint8  cur_tex_buf;
 739   wxUint8  acc_tex_buf;
 740   int skip_drawing; //rendering is not required. used for frame buffer emulation
 741
 742   //fog related slots. Added by Gonetz
 743   float fog_multiplier, fog_offset;
 744   enum {
 745     fog_disabled,
 746     fog_enabled,
 747     fog_blend,
 748     fog_blend_inverse
 749     }
 750   fog_mode;
 751 };
 752
 753 struct RDP : public RDP_Base
 754 {
 755   // Clipping
 756   int clip;     // clipping flags
 757   VERTEX *vtx1; //[256] copy vertex buffer #1 (used for clipping)
 758   VERTEX *vtx2; //[256] copy vertex buffer #2
 759   VERTEX *vtxbuf;   // current vertex buffer (reset to vtx, used to determine current vertex buffer)
 760   VERTEX *vtxbuf2;
 761   int n_global;   // Used to pass the number of vertices from clip_z to clip_tri
 762   int vtx_buffer;
 763
 764   CACHE_LUT *cache[MAX_TMU]; //[MAX_CACHE]
 765   CACHE_LUT *cur_cache[MAX_TMU];
 766   wxUint32   cur_cache_n[MAX_TMU];
 767   int     n_cached[MAX_TMU];
 768
 769   // Vertices
 770   VERTEX *vtx; //[MAX_VTX]
 771   int v0, vn;
 772
 773   COLOR_IMAGE *frame_buffers; //[NUMTEXBUF+2]
 774   TEXTURE_BUFFER texbufs[2];
 775
 776   char RomName[21];
 777
 778   RDP();
 779   ~RDP();
 780   void Reset();
 781 };
 782
 783
 784 void SetWireframeCol ();
 785 void ChangeSize ();
 786 void GoToFullScreen();
 787
 788 extern RDP rdp;
 789 extern SETTINGS settings;
 790 extern HOTKEY_INFO hotkey_info;
 791 extern VOODOO voodoo;
 792
 793 extern GrTexInfo  fontTex;
 794 extern GrTexInfo  cursorTex;
 795 extern wxUint32   offset_font;
 796 extern wxUint32   offset_cursor;
 797 extern wxUint32   offset_textures;
 798 extern wxUint32   offset_texbuf1;
 799
 800 extern int      ucode_error_report;
 801
 802 /*
 803 extern wxString pluginPath;
 804 extern wxString iniPath;
 805 */
 806 // RDP functions
 807 void rdp_reset ();
 808
 809 extern const char *ACmp[];
 810 extern const char *Mode0[];
 811 extern const char *Mode1[];
 812 extern const char *Mode2[];
 813 extern const char *Mode3[];
 814 extern const char *Alpha0[];
 815 #define Alpha1 Alpha0
 816 extern const char *Alpha2[];
 817 #define Alpha3 Alpha0
 818 extern const char *FBLa[];
 819 extern const char *FBLb[];
 820 extern const char *FBLc[];
 821 extern const char *FBLd[];
 822 extern const char *str_zs[];
 823 extern const char *str_yn[];
 824 extern const char *str_offon[];
 825 extern const char *str_cull[];
 826 // I=intensity probably
 827 extern const char *str_format[];
 828 extern const char *str_size[];
 829 extern const char *str_cm[];
 830 extern const char *str_lod[];
 831 extern const char *str_aspect[];
 832 extern const char *str_filter[];
 833 extern const char *str_tlut[];
 834 extern const char *CIStatus[];
 835
 836 #define FBL_D_1 2
 837 #define FBL_D_0 3
 838
 839 #ifndef max
 840 #define max(a,b)            (((a) > (b)) ? (a) : (b))
 841 #endif
 842 #ifndef min
 843 #define min(a,b)            (((a) < (b)) ? (a) : (b))
 844 #endif
 845 #ifndef TRUE
 846 #define TRUE 1
 847 #endif
 848 #ifndef FALSE
 849 #define FALSE 0
 850 #endif
 851 #ifndef HIWORD
 852 #define HIWORD(a) ((unsigned int)(a) >> 16)
 853 #endif
 854 #ifndef LOWORD
 855 #define LOWORD(a) ((a) & 0xFFFF)
 856 #endif
 857
 858 // Convert from u0/v0/u1/v1 to the real coordinates without regard to tmu
 859 __inline void ConvertCoordsKeep (VERTEX *v, int n)
 860 {
 861   for (int i=0; i<n; i++)
 862   {
 863     v[i].uc(0) = v[i].u0;
 864     v[i].vc(0) = v[i].v0;
 865     v[i].uc(1) = v[i].u1;
 866     v[i].vc(1) = v[i].v1;
 867   }
 868 }
 869
 870 // Convert from u0/v0/u1/v1 to the real coordinates based on the tmu they are on
 871 __inline void ConvertCoordsConvert (VERTEX *v, int n)
 872 {
 873   for (int i=0; i<n; i++)
 874   {
 875     v[i].uc(rdp.t0) = v[i].u0;
 876     v[i].vc(rdp.t0) = v[i].v0;
 877     v[i].uc(rdp.t1) = v[i].u1;
 878     v[i].vc(rdp.t1) = v[i].v1;
 879   }
 880 }
 881
 882 __inline void AllowShadeMods (VERTEX *v, int n)
 883 {
 884   for (int i=0; i<n; i++)
 885   {
 886     v[i].shade_mod = 0;
 887   }
 888 }
 889
 890 __inline void AddOffset (VERTEX *v, int n)
 891 {
 892   for (int i=0; i<n; i++)
 893   {
 894     v[i].x += rdp.offset_x;
 895     v[i].y += rdp.offset_y;
 896   }
 897 }
 898
 899 __inline void CalculateFog (VERTEX *v)
 900 {
 901   if (rdp.flags & FOG_ENABLED)
 902   {
 903     if (v->w < 0.0f)
 904       v->f = 0.0f;
 905     else
 906       v->f = min(255.0f, max(0.0f, v->z_w * rdp.fog_multiplier + rdp.fog_offset));
 907     v->a = (wxUint8)v->f;
 908   }
 909   else
 910   {
 911     v->f = 1.0f;
 912   }
 913 }
 914
 915 void newSwapBuffers();
 916 extern int SwapOK;
 917
 918 // ** utility functions
 919 void load_palette (wxUint32 addr, wxUint16 start, wxUint16 count);
 920 void setTBufTex(wxUint16 t_mem, wxUint32 cnt);
 921
 922 #endif  // ifndef RDP_H