1*9a0e4156SSadaf Ebrahimi(* Capstone Disassembly Engine 2*9a0e4156SSadaf Ebrahimi * By Nguyen Anh Quynh <[email protected]>, 2013-2014 *) 3*9a0e4156SSadaf Ebrahimi 4*9a0e4156SSadaf Ebrahimiopen Printf 5*9a0e4156SSadaf Ebrahimiopen List 6*9a0e4156SSadaf Ebrahimiopen Capstone 7*9a0e4156SSadaf Ebrahimi 8*9a0e4156SSadaf Ebrahimilet _X86_CODE16 = "\x8d\x4c\x32\x08\x01\xd8\x81\xc6\x34\x12\x00\x00";; 9*9a0e4156SSadaf Ebrahimilet _X86_CODE32 = "\x8d\x4c\x32\x08\x01\xd8\x81\xc6\x34\x12\x00\x00";; 10*9a0e4156SSadaf Ebrahimilet _X86_CODE64 = "\x55\x48\x8b\x05\xb8\x13\x00\x00";; 11*9a0e4156SSadaf Ebrahimilet _ARM_CODE = "\xED\xFF\xFF\xEB\x04\xe0\x2d\xe5\x00\x00\x00\x00\xe0\x83\x22\xe5\xf1\x02\x03\x0e\x00\x00\xa0\xe3\x02\x30\xc1\xe7\x00\x00\x53\xe3";; 12*9a0e4156SSadaf Ebrahimilet _ARM_CODE2 = "\x10\xf1\x10\xe7\x11\xf2\x31\xe7\xdc\xa1\x2e\xf3\xe8\x4e\x62\xf3";; 13*9a0e4156SSadaf Ebrahimilet _THUMB_CODE = "\x70\x47\xeb\x46\x83\xb0\xc9\x68";; 14*9a0e4156SSadaf Ebrahimilet _THUMB_CODE2 = "\x4f\xf0\x00\x01\xbd\xe8\x00\x88";; 15*9a0e4156SSadaf Ebrahimilet _MIPS_CODE = "\x0C\x10\x00\x97\x00\x00\x00\x00\x24\x02\x00\x0c\x8f\xa2\x00\x00\x34\x21\x34\x56";; 16*9a0e4156SSadaf Ebrahimilet _MIPS_CODE2 = "\x56\x34\x21\x34\xc2\x17\x01\x00";; 17*9a0e4156SSadaf Ebrahimilet _ARM64_CODE = "\x21\x7c\x02\x9b\x21\x7c\x00\x53\x00\x40\x21\x4b\xe1\x0b\x40\xb9";; 18*9a0e4156SSadaf Ebrahimilet _PPC_CODE = "\x80\x20\x00\x00\x80\x3f\x00\x00\x10\x43\x23\x0e\xd0\x44\x00\x80\x4c\x43\x22\x02\x2d\x03\x00\x80\x7c\x43\x20\x14\x7c\x43\x20\x93\x4f\x20\x00\x21\x4c\xc8\x00\x21";; 19*9a0e4156SSadaf Ebrahimilet _SPARC_CODE = "\x80\xa0\x40\x02\x85\xc2\x60\x08\x85\xe8\x20\x01\x81\xe8\x00\x00\x90\x10\x20\x01\xd5\xf6\x10\x16\x21\x00\x00\x0a\x86\x00\x40\x02\x01\x00\x00\x00\x12\xbf\xff\xff\x10\xbf\xff\xff\xa0\x02\x00\x09\x0d\xbf\xff\xff\xd4\x20\x60\x00\xd4\x4e\x00\x16\x2a\xc2\x80\x03";; 20*9a0e4156SSadaf Ebrahimilet _SPARCV9_CODE = "\x81\xa8\x0a\x24\x89\xa0\x10\x20\x89\xa0\x1a\x60\x89\xa0\x00\xe0";; 21*9a0e4156SSadaf Ebrahimilet _SYSZ_CODE = "\xed\x00\x00\x00\x00\x1a\x5a\x0f\x1f\xff\xc2\x09\x80\x00\x00\x00\x07\xf7\xeb\x2a\xff\xff\x7f\x57\xe3\x01\xff\xff\x7f\x57\xeb\x00\xf0\x00\x00\x24\xb2\x4f\x00\x78";; 22*9a0e4156SSadaf Ebrahimilet _XCORE_CODE = "\xfe\x0f\xfe\x17\x13\x17\xc6\xfe\xec\x17\x97\xf8\xec\x4f\x1f\xfd\xec\x37\x07\xf2\x45\x5b\xf9\xfa\x02\x06\x1b\x10";; 23*9a0e4156SSadaf Ebrahimi 24*9a0e4156SSadaf Ebrahimilet all_tests = [ 25*9a0e4156SSadaf Ebrahimi (CS_ARCH_X86, [CS_MODE_16], _X86_CODE16, "X86 16bit (Intel syntax)", 0L); 26*9a0e4156SSadaf Ebrahimi (CS_ARCH_X86, [CS_MODE_32], _X86_CODE32, "X86 32bit (ATT syntax)", _CS_OPT_SYNTAX_ATT); 27*9a0e4156SSadaf Ebrahimi (CS_ARCH_X86, [CS_MODE_32], _X86_CODE32, "X86 32 (Intel syntax)", 0L); 28*9a0e4156SSadaf Ebrahimi (CS_ARCH_X86, [CS_MODE_64], _X86_CODE64, "X86 64 (Intel syntax)", 0L); 29*9a0e4156SSadaf Ebrahimi (CS_ARCH_ARM, [CS_MODE_ARM], _ARM_CODE, "ARM", 0L); 30*9a0e4156SSadaf Ebrahimi (CS_ARCH_ARM, [CS_MODE_ARM], _ARM_CODE2, "ARM: Cortex-A15 + NEON", 0L); 31*9a0e4156SSadaf Ebrahimi (CS_ARCH_ARM, [CS_MODE_THUMB], _THUMB_CODE, "THUMB", 0L); 32*9a0e4156SSadaf Ebrahimi (CS_ARCH_ARM, [CS_MODE_THUMB], _THUMB_CODE2, "THUMB-2", 0L); 33*9a0e4156SSadaf Ebrahimi (CS_ARCH_ARM64, [CS_MODE_ARM], _ARM64_CODE, "ARM-64", 0L); 34*9a0e4156SSadaf Ebrahimi (CS_ARCH_MIPS, [CS_MODE_MIPS32; CS_MODE_BIG_ENDIAN], _MIPS_CODE, "MIPS-32 (Big-endian)", 0L); 35*9a0e4156SSadaf Ebrahimi (CS_ARCH_MIPS, [CS_MODE_MIPS64; CS_MODE_LITTLE_ENDIAN], _MIPS_CODE2, "MIPS-64-EL (Little-endian)", 0L); 36*9a0e4156SSadaf Ebrahimi (CS_ARCH_PPC, [CS_MODE_BIG_ENDIAN], _PPC_CODE, "PPC-64", 0L); 37*9a0e4156SSadaf Ebrahimi (CS_ARCH_PPC, [CS_MODE_BIG_ENDIAN], _PPC_CODE, "PPC-64, print register with number only", 0L); 38*9a0e4156SSadaf Ebrahimi (CS_ARCH_SPARC, [CS_MODE_BIG_ENDIAN], _SPARC_CODE, "Sparc", 0L); 39*9a0e4156SSadaf Ebrahimi (CS_ARCH_SPARC, [CS_MODE_BIG_ENDIAN; CS_MODE_V9], _SPARCV9_CODE, "SparcV9", 0L); 40*9a0e4156SSadaf Ebrahimi (CS_ARCH_SYSZ, [CS_MODE_LITTLE_ENDIAN], _SYSZ_CODE, "SystemZ", 0L); 41*9a0e4156SSadaf Ebrahimi (CS_ARCH_XCORE, [CS_MODE_LITTLE_ENDIAN], _XCORE_CODE, "XCore", 0L); 42*9a0e4156SSadaf Ebrahimi];; 43*9a0e4156SSadaf Ebrahimi 44*9a0e4156SSadaf Ebrahimi 45*9a0e4156SSadaf Ebrahimilet print_insn insn = 46*9a0e4156SSadaf Ebrahimi printf "0x%x\t%s\t%s\n" insn.address insn.mnemonic insn.op_str;; 47*9a0e4156SSadaf Ebrahimi 48*9a0e4156SSadaf Ebrahimilet print_arch x = 49*9a0e4156SSadaf Ebrahimi let (arch, mode, code, comment, syntax) = x in 50*9a0e4156SSadaf Ebrahimi let handle = cs_open arch mode in ( 51*9a0e4156SSadaf Ebrahimi if syntax != 0L then ( 52*9a0e4156SSadaf Ebrahimi let err = cs_option handle CS_OPT_SYNTAX syntax in 53*9a0e4156SSadaf Ebrahimi match err with 54*9a0e4156SSadaf Ebrahimi | _ -> (); 55*9a0e4156SSadaf Ebrahimi ); 56*9a0e4156SSadaf Ebrahimi let insns = cs_disasm handle code 0x1000L 0L in ( 57*9a0e4156SSadaf Ebrahimi printf "*************\n"; 58*9a0e4156SSadaf Ebrahimi printf "Platform: %s\n" comment; 59*9a0e4156SSadaf Ebrahimi List.iter print_insn insns; 60*9a0e4156SSadaf Ebrahimi ); 61*9a0e4156SSadaf Ebrahimi match cs_close handle with 62*9a0e4156SSadaf Ebrahimi | 0 -> (); 63*9a0e4156SSadaf Ebrahimi | _ -> printf "Failed to close handle"; 64*9a0e4156SSadaf Ebrahimi );; 65*9a0e4156SSadaf Ebrahimi 66*9a0e4156SSadaf Ebrahimi 67*9a0e4156SSadaf EbrahimiList.iter print_arch all_tests;; 68