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 Capstone 6*9a0e4156SSadaf Ebrahimiopen X86 7*9a0e4156SSadaf Ebrahimiopen X86_const 8*9a0e4156SSadaf Ebrahimi 9*9a0e4156SSadaf Ebrahimi 10*9a0e4156SSadaf Ebrahimilet print_string_hex comment str = 11*9a0e4156SSadaf Ebrahimi printf "%s" comment; 12*9a0e4156SSadaf Ebrahimi for i = 0 to (Array.length str - 1) do 13*9a0e4156SSadaf Ebrahimi printf "0x%02x " str.(i) 14*9a0e4156SSadaf Ebrahimi done; 15*9a0e4156SSadaf Ebrahimi printf "\n" 16*9a0e4156SSadaf Ebrahimi 17*9a0e4156SSadaf Ebrahimi 18*9a0e4156SSadaf Ebrahimilet _X86_CODE16 = "\x8d\x4c\x32\x08\x01\xd8\x81\xc6\x34\x12\x00\x00";; 19*9a0e4156SSadaf Ebrahimilet _X86_CODE32 = "\x8d\x4c\x32\x08\x01\xd8\x81\xc6\x34\x12\x00\x00";; 20*9a0e4156SSadaf Ebrahimilet _X86_CODE64 = "\x55\x48\x8b\x05\xb8\x13\x00\x00";; 21*9a0e4156SSadaf Ebrahimi 22*9a0e4156SSadaf Ebrahimi 23*9a0e4156SSadaf Ebrahimilet all_tests = [ 24*9a0e4156SSadaf Ebrahimi (CS_ARCH_X86, [CS_MODE_16], _X86_CODE16, "X86 16bit (Intel syntax)", 0L); 25*9a0e4156SSadaf Ebrahimi (CS_ARCH_X86, [CS_MODE_32], _X86_CODE32, "X86 32bit (ATT syntax)", _CS_OPT_SYNTAX_ATT); 26*9a0e4156SSadaf Ebrahimi (CS_ARCH_X86, [CS_MODE_32], _X86_CODE32, "X86 32 (Intel syntax)", 0L); 27*9a0e4156SSadaf Ebrahimi (CS_ARCH_X86, [CS_MODE_64], _X86_CODE64, "X86 64 (Intel syntax)", 0L); 28*9a0e4156SSadaf Ebrahimi];; 29*9a0e4156SSadaf Ebrahimi 30*9a0e4156SSadaf Ebrahimilet print_op handle i op = 31*9a0e4156SSadaf Ebrahimi ( match op.value with 32*9a0e4156SSadaf Ebrahimi | X86_OP_INVALID _ -> (); (* this would never happens *) 33*9a0e4156SSadaf Ebrahimi | X86_OP_REG reg -> printf "\t\top[%d]: REG = %s [sz=%d]\n" i (cs_reg_name handle reg) op.size; 34*9a0e4156SSadaf Ebrahimi | X86_OP_IMM imm -> printf "\t\top[%d]: IMM = 0x%x [sz=%d]\n" i imm op.size; 35*9a0e4156SSadaf Ebrahimi | X86_OP_MEM mem -> ( printf "\t\top[%d]: MEM [sz=%d]\n" i op.size; 36*9a0e4156SSadaf Ebrahimi if mem.base != 0 then 37*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.base: REG = %s\n" i (cs_reg_name handle mem.base); 38*9a0e4156SSadaf Ebrahimi if mem.index != 0 then 39*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.index: REG = %s\n" i (cs_reg_name handle mem.index); 40*9a0e4156SSadaf Ebrahimi if mem.scale != 1 then 41*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.scale: %d\n" i mem.scale; 42*9a0e4156SSadaf Ebrahimi if mem.disp != 0 then 43*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.disp: 0x%x\n" i mem.disp; 44*9a0e4156SSadaf Ebrahimi ); 45*9a0e4156SSadaf Ebrahimi ); 46*9a0e4156SSadaf Ebrahimi ();; 47*9a0e4156SSadaf Ebrahimi 48*9a0e4156SSadaf Ebrahimi 49*9a0e4156SSadaf Ebrahimilet print_detail handle mode insn = 50*9a0e4156SSadaf Ebrahimi match insn.arch with 51*9a0e4156SSadaf Ebrahimi | CS_INFO_X86 x86 -> ( 52*9a0e4156SSadaf Ebrahimi print_string_hex "\tPrefix: " x86.prefix; 53*9a0e4156SSadaf Ebrahimi 54*9a0e4156SSadaf Ebrahimi (* print instruction's opcode *) 55*9a0e4156SSadaf Ebrahimi print_string_hex "\tOpcode: " x86.opcode; 56*9a0e4156SSadaf Ebrahimi 57*9a0e4156SSadaf Ebrahimi (* print operand's size, address size, displacement size & immediate size *) 58*9a0e4156SSadaf Ebrahimi printf "\taddr_size: %u\n" x86.addr_size; 59*9a0e4156SSadaf Ebrahimi 60*9a0e4156SSadaf Ebrahimi (* print modRM byte *) 61*9a0e4156SSadaf Ebrahimi printf "\tmodrm: 0x%x\n" x86.modrm; 62*9a0e4156SSadaf Ebrahimi 63*9a0e4156SSadaf Ebrahimi (* print displacement value *) 64*9a0e4156SSadaf Ebrahimi if x86.disp != 0 then 65*9a0e4156SSadaf Ebrahimi printf "\tdisp: 0x%x\n" x86.disp; 66*9a0e4156SSadaf Ebrahimi 67*9a0e4156SSadaf Ebrahimi (* SIB is invalid in 16-bit mode *) 68*9a0e4156SSadaf Ebrahimi if not (List.mem CS_MODE_16 mode) then ( 69*9a0e4156SSadaf Ebrahimi (* print SIB byte *) 70*9a0e4156SSadaf Ebrahimi printf "\tsib: 0x%x\n" x86.sib; 71*9a0e4156SSadaf Ebrahimi 72*9a0e4156SSadaf Ebrahimi (* print sib index/scale/base (if applicable) *) 73*9a0e4156SSadaf Ebrahimi if x86.sib_index != _X86_REG_INVALID then 74*9a0e4156SSadaf Ebrahimi printf "\tsib_index: %s, sib_scale: %u, sib_base: %s\n" 75*9a0e4156SSadaf Ebrahimi (cs_reg_name handle x86.sib_index) 76*9a0e4156SSadaf Ebrahimi x86.sib_scale 77*9a0e4156SSadaf Ebrahimi (cs_reg_name handle x86.sib_base); 78*9a0e4156SSadaf Ebrahimi ); 79*9a0e4156SSadaf Ebrahimi 80*9a0e4156SSadaf Ebrahimi (* print all operands info (type & value) *) 81*9a0e4156SSadaf Ebrahimi if (Array.length x86.operands) > 0 then ( 82*9a0e4156SSadaf Ebrahimi printf "\top_count: %d\n" (Array.length x86.operands); 83*9a0e4156SSadaf Ebrahimi Array.iteri (print_op handle) x86.operands; 84*9a0e4156SSadaf Ebrahimi ); 85*9a0e4156SSadaf Ebrahimi printf "\n"; 86*9a0e4156SSadaf Ebrahimi ); 87*9a0e4156SSadaf Ebrahimi | _ -> (); 88*9a0e4156SSadaf Ebrahimi ;; 89*9a0e4156SSadaf Ebrahimi 90*9a0e4156SSadaf Ebrahimi 91*9a0e4156SSadaf Ebrahimilet print_insn handle mode insn = 92*9a0e4156SSadaf Ebrahimi printf "0x%x\t%s\t%s\n" insn.address insn.mnemonic insn.op_str; 93*9a0e4156SSadaf Ebrahimi print_detail handle mode insn 94*9a0e4156SSadaf Ebrahimi 95*9a0e4156SSadaf Ebrahimi 96*9a0e4156SSadaf Ebrahimilet print_arch x = 97*9a0e4156SSadaf Ebrahimi let (arch, mode, code, comment, syntax) = x in 98*9a0e4156SSadaf Ebrahimi let handle = cs_open arch mode in ( 99*9a0e4156SSadaf Ebrahimi if syntax != 0L then ( 100*9a0e4156SSadaf Ebrahimi let err = cs_option handle CS_OPT_SYNTAX syntax in 101*9a0e4156SSadaf Ebrahimi match err with 102*9a0e4156SSadaf Ebrahimi | _ -> (); 103*9a0e4156SSadaf Ebrahimi ); 104*9a0e4156SSadaf Ebrahimi let err = cs_option handle CS_OPT_DETAIL _CS_OPT_ON in 105*9a0e4156SSadaf Ebrahimi match err with 106*9a0e4156SSadaf Ebrahimi | _ -> (); 107*9a0e4156SSadaf Ebrahimi let insns = cs_disasm handle code 0x1000L 0L in ( 108*9a0e4156SSadaf Ebrahimi printf "*************\n"; 109*9a0e4156SSadaf Ebrahimi printf "Platform: %s\n" comment; 110*9a0e4156SSadaf Ebrahimi List.iter (print_insn handle mode) insns; 111*9a0e4156SSadaf Ebrahimi ); 112*9a0e4156SSadaf Ebrahimi match cs_close handle with 113*9a0e4156SSadaf Ebrahimi | 0 -> (); 114*9a0e4156SSadaf Ebrahimi | _ -> printf "Failed to close handle"; 115*9a0e4156SSadaf Ebrahimi );; 116*9a0e4156SSadaf Ebrahimi 117*9a0e4156SSadaf EbrahimiList.iter print_arch all_tests;; 118