xref: /aosp_15_r20/external/capstone/bindings/ocaml/test_arm.ml (revision 9a0e4156d50a75a99ec4f1653a0e9602a5d45c18)
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