// license:BSD-3-Clause // copyright-holders:Ville Linde, hap, Nicola Salmoria /****************************************************************************** Seibu SPI hardware ******************************************************************************/ #include "machine/eepromser.h" #include "machine/7200fifo.h" #include "sound/okim6295.h" class seibuspi_state : public driver_device { public: seibuspi_state(const machine_config &mconfig, device_type type, const char *tag) : driver_device(mconfig, type, tag) , m_maincpu(*this, "maincpu") , m_audiocpu(*this, "audiocpu") , m_mainram(*this, "mainram") , m_z80_rom(*this, "audiocpu") , m_eeprom(*this, "eeprom") , m_soundfifo(*this, "soundfifo%u", 1) , m_oki(*this, "oki%u", 1) , m_gfxdecode(*this, "gfxdecode") , m_palette(*this, "palette") , m_key(*this, "KEY.%u", 0) , m_special(*this, "SPECIAL") , m_z80_bank(*this, "z80_bank") { } required_device m_maincpu; optional_device m_audiocpu; required_shared_ptr m_mainram; optional_memory_region m_z80_rom; optional_device m_eeprom; optional_device_array m_soundfifo; optional_device_array m_oki; required_device m_gfxdecode; required_device m_palette; optional_ioport_array<5> m_key; optional_ioport m_special; optional_memory_bank m_z80_bank; int m_z80_prg_transfer_pos; int m_z80_lastbank; uint8_t m_sb_coin_latch; uint8_t m_ejsakura_input_port; tilemap_t *m_text_layer; tilemap_t *m_back_layer; tilemap_t *m_midl_layer; tilemap_t *m_fore_layer; uint32_t m_video_dma_length; uint32_t m_video_dma_address; uint16_t m_layer_enable; uint16_t m_layer_bank; uint8_t m_rf2_layer_bank; uint16_t m_scrollram[6]; int m_rowscroll_enable; int m_midl_layer_offset; int m_fore_layer_offset; int m_text_layer_offset; int m_fore_layer_d13; int m_back_layer_d14; int m_midl_layer_d14; int m_fore_layer_d14; std::unique_ptr m_tilemap_ram; std::unique_ptr m_palette_ram; std::unique_ptr m_sprite_ram; uint32_t m_tilemap_ram_size; uint32_t m_palette_ram_size; uint32_t m_sprite_ram_size; uint32_t m_bg_fore_layer_position; uint8_t m_alpha_table[0x2000]; int m_sprite_bpp; DECLARE_WRITE16_MEMBER(tile_decrypt_key_w); DECLARE_WRITE16_MEMBER(spi_layer_bank_w); DECLARE_WRITE16_MEMBER(spi_layer_enable_w); DECLARE_WRITE8_MEMBER(rf2_layer_bank_w); DECLARE_WRITE16_MEMBER(scroll_w); DECLARE_WRITE32_MEMBER(tilemap_dma_start_w); DECLARE_WRITE32_MEMBER(palette_dma_start_w); DECLARE_WRITE16_MEMBER(sprite_dma_start_w); DECLARE_WRITE32_MEMBER(video_dma_length_w); DECLARE_WRITE32_MEMBER(video_dma_address_w); DECLARE_READ8_MEMBER(spi_status_r); DECLARE_READ8_MEMBER(spi_ds2404_unknown_r); DECLARE_READ8_MEMBER(sb_coin_r); DECLARE_WRITE8_MEMBER(spi_coin_w); DECLARE_READ8_MEMBER(sound_fifo_status_r); DECLARE_WRITE8_MEMBER(z80_prg_transfer_w); DECLARE_WRITE8_MEMBER(z80_enable_w); DECLARE_READ8_MEMBER(z80_soundfifo_status_r); DECLARE_WRITE8_MEMBER(z80_bank_w); DECLARE_READ32_MEMBER(ejsakura_keyboard_r); DECLARE_WRITE32_MEMBER(ejsakura_input_select_w); DECLARE_WRITE8_MEMBER(eeprom_w); DECLARE_WRITE8_MEMBER(spi_layerbanks_eeprom_w); DECLARE_WRITE8_MEMBER(oki_bank_w); DECLARE_READ32_MEMBER(senkyu_speedup_r); DECLARE_READ32_MEMBER(senkyua_speedup_r); DECLARE_READ32_MEMBER(batlball_speedup_r); DECLARE_READ32_MEMBER(rdft_speedup_r); DECLARE_READ32_MEMBER(viprp1_speedup_r); DECLARE_READ32_MEMBER(viprp1o_speedup_r); DECLARE_READ32_MEMBER(rf2_speedup_r); DECLARE_READ32_MEMBER(rfjet_speedup_r); DECLARE_CUSTOM_INPUT_MEMBER(ejanhs_encode); DECLARE_WRITE_LINE_MEMBER(ymf_irqhandler); IRQ_CALLBACK_MEMBER(spi_irq_callback); INTERRUPT_GEN_MEMBER(spi_interrupt); void set_layer_offsets(); void drawgfx_blend(bitmap_rgb32 &bitmap, const rectangle &cliprect, gfx_element *gfx, uint32_t code, uint32_t color, int flipx, int flipy, int sx, int sy, bitmap_ind8 &primap, int primask); void draw_sprites(bitmap_rgb32 &bitmap, const rectangle &cliprect, bitmap_ind8 &primap, int priority); void combine_tilemap(bitmap_rgb32 &bitmap, const rectangle &cliprect, tilemap_t *tile, int sx, int sy, int opaque, int16_t *rowscroll); virtual void machine_start() override; virtual void video_start() override; DECLARE_MACHINE_RESET(spi); DECLARE_MACHINE_RESET(sxx2e); DECLARE_VIDEO_START(ejanhs); DECLARE_VIDEO_START(sys386f); TILE_GET_INFO_MEMBER(get_text_tile_info); TILE_GET_INFO_MEMBER(get_back_tile_info); TILE_GET_INFO_MEMBER(get_midl_tile_info); TILE_GET_INFO_MEMBER(get_fore_tile_info); uint32_t screen_update_spi(screen_device &screen, bitmap_rgb32 &bitmap, const rectangle &cliprect); uint32_t screen_update_sys386f(screen_device &screen, bitmap_rgb32 &bitmap, const rectangle &cliprect); void register_video_state(); void init_spi_common(); void init_sei252(); void init_batlball(); void init_senkyu(); void init_viprp1(); void init_viprp1o(); void init_rdft(); void init_rfjet(); void init_senkyua(); void init_rdft2(); void init_ejanhs(); void init_sys386f(); void text_decrypt(uint8_t *rom); void bg_decrypt(uint8_t *rom, int size); void rdft2_text_decrypt(uint8_t *rom); void rdft2_bg_decrypt(uint8_t *rom, int size); void rfjet_text_decrypt(uint8_t *rom); void rfjet_bg_decrypt(uint8_t *rom, int size); void sys386f(machine_config &config); void sxx2f(machine_config &config); void rdft2(machine_config &config); void ejanhs(machine_config &config); void sys386i(machine_config &config); void sxx2g(machine_config &config); void spi(machine_config &config); void sxx2e(machine_config &config); void base_map(address_map &map); void rdft2_map(address_map &map); void rise_map(address_map &map); void sei252_map(address_map &map); void spi_map(address_map &map); void spi_soundmap(address_map &map); void spi_ymf271_map(address_map &map); void sxx2e_map(address_map &map); void sxx2e_soundmap(address_map &map); void sxx2f_map(address_map &map); void sys386f_map(address_map &map); void sys386i_map(address_map &map); };