1*9a0e4156SSadaf Ebrahimi(* Capstone Disassembly Engine 2*9a0e4156SSadaf Ebrahimi* By Guillaume Jeanne <[email protected]>, 2014> *) 3*9a0e4156SSadaf Ebrahimi 4*9a0e4156SSadaf Ebrahimiopen Printf 5*9a0e4156SSadaf Ebrahimiopen Capstone 6*9a0e4156SSadaf Ebrahimiopen Ppc 7*9a0e4156SSadaf Ebrahimi 8*9a0e4156SSadaf Ebrahimi 9*9a0e4156SSadaf Ebrahimilet print_string_hex comment str = 10*9a0e4156SSadaf Ebrahimi printf "%s" comment; 11*9a0e4156SSadaf Ebrahimi for i = 0 to (Array.length str - 1) do 12*9a0e4156SSadaf Ebrahimi printf "0x%02x " str.(i) 13*9a0e4156SSadaf Ebrahimi done; 14*9a0e4156SSadaf Ebrahimi printf "\n" 15*9a0e4156SSadaf Ebrahimi 16*9a0e4156SSadaf Ebrahimi 17*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";; 18*9a0e4156SSadaf Ebrahimi 19*9a0e4156SSadaf Ebrahimilet all_tests = [ 20*9a0e4156SSadaf Ebrahimi (CS_ARCH_PPC, [CS_MODE_64; CS_MODE_BIG_ENDIAN], _PPC_CODE, "PPC-64"); 21*9a0e4156SSadaf Ebrahimi];; 22*9a0e4156SSadaf Ebrahimi 23*9a0e4156SSadaf Ebrahimilet print_op handle i op = 24*9a0e4156SSadaf Ebrahimi ( match op.value with 25*9a0e4156SSadaf Ebrahimi | PPC_OP_INVALID _ -> (); (* this would never happens *) 26*9a0e4156SSadaf Ebrahimi | PPC_OP_REG reg -> printf "\t\top[%d]: REG = %s\n" i (cs_reg_name handle reg); 27*9a0e4156SSadaf Ebrahimi | PPC_OP_IMM imm -> printf "\t\top[%d]: IMM = 0x%x\n" i imm; 28*9a0e4156SSadaf Ebrahimi | PPC_OP_MEM mem -> ( printf "\t\top[%d]: MEM\n" i; 29*9a0e4156SSadaf Ebrahimi if mem.base != 0 then 30*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.base: REG = %s\n" i (cs_reg_name handle mem.base); 31*9a0e4156SSadaf Ebrahimi if mem.disp != 0 then 32*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.disp: 0x%x\n" i mem.disp; 33*9a0e4156SSadaf Ebrahimi ); 34*9a0e4156SSadaf Ebrahimi | PPC_OP_CRX crx -> ( printf "\t\top[%d]: CRX\n" i; 35*9a0e4156SSadaf Ebrahimi if crx.scale != 0 then 36*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].crx.scale = %u\n" i crx.scale; 37*9a0e4156SSadaf Ebrahimi if crx.reg != 0 then 38*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].crx.reg = %s\n" i (cs_reg_name handle crx.reg); 39*9a0e4156SSadaf Ebrahimi if crx.cond != 0 then 40*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].crx.cond = 0x%x\n" i crx.cond; 41*9a0e4156SSadaf Ebrahimi ); 42*9a0e4156SSadaf Ebrahimi ); 43*9a0e4156SSadaf Ebrahimi ();; 44*9a0e4156SSadaf Ebrahimi 45*9a0e4156SSadaf Ebrahimi 46*9a0e4156SSadaf Ebrahimilet print_detail handle insn = 47*9a0e4156SSadaf Ebrahimi match insn.arch with 48*9a0e4156SSadaf Ebrahimi | CS_INFO_PPC ppc -> ( 49*9a0e4156SSadaf Ebrahimi (* print all operands info (type & value) *) 50*9a0e4156SSadaf Ebrahimi if (Array.length ppc.operands) > 0 then ( 51*9a0e4156SSadaf Ebrahimi printf "\top_count: %d\n" (Array.length ppc.operands); 52*9a0e4156SSadaf Ebrahimi Array.iteri (print_op handle) ppc.operands; 53*9a0e4156SSadaf Ebrahimi ); 54*9a0e4156SSadaf Ebrahimi printf "\n"; 55*9a0e4156SSadaf Ebrahimi ); 56*9a0e4156SSadaf Ebrahimi | _ -> (); 57*9a0e4156SSadaf Ebrahimi ;; 58*9a0e4156SSadaf Ebrahimi 59*9a0e4156SSadaf Ebrahimi 60*9a0e4156SSadaf Ebrahimilet print_insn handle insn = 61*9a0e4156SSadaf Ebrahimi printf "0x%x\t%s\t%s\n" insn.address insn.mnemonic insn.op_str; 62*9a0e4156SSadaf Ebrahimi print_detail handle insn 63*9a0e4156SSadaf Ebrahimi 64*9a0e4156SSadaf Ebrahimi 65*9a0e4156SSadaf Ebrahimilet print_arch x = 66*9a0e4156SSadaf Ebrahimi let (arch, mode, code, comment) = x in 67*9a0e4156SSadaf Ebrahimi let handle = cs_open arch mode in 68*9a0e4156SSadaf Ebrahimi let err = cs_option handle CS_OPT_DETAIL _CS_OPT_ON in 69*9a0e4156SSadaf Ebrahimi match err with 70*9a0e4156SSadaf Ebrahimi | _ -> (); 71*9a0e4156SSadaf Ebrahimi let insns = cs_disasm handle code 0x1000L 0L in 72*9a0e4156SSadaf Ebrahimi printf "*************\n"; 73*9a0e4156SSadaf Ebrahimi printf "Platform: %s\n" comment; 74*9a0e4156SSadaf Ebrahimi List.iter (print_insn handle) insns; 75*9a0e4156SSadaf Ebrahimi match cs_close handle with 76*9a0e4156SSadaf Ebrahimi | 0 -> (); 77*9a0e4156SSadaf Ebrahimi | _ -> printf "Failed to close handle"; 78*9a0e4156SSadaf Ebrahimi ;; 79*9a0e4156SSadaf Ebrahimi 80*9a0e4156SSadaf Ebrahimi 81*9a0e4156SSadaf EbrahimiList.iter print_arch all_tests;; 82