diff options
Diffstat (limited to 'src/mame/drivers/supduck.cpp')
-rw-r--r-- | src/mame/drivers/supduck.cpp | 513 |
1 files changed, 513 insertions, 0 deletions
diff --git a/src/mame/drivers/supduck.cpp b/src/mame/drivers/supduck.cpp new file mode 100644 index 00000000000..56ae254dccf --- /dev/null +++ b/src/mame/drivers/supduck.cpp @@ -0,0 +1,513 @@ +// license:BSD-3-Clause +// copyright-holders:David Haywood +/********************************************************************************* + + Super Duck (c) 1992 Comad + + hardware appears to be roughly based off Bionic Commando, close to the + Tiger Road / F1-Dream based Pushman / Bouncing Balls. + + +PCB Clocks as measured: + +Crystal 1: 8mhz +Crystal 2: 24mhz + +All clock timing comes from crystal 1 + 68k - 8mhz + Z80 - 2mhz + OKI M6295 - 1mhz + +*********************************************************************************/ + + +#include "emu.h" +#include "cpu/z80/z80.h" +#include "cpu/m68000/m68000.h" +#include "sound/okim6295.h" +#include "video/bufsprite.h" +#include "video/tigeroad_spr.h" + +class supduck_state : public driver_device +{ +public: + supduck_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_spriteram(*this, "spriteram") , + m_text_videoram(*this, "textvideoram"), + m_fore_videoram(*this, "forevideoram"), + m_back_videoram(*this, "backvideoram"), + m_gfxdecode(*this, "gfxdecode"), + m_palette(*this, "palette"), + m_spritegen(*this, "spritegen") + { } + + // devices + required_device<cpu_device> m_maincpu; + required_device<z80_device> m_audiocpu; + + // shared pointers + required_device<buffered_spriteram16_device> m_spriteram; + required_shared_ptr<UINT16> m_text_videoram; + required_shared_ptr<UINT16> m_fore_videoram; + required_shared_ptr<UINT16> m_back_videoram; + + required_device<gfxdecode_device> m_gfxdecode; + required_device<palette_device> m_palette; + required_device<tigeroad_spr_device> m_spritegen; + + tilemap_t *m_text_tilemap; + tilemap_t *m_fore_tilemap; + tilemap_t *m_back_tilemap; + + UINT32 screen_update(screen_device &screen, bitmap_ind16 &bitmap, const rectangle &cliprect); + + DECLARE_WRITE16_MEMBER(text_videoram_w); + DECLARE_WRITE16_MEMBER(fore_videoram_w); + DECLARE_WRITE16_MEMBER(back_videoram_w); + DECLARE_WRITE16_MEMBER(supduck_scroll_w); + + DECLARE_WRITE16_MEMBER(supduck_4000_w); + DECLARE_WRITE16_MEMBER(supduck_4002_w); + + TILEMAP_MAPPER_MEMBER(supduk_tilemap_scan); + + DECLARE_WRITE8_MEMBER(okibank_w); + +protected: + + // driver_device overrides + virtual void machine_start(); + virtual void machine_reset(); + + virtual void video_start(); + + TILE_GET_INFO_MEMBER(get_text_tile_info); + TILE_GET_INFO_MEMBER(get_fore_tile_info); + TILE_GET_INFO_MEMBER(get_back_tile_info); + +}; + + + +TILEMAP_MAPPER_MEMBER(supduck_state::supduk_tilemap_scan) +{ + // where does each page start? + int pagesize = 0x8 * 0x8; + + int offset = ((col & ~0x7) / 0x8) * (pagesize); + offset += ((row^0x3f) & 0x7)*0x8; + offset += col & 0x7; + + offset &= 0x3ff; + + offset += (((row^0x3f) & ~0x7) / 0x8) * 0x400; + + + return offset; +} + +void supduck_state::video_start() +{ + m_text_tilemap = &machine().tilemap().create(m_gfxdecode, tilemap_get_info_delegate(FUNC(supduck_state::get_text_tile_info),this), TILEMAP_SCAN_ROWS, 8, 8, 32, 32); + + m_fore_tilemap = &machine().tilemap().create(m_gfxdecode, tilemap_get_info_delegate(FUNC(supduck_state::get_fore_tile_info),this), tilemap_mapper_delegate(FUNC(supduck_state::supduk_tilemap_scan),this), 32, 32, 128,64); + m_back_tilemap = &machine().tilemap().create(m_gfxdecode, tilemap_get_info_delegate(FUNC(supduck_state::get_back_tile_info),this), tilemap_mapper_delegate(FUNC(supduck_state::supduk_tilemap_scan),this), 32, 32, 128,64); + + m_text_tilemap->set_transparent_pen(0x3); + m_fore_tilemap->set_transparent_pen(0xf); + +} + +UINT32 supduck_state::screen_update(screen_device &screen, bitmap_ind16 &bitmap, const rectangle &cliprect) +{ + bitmap.fill(m_palette->black_pen(), cliprect); + + m_back_tilemap->draw(screen, bitmap, cliprect, 0, 0); + m_fore_tilemap->draw(screen, bitmap, cliprect, 0, 0); + + m_spritegen->draw_sprites(bitmap, cliprect, m_gfxdecode, 3, m_spriteram->buffer(), m_spriteram->bytes(), flip_screen(), 1 ); + + m_text_tilemap->draw(screen, bitmap, cliprect, 0, 0); + return 0; +} + + +WRITE16_MEMBER(supduck_state::text_videoram_w) +{ + COMBINE_DATA(&m_text_videoram[offset]); + m_text_tilemap->mark_tile_dirty(offset); +} + +WRITE16_MEMBER(supduck_state::fore_videoram_w) +{ + COMBINE_DATA(&m_fore_videoram[offset]); + m_fore_tilemap->mark_tile_dirty(offset); +} + +WRITE16_MEMBER(supduck_state::back_videoram_w) +{ + COMBINE_DATA(&m_back_videoram[offset]); + m_back_tilemap->mark_tile_dirty(offset); +} + + +TILE_GET_INFO_MEMBER(supduck_state::get_text_tile_info) // same as tigeroad.c +{ + UINT16 *videoram = m_text_videoram; + int data = videoram[tile_index]; + int attr = data >> 8; + int code = (data & 0xff) + ((attr & 0xc0) << 2) + ((attr & 0x20) << 5); + int color = attr & 0x0f; + int flags = (attr & 0x10) ? TILE_FLIPY : 0; + + SET_TILE_INFO_MEMBER(0, code, color, flags); +} + +TILE_GET_INFO_MEMBER(supduck_state::get_fore_tile_info) +{ + UINT16 *videoram = m_fore_videoram; + int data = videoram[tile_index]; + int code = data & 0xff; + if (data & 0x4000) code |= 0x100; + if (data & 0x8000) code |= 0x200; + + int color = (data & 0x0f00)>>8; + int flags = (data & 0x2000) ? TILE_FLIPX : 0; + flags |=(data & 0x1000) ? TILE_FLIPY : 0; + + + SET_TILE_INFO_MEMBER(1, code, color, flags); +} + +TILE_GET_INFO_MEMBER(supduck_state::get_back_tile_info) +{ + UINT16 *videoram = m_back_videoram; + int data = videoram[tile_index]; + + int code = data & 0xff; + if (data & 0x4000) code |= 0x100; + if (data & 0x8000) code |= 0x200; + + int color = (data & 0x0f00)>>8; + int flags = (data & 0x2000) ? TILE_FLIPX : 0; + flags |=(data & 0x1000) ? TILE_FLIPY : 0; + + SET_TILE_INFO_MEMBER(2, code, color, flags); +} + + + +WRITE16_MEMBER(supduck_state::supduck_4000_w) +{ +} + + +WRITE16_MEMBER(supduck_state::supduck_4002_w) +{ + data &= mem_mask; + + soundlatch_byte_w(space, 0, (data>>8)); + m_audiocpu->set_input_line(0, HOLD_LINE); + +} + +WRITE16_MEMBER(supduck_state::supduck_scroll_w) +{ + data &= mem_mask; + + switch (offset) + { + case 0: + m_back_tilemap->set_scrollx(0, data); + break; + case 1: + m_back_tilemap->set_scrolly(0, -data - 32 * 8); + break; + case 2: + m_fore_tilemap->set_scrollx(0, data); + break; + case 3: + m_fore_tilemap->set_scrolly(0, -data - 32 * 8); + break; + } +} + + + +static ADDRESS_MAP_START( main_map, AS_PROGRAM, 16, supduck_state ) + AM_RANGE(0x000000, 0x03ffff) AM_ROM AM_WRITENOP + AM_RANGE(0xfe0000, 0xfe1fff) AM_RAM AM_SHARE("spriteram") + + AM_RANGE(0xfe4000, 0xfe4001) AM_READ_PORT("P1_P2") AM_WRITE( supduck_4000_w ) + AM_RANGE(0xfe4002, 0xfe4003) AM_READ_PORT("SYSTEM") AM_WRITE( supduck_4002_w ) + AM_RANGE(0xfe4004, 0xfe4005) AM_READ_PORT("DSW") + + AM_RANGE(0xfe8000, 0xfe8007) AM_WRITE(supduck_scroll_w) + AM_RANGE(0xfe800e, 0xfe800f) AM_WRITENOP // watchdog or irqack + + AM_RANGE(0xfec000, 0xfecfff) AM_RAM_WRITE(text_videoram_w) AM_SHARE("textvideoram") + AM_RANGE(0xff0000, 0xff3fff) AM_RAM_WRITE(back_videoram_w) AM_SHARE("backvideoram") + AM_RANGE(0xff4000, 0xff7fff) AM_RAM_WRITE(fore_videoram_w) AM_SHARE("forevideoram") + AM_RANGE(0xff8000, 0xff87ff) AM_RAM_DEVWRITE("palette", palette_device, write) AM_SHARE("palette") + AM_RANGE(0xffc000, 0xffffff) AM_RAM /* working RAM */ +ADDRESS_MAP_END + +static ADDRESS_MAP_START( sound_map, AS_PROGRAM, 8, supduck_state ) + AM_RANGE(0x0000, 0x7fff) AM_ROM + AM_RANGE(0x8000, 0x87ff) AM_RAM + AM_RANGE(0x9000, 0x9000) AM_WRITE(okibank_w) + AM_RANGE(0x9800, 0x9800) AM_DEVREADWRITE("oki", okim6295_device, read, write) + AM_RANGE(0xa000, 0xa000) AM_READ(soundlatch_byte_r) +ADDRESS_MAP_END + +static ADDRESS_MAP_START( oki_map, AS_0, 8, supduck_state ) + AM_RANGE(0x00000, 0x1ffff) AM_ROM + AM_RANGE(0x20000, 0x3ffff) AM_ROMBANK("okibank") +ADDRESS_MAP_END + +WRITE8_MEMBER(supduck_state::okibank_w) +{ + // bit 0x80 is written on startup? + + membank("okibank")->set_entry(data&0x03); +} + + +static INPUT_PORTS_START( supduck ) + PORT_START("P1_P2") + PORT_BIT( 0x0001, IP_ACTIVE_LOW, IPT_JOYSTICK_RIGHT ) PORT_8WAY PORT_PLAYER(1) + PORT_BIT( 0x0002, IP_ACTIVE_LOW, IPT_JOYSTICK_LEFT ) PORT_8WAY PORT_PLAYER(1) + PORT_BIT( 0x0004, IP_ACTIVE_LOW, IPT_JOYSTICK_DOWN ) PORT_8WAY PORT_PLAYER(1) + PORT_BIT( 0x0008, IP_ACTIVE_LOW, IPT_JOYSTICK_UP ) PORT_8WAY PORT_PLAYER(1) + PORT_BIT( 0x0010, IP_ACTIVE_LOW, IPT_BUTTON1 ) PORT_PLAYER(1) + PORT_BIT( 0x0020, IP_ACTIVE_LOW, IPT_BUTTON2 ) PORT_PLAYER(1) + PORT_BIT( 0x0040, IP_ACTIVE_LOW, IPT_BUTTON3 ) PORT_PLAYER(1) + PORT_BIT( 0x0080, IP_ACTIVE_LOW, IPT_BUTTON4 ) PORT_PLAYER(1) + PORT_BIT( 0x0100, IP_ACTIVE_LOW, IPT_JOYSTICK_RIGHT ) PORT_8WAY PORT_PLAYER(2) + PORT_BIT( 0x0200, IP_ACTIVE_LOW, IPT_JOYSTICK_LEFT ) PORT_8WAY PORT_PLAYER(2) + PORT_BIT( 0x0400, IP_ACTIVE_LOW, IPT_JOYSTICK_DOWN ) PORT_8WAY PORT_PLAYER(2) + PORT_BIT( 0x0800, IP_ACTIVE_LOW, IPT_JOYSTICK_UP ) PORT_8WAY PORT_PLAYER(2) + PORT_BIT( 0x1000, IP_ACTIVE_LOW, IPT_BUTTON1 ) PORT_PLAYER(2) + PORT_BIT( 0x2000, IP_ACTIVE_LOW, IPT_BUTTON2 ) PORT_PLAYER(2) + PORT_BIT( 0x4000, IP_ACTIVE_LOW, IPT_BUTTON3 ) PORT_PLAYER(2) + PORT_BIT( 0x8000, IP_ACTIVE_LOW, IPT_BUTTON4 ) PORT_PLAYER(2) + + PORT_START("SYSTEM") + PORT_BIT( 0x00ff, IP_ACTIVE_LOW, IPT_UNKNOWN ) + PORT_BIT( 0x0100, IP_ACTIVE_LOW, IPT_START1 ) + PORT_BIT( 0x0200, IP_ACTIVE_LOW, IPT_START2 ) + PORT_BIT( 0x0400, IP_ACTIVE_LOW, IPT_CUSTOM ) PORT_VBLANK("screen") /* not sure, probably wrong */ + PORT_BIT( 0x0800, IP_ACTIVE_LOW, IPT_UNKNOWN ) + PORT_BIT( 0x1000, IP_ACTIVE_LOW, IPT_UNKNOWN ) + PORT_BIT( 0x2000, IP_ACTIVE_LOW, IPT_SERVICE1 ) + PORT_BIT( 0x4000, IP_ACTIVE_LOW, IPT_COIN1 ) + PORT_BIT( 0x8000, IP_ACTIVE_LOW, IPT_COIN2 ) + + PORT_START("DSW") + PORT_DIPNAME( 0x0007, 0x0007, DEF_STR( Coinage ) ) PORT_DIPLOCATION("DIP-A:1,2,3") + PORT_DIPSETTING( 0x0000, DEF_STR( 5C_1C ) ) + PORT_DIPSETTING( 0x0001, DEF_STR( 4C_1C ) ) + PORT_DIPSETTING( 0x0002, DEF_STR( 3C_1C ) ) + PORT_DIPSETTING( 0x0003, DEF_STR( 2C_1C ) ) + PORT_DIPSETTING( 0x0007, DEF_STR( 1C_1C ) ) + PORT_DIPSETTING( 0x0006, DEF_STR( 1C_2C ) ) + PORT_DIPSETTING( 0x0005, DEF_STR( 1C_3C ) ) + PORT_DIPSETTING( 0x0004, DEF_STR( 1C_4C ) ) + PORT_DIPNAME( 0x0008, 0x0008, DEF_STR( Unknown ) ) PORT_DIPLOCATION("DIP-A:4") + PORT_DIPSETTING( 0x0008, DEF_STR( Off ) ) + PORT_DIPSETTING( 0x0000, DEF_STR( On ) ) + PORT_DIPNAME( 0x0010, 0x0010, DEF_STR( Demo_Sounds ) ) PORT_DIPLOCATION("DIP-A:5") + PORT_DIPSETTING( 0x0000, DEF_STR( Off ) ) + PORT_DIPSETTING( 0x0010, DEF_STR( On ) ) + PORT_DIPNAME( 0x0020, 0x0020, "Game Sound" ) PORT_DIPLOCATION("DIP-A:6") /* Kills all sounds except for Coin-In */ + PORT_DIPSETTING( 0x0000, DEF_STR( Off ) ) + PORT_DIPSETTING( 0x0020, DEF_STR( On ) ) + PORT_DIPNAME( 0x00c0, 0x0080, DEF_STR( Lives ) ) PORT_DIPLOCATION("DIP-A:7,8") + PORT_DIPSETTING( 0x00c0, "2" ) + PORT_DIPSETTING( 0x0080, "3" ) + PORT_DIPSETTING( 0x0040, "4" ) + PORT_DIPSETTING( 0x0000, "5" ) + PORT_DIPNAME( 0x0100, 0x0100, DEF_STR( Unknown ) ) PORT_DIPLOCATION("DIP-B:1") + PORT_DIPSETTING( 0x0100, DEF_STR( Off ) ) + PORT_DIPSETTING( 0x0000, DEF_STR( On ) ) + PORT_DIPNAME( 0x0200, 0x0200, DEF_STR( Unknown ) ) PORT_DIPLOCATION("DIP-B:2") + PORT_DIPSETTING( 0x0200, DEF_STR( Off ) ) + PORT_DIPSETTING( 0x0000, DEF_STR( On ) ) + PORT_DIPNAME( 0x0400, 0x0400, DEF_STR( Unknown ) ) PORT_DIPLOCATION("DIP-B:3") + PORT_DIPSETTING( 0x0400, DEF_STR( Off ) ) + PORT_DIPSETTING( 0x0000, DEF_STR( On ) ) + PORT_DIPNAME( 0x0800, 0x0800, DEF_STR( Unknown ) ) PORT_DIPLOCATION("DIP-B:4") + PORT_DIPSETTING( 0x0800, DEF_STR( Off ) ) + PORT_DIPSETTING( 0x0000, DEF_STR( On ) ) + PORT_DIPNAME( 0x1000, 0x1000, DEF_STR( Unknown ) ) PORT_DIPLOCATION("DIP-B:5") + PORT_DIPSETTING( 0x1000, DEF_STR( Off ) ) + PORT_DIPSETTING( 0x0000, DEF_STR( On ) ) + PORT_DIPNAME( 0x2000, 0x2000, DEF_STR( Unknown ) ) PORT_DIPLOCATION("DIP-B:6") + PORT_DIPSETTING( 0x2000, DEF_STR( Off ) ) + PORT_DIPSETTING( 0x0000, DEF_STR( On ) ) + PORT_DIPNAME( 0x4000, 0x4000, "Character Test" ) PORT_DIPLOCATION("DIP-B:7") + PORT_DIPSETTING( 0x4000, DEF_STR( Off ) ) + PORT_DIPSETTING( 0x0000, DEF_STR( On ) ) + PORT_SERVICE_DIPLOC( 0x8000, IP_ACTIVE_LOW, "DIP-B:8" ) +INPUT_PORTS_END + + +static const gfx_layout spritelayout_bionicc= +{ + 16,16, /* 16*16 sprites */ + RGN_FRAC(1,4), /* 2048 sprites */ + 4, /* 4 bits per pixel */ + { RGN_FRAC(3,4), RGN_FRAC(2,4), RGN_FRAC(1,4), RGN_FRAC(0,4) }, + { + 0,1,2,3,4,5,6,7, + (16*8)+0,(16*8)+1,(16*8)+2,(16*8)+3, + (16*8)+4,(16*8)+5,(16*8)+6,(16*8)+7 + }, + { + 0*8, 1*8, 2*8, 3*8, 4*8, 5*8, 6*8, 7*8, + 8*8, 9*8, 10*8, 11*8, 12*8, 13*8, 14*8, 15*8, + }, + 256 /* every sprite takes 256 consecutive bytes */ +}; + +static const gfx_layout vramlayout_bionicc= +{ + 8,8, /* 8*8 characters */ + RGN_FRAC(1,1), /* 1024 character */ + 2, /* 2 bitplanes */ + { 4,0 }, + { 0,1,2,3,8,9,10,11 }, + { 0*16, 1*16, 2*16, 3*16, 4*16, 5*16, 6*16, 7*16 }, + 128 /* every character takes 128 consecutive bytes */ +}; + +// same as the ROM tilemap layout from tigeroad +static const gfx_layout tile_layout = +{ + 32, 32, + RGN_FRAC(1, 2), + 4, + { RGN_FRAC(1,2)+4, RGN_FRAC(1,2)+0, 4, 0 }, + { + 0, 1, 2, 3, 8 + 0, 8 + 1, 8 + 2, 8 + 3, + 64 * 8 + 0, 64 * 8 + 1, 64 * 8 + 2, 64 * 8 + 3, 64 * 8 + 8 + 0, 64 * 8 + 8 + 1, 64 * 8 + 8 + 2, 64 * 8 + 8 + 3, + 2 * 64 * 8 + 0, 2 * 64 * 8 + 1, 2 * 64 * 8 + 2, 2 * 64 * 8 + 3, 2 * 64 * 8 + 8 + 0, 2 * 64 * 8 + 8 + 1, 2 * 64 * 8 + 8 + 2, 2 * 64 * 8 + 8 + 3, + 3 * 64 * 8 + 0, 3 * 64 * 8 + 1, 3 * 64 * 8 + 2, 3 * 64 * 8 + 3, 3 * 64 * 8 + 8 + 0, 3 * 64 * 8 + 8 + 1, 3 * 64 * 8 + 8 + 2, 3 * 64 * 8 + 8 + 3, + }, + { + 0 * 16, 1 * 16, 2 * 16, 3 * 16, 4 * 16, 5 * 16, 6 * 16, 7 * 16, + 8 * 16, 9 * 16, 10 * 16, 11 * 16, 12 * 16, 13 * 16, 14 * 16, 15 * 16, + 16 * 16, 17 * 16, 18 * 16, 19 * 16, 20 * 16, 21 * 16, 22 * 16, 23 * 16, + 24 * 16, 25 * 16, 26 * 16, 27 * 16, 28 * 16, 29 * 16, 30 * 16, 31 * 16 + }, + 256 * 8 +}; + + + +static GFXDECODE_START( supduck ) + GFXDECODE_ENTRY( "gfx1", 0, vramlayout_bionicc, 768, 64 ) /* colors 768-1023 */ + GFXDECODE_ENTRY( "gfx2", 0, tile_layout, 0, 16 ) /* colors 0- 63 */ + GFXDECODE_ENTRY( "gfx3", 0, tile_layout, 256, 16 ) /* colors 256- 319 */ + GFXDECODE_ENTRY( "gfx4", 0, spritelayout_bionicc, 512, 16 ) /* colors 512- 767 */ +GFXDECODE_END + + + +void supduck_state::machine_start() +{ + membank("okibank")->configure_entries(0, 4, memregion("okibank")->base(), 0x20000); + membank("okibank")->set_entry(0); +} + +void supduck_state::machine_reset() +{ +} + + +static MACHINE_CONFIG_START( supduck, supduck_state ) + + /* basic machine hardware */ + MCFG_CPU_ADD("maincpu", M68000, XTAL_8MHz) /* Verified on PCB */ + MCFG_CPU_PROGRAM_MAP(main_map) + MCFG_CPU_VBLANK_INT_DRIVER("screen", supduck_state, irq2_line_hold) // 2 & 4? + + MCFG_CPU_ADD("audiocpu", Z80, XTAL_8MHz/4) /* 2MHz - verified on PCB */ + MCFG_CPU_PROGRAM_MAP(sound_map) + + /* video hardware */ + MCFG_SCREEN_ADD("screen", RASTER) + MCFG_SCREEN_REFRESH_RATE(60) + MCFG_SCREEN_VBLANK_TIME(ATTOSECONDS_IN_USEC(2500)) + MCFG_SCREEN_UPDATE_DRIVER(supduck_state, screen_update) + MCFG_SCREEN_SIZE(32*8, 32*8) + MCFG_SCREEN_VISIBLE_AREA(0*8, 32*8-1, 2*8, 30*8-1) + MCFG_SCREEN_PALETTE("palette") + MCFG_SCREEN_VBLANK_DEVICE("spriteram", buffered_spriteram16_device, vblank_copy_rising) + + MCFG_BUFFERED_SPRITERAM16_ADD("spriteram") + + MCFG_GFXDECODE_ADD("gfxdecode", "palette", supduck) + + MCFG_DEVICE_ADD("spritegen", TIGEROAD_SPRITE, 0) + + MCFG_PALETTE_ADD("palette", 0x800/2) + MCFG_PALETTE_FORMAT(xRGBRRRRGGGGBBBB_bit4) + + /* sound hardware */ + MCFG_SPEAKER_STANDARD_MONO("mono") + + MCFG_OKIM6295_ADD("oki", XTAL_8MHz/8, OKIM6295_PIN7_HIGH) // 1MHz - Verified on PCB, pin 7 not verified + MCFG_SOUND_ROUTE(ALL_OUTPUTS, "mono", 1.0) + MCFG_DEVICE_ADDRESS_MAP(AS_0, oki_map) + +MACHINE_CONFIG_END + + + +/*************************************************************************** + + Game driver(s) + +***************************************************************************/ + +ROM_START( supduck ) + ROM_REGION( 0x40000, "maincpu", 0 ) /* 68000 code */ + ROM_LOAD16_BYTE( "5.u16n", 0x00000, 0x20000, CRC(837a559a) SHA1(ed5ad744a4145dfbef56ad2e6eec3ff14c20de1c) ) + ROM_LOAD16_BYTE( "6.u16l", 0x00001, 0x20000, CRC(508e9905) SHA1(2da3f12caa29066b4d54b22573cfdfcea8916f99) ) + + ROM_REGION( 0x10000, "audiocpu", 0 ) + ROM_LOAD( "4.su6", 0x00000, 0x8000, CRC(d75863ea) SHA1(497d11b86f4f69134943fc3448d195c6e7acbe8f) ) + + ROM_REGION( 0x08000, "gfx1", 0 ) + ROM_LOAD( "3.cu15", 0x00000, 0x8000, CRC(b1cacca4) SHA1(b4a486618197cf2b85a121b5640cd773b2d453fc) ) + + ROM_REGION( 0x80000, "gfx2", 0 ) + ROM_LOAD( "7.uu29", 0x00000, 0x20000, CRC(f3251b20) SHA1(8ebb9b98324de14356c9a57ae8a77dc4118fb5c2) ) + ROM_LOAD( "8.uu30", 0x20000, 0x20000, CRC(03c60cbd) SHA1(bf3be7161f69187350eb9d9d4209b93f8b67d0f1) ) + ROM_LOAD( "9.uu31", 0x40000, 0x20000, CRC(9b6d3430) SHA1(ade2decc5bcf817498b1198a2244d1c65bc20bea) ) + ROM_LOAD( "10.uu32", 0x60000, 0x20000, CRC(beed2616) SHA1(c077a3de4a6d451a568694ab70e85830d585a41d) ) + + ROM_REGION( 0x80000, "gfx3", 0 ) + ROM_LOAD( "11.ul29", 0x00000, 0x20000, CRC(1b6958a4) SHA1(ca93f898702e14ece24d5cfced38d622d3596d0f) ) + ROM_LOAD( "12.ul30", 0x20000, 0x20000, CRC(3e6bd24b) SHA1(f93b5c78d815bd30ecb9cfe2cd257548e467e852) ) + ROM_LOAD( "13.ul31", 0x40000, 0x20000, CRC(bff7b7cd) SHA1(2f65cadcfcc02fe31ba721eea9f45d4a729e4374) ) + ROM_LOAD( "14.ul32", 0x60000, 0x20000, CRC(97a7310b) SHA1(76b82bfea64b59890c0ba2e1688b7321507a4da7) ) + + ROM_REGION( 0x80000, "gfx4", 0 ) + ROM_LOAD( "15.u1d", 0x60000, 0x20000, CRC(81bf1f27) SHA1(7a66630a2da85387904917d3c136880dffcb9649) ) + ROM_LOAD( "16.u2d", 0x40000, 0x20000, CRC(9573d6ec) SHA1(9923be782bae47c49913d01554bcf3e5efb5395b) ) + ROM_LOAD( "17.u1c", 0x20000, 0x20000, CRC(21ef14d4) SHA1(66e389aaa1186921a07da9a9a9eda88a1083ad42) ) + ROM_LOAD( "18.u2c", 0x00000, 0x20000, CRC(33dd0674) SHA1(b95dfcc16d939bac77f338b8a8cada19328a1993) ) + + ROM_REGION( 0x80000, "oki", 0 ) + ROM_LOAD( "2.su12", 0x00000, 0x20000, CRC(745d42fb) SHA1(f9aee3ddbad3cc2f3a7002ee0d762eb041967e1e) ) // static sample data + + ROM_REGION( 0x80000, "okibank", 0 ) + ROM_LOAD( "1.su13", 0x00000, 0x80000, CRC(7fb1ed42) SHA1(77ec86a6454398e329066aa060e9b6a39085ce71) ) // banked sample data +ROM_END + +GAME( 1992, supduck, 0, supduck, supduck, driver_device, 0, ROT0, "Comad", "Super Duck", MACHINE_SUPPORTS_SAVE ) |