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 Arm 7*9a0e4156SSadaf Ebrahimiopen Arm_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 _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";; 19*9a0e4156SSadaf Ebrahimilet _ARM_CODE2 = "\xd1\xe8\x00\xf0\xf0\x24\x04\x07\x1f\x3c\xf2\xc0\x00\x00\x4f\xf0\x00\x01\x46\x6c";; 20*9a0e4156SSadaf Ebrahimilet _THUMB_CODE2 = "\x4f\xf0\x00\x01\xbd\xe8\x00\x88\xd1\xe8\x00\xf0";; 21*9a0e4156SSadaf Ebrahimilet _THUMB_CODE = "\x70\x47\xeb\x46\x83\xb0\xc9\x68\x1f\xb1";; 22*9a0e4156SSadaf Ebrahimi 23*9a0e4156SSadaf Ebrahimi 24*9a0e4156SSadaf Ebrahimilet all_tests = [ 25*9a0e4156SSadaf Ebrahimi (CS_ARCH_ARM, [CS_MODE_ARM], _ARM_CODE, "ARM"); 26*9a0e4156SSadaf Ebrahimi (CS_ARCH_ARM, [CS_MODE_THUMB], _THUMB_CODE, "Thumb"); 27*9a0e4156SSadaf Ebrahimi (CS_ARCH_ARM, [CS_MODE_THUMB], _ARM_CODE2, "Thumb-mixed"); 28*9a0e4156SSadaf Ebrahimi (CS_ARCH_ARM, [CS_MODE_THUMB], _THUMB_CODE2, "Thumb-2"); 29*9a0e4156SSadaf Ebrahimi];; 30*9a0e4156SSadaf Ebrahimi 31*9a0e4156SSadaf Ebrahimi 32*9a0e4156SSadaf Ebrahimilet print_op handle i op = 33*9a0e4156SSadaf Ebrahimi ( match op.value with 34*9a0e4156SSadaf Ebrahimi | ARM_OP_INVALID _ -> (); (* this would never happens *) 35*9a0e4156SSadaf Ebrahimi | ARM_OP_REG reg -> printf "\t\top[%d]: REG = %s\n" i (cs_reg_name handle reg); 36*9a0e4156SSadaf Ebrahimi | ARM_OP_CIMM imm -> printf "\t\top[%d]: C-IMM = %u\n" i imm; 37*9a0e4156SSadaf Ebrahimi | ARM_OP_PIMM imm -> printf "\t\top[%d]: P-IMM = %u\n" i imm; 38*9a0e4156SSadaf Ebrahimi | ARM_OP_IMM imm -> printf "\t\top[%d]: IMM = 0x%x\n" i imm; 39*9a0e4156SSadaf Ebrahimi | ARM_OP_FP fp -> printf "\t\top[%d]: FP = %f\n" i fp; 40*9a0e4156SSadaf Ebrahimi | ARM_OP_MEM mem -> ( printf "\t\top[%d]: MEM\n" i; 41*9a0e4156SSadaf Ebrahimi if mem.base != 0 then 42*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.base: REG = %s\n" i (cs_reg_name handle mem.base); 43*9a0e4156SSadaf Ebrahimi if mem.index != 0 then 44*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.index: REG = %s\n" i (cs_reg_name handle mem.index); 45*9a0e4156SSadaf Ebrahimi if mem.scale != 1 then 46*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.scale: %d\n" i mem.scale; 47*9a0e4156SSadaf Ebrahimi if mem.disp != 0 then 48*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.disp: 0x%x\n" i mem.disp; 49*9a0e4156SSadaf Ebrahimi if mem.lshift != 0 then 50*9a0e4156SSadaf Ebrahimi printf "\t\t\toperands[%u].mem.lshift: 0x%x\n" i mem.lshift; 51*9a0e4156SSadaf Ebrahimi ); 52*9a0e4156SSadaf Ebrahimi | ARM_OP_SETEND sd -> printf "\t\top[%d]: SETEND = %u\n" i sd; 53*9a0e4156SSadaf Ebrahimi ); 54*9a0e4156SSadaf Ebrahimi 55*9a0e4156SSadaf Ebrahimi if op.shift.shift_type != _ARM_SFT_INVALID && op.shift.shift_value > 0 then 56*9a0e4156SSadaf Ebrahimi printf "\t\t\tShift: type = %u, value = %u\n" 57*9a0e4156SSadaf Ebrahimi op.shift.shift_type op.shift.shift_value; 58*9a0e4156SSadaf Ebrahimi ();; 59*9a0e4156SSadaf Ebrahimi 60*9a0e4156SSadaf Ebrahimi 61*9a0e4156SSadaf Ebrahimilet print_detail handle insn = 62*9a0e4156SSadaf Ebrahimi match insn.arch with 63*9a0e4156SSadaf Ebrahimi | CS_INFO_ARM arm -> ( 64*9a0e4156SSadaf Ebrahimi if arm.cc != _ARM_CC_AL && arm.cc != _ARM_CC_INVALID then 65*9a0e4156SSadaf Ebrahimi printf "\tCode condition: %u\n" arm.cc; 66*9a0e4156SSadaf Ebrahimi 67*9a0e4156SSadaf Ebrahimi if arm.update_flags then 68*9a0e4156SSadaf Ebrahimi printf "\tUpdate-flags: True\n"; 69*9a0e4156SSadaf Ebrahimi 70*9a0e4156SSadaf Ebrahimi if arm.writeback then 71*9a0e4156SSadaf Ebrahimi printf "\tWriteback: True\n"; 72*9a0e4156SSadaf Ebrahimi 73*9a0e4156SSadaf Ebrahimi (* print all operands info (type & value) *) 74*9a0e4156SSadaf Ebrahimi if (Array.length arm.operands) > 0 then ( 75*9a0e4156SSadaf Ebrahimi printf "\top_count: %d\n" (Array.length arm.operands); 76*9a0e4156SSadaf Ebrahimi Array.iteri (print_op handle) arm.operands; 77*9a0e4156SSadaf Ebrahimi ); 78*9a0e4156SSadaf Ebrahimi printf "\n"; 79*9a0e4156SSadaf Ebrahimi ); 80*9a0e4156SSadaf Ebrahimi | _ -> (); 81*9a0e4156SSadaf Ebrahimi ;; 82*9a0e4156SSadaf Ebrahimi 83*9a0e4156SSadaf Ebrahimi 84*9a0e4156SSadaf Ebrahimilet print_insn handle insn = 85*9a0e4156SSadaf Ebrahimi printf "0x%x\t%s\t%s\n" insn.address insn.mnemonic insn.op_str; 86*9a0e4156SSadaf Ebrahimi print_detail handle insn 87*9a0e4156SSadaf Ebrahimi 88*9a0e4156SSadaf Ebrahimi 89*9a0e4156SSadaf Ebrahimilet print_arch x = 90*9a0e4156SSadaf Ebrahimi let (arch, mode, code, comment) = x in 91*9a0e4156SSadaf Ebrahimi let handle = cs_open arch mode in 92*9a0e4156SSadaf Ebrahimi let err = cs_option handle CS_OPT_DETAIL _CS_OPT_ON in 93*9a0e4156SSadaf Ebrahimi match err with 94*9a0e4156SSadaf Ebrahimi | _ -> (); 95*9a0e4156SSadaf Ebrahimi let insns = cs_disasm handle code 0x1000L 0L in 96*9a0e4156SSadaf Ebrahimi printf "*************\n"; 97*9a0e4156SSadaf Ebrahimi printf "Platform: %s\n" comment; 98*9a0e4156SSadaf Ebrahimi List.iter (print_insn handle) insns; 99*9a0e4156SSadaf Ebrahimi match cs_close handle with 100*9a0e4156SSadaf Ebrahimi | 0 -> (); 101*9a0e4156SSadaf Ebrahimi | _ -> printf "Failed to close handle"; 102*9a0e4156SSadaf Ebrahimi ;; 103*9a0e4156SSadaf Ebrahimi 104*9a0e4156SSadaf Ebrahimi 105*9a0e4156SSadaf EbrahimiList.iter print_arch all_tests;; 106