xref: /aosp_15_r20/external/capstone/bindings/ocaml/test_x86.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 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