1 /* Pretty formatting of GIMPLE statements and expressions.
2 Copyright (C) 2001-2019 Free Software Foundation, Inc.
3 Contributed by Aldy Hernandez <aldyh@redhat.com> and
4 Diego Novillo <dnovillo@google.com>
6 This file is part of GCC.
8 GCC is free software; you can redistribute it and/or modify it under
9 the terms of the GNU General Public License as published by the Free
10 Software Foundation; either version 3, or (at your option) any later
13 GCC is distributed in the hope that it will be useful, but WITHOUT ANY
14 WARRANTY; without even the implied warranty of MERCHANTABILITY or
15 FITNESS FOR A PARTICULAR PURPOSE. See the GNU General Public License
18 You should have received a copy of the GNU General Public License
19 along with GCC; see the file COPYING3. If not see
20 <http://www.gnu.org/licenses/>. */
24 #include "coretypes.h"
29 #include "gimple-predict.h"
32 #include "gimple-pretty-print.h"
33 #include "internal-fn.h"
35 #include "gimple-iterator.h"
37 #include "dumpfile.h" /* for dump_flags */
38 #include "value-prof.h"
39 #include "trans-mem.h"
41 #include "stringpool.h"
46 #define INDENT(SPACE) \
47 do { int i; for (i = 0; i < SPACE; i++) pp_space (buffer); } while (0)
49 #define GIMPLE_NIY do_niy (buffer,gs)
51 /* Try to print on BUFFER a default message for the unrecognized
52 gimple statement GS. */
55 do_niy (pretty_printer
*buffer
, gimple
*gs
)
57 pp_printf (buffer
, "<<< Unknown GIMPLE statement: %s >>>\n",
58 gimple_code_name
[(int) gimple_code (gs
)]);
62 /* Emit a newline and SPC indentation spaces to BUFFER. */
65 newline_and_indent (pretty_printer
*buffer
, int spc
)
72 /* Print the GIMPLE statement GS on stderr. */
75 debug_gimple_stmt (gimple
*gs
)
77 print_gimple_stmt (stderr
, gs
, 0, TDF_VOPS
|TDF_MEMSYMS
);
81 /* Return formatted string of a VALUE probability
82 (biased by REG_BR_PROB_BASE). Returned string is allocated
83 by xstrdup_for_dump. */
86 dump_profile (profile_count
&count
)
89 if (!count
.initialized_p ())
92 buf
= xasprintf ("[count: %" PRId64
"]",
93 count
.to_gcov_type ());
94 else if (count
.initialized_p ())
95 buf
= xasprintf ("[local count: %" PRId64
"]",
96 count
.to_gcov_type ());
98 const char *ret
= xstrdup_for_dump (buf
);
104 /* Return formatted string of a VALUE probability
105 (biased by REG_BR_PROB_BASE). Returned string is allocated
106 by xstrdup_for_dump. */
109 dump_probability (profile_probability probability
)
111 float minimum
= 0.01f
;
114 if (probability
.initialized_p ())
116 fvalue
= probability
.to_reg_br_prob_base () * 100.0f
/ REG_BR_PROB_BASE
;
117 if (fvalue
< minimum
&& probability
.to_reg_br_prob_base ())
122 if (probability
.initialized_p ())
123 buf
= xasprintf ("[%.2f%%]", fvalue
);
125 buf
= xasprintf ("[INV]");
127 const char *ret
= xstrdup_for_dump (buf
);
133 /* Dump E probability to BUFFER. */
136 dump_edge_probability (pretty_printer
*buffer
, edge e
)
138 pp_scalar (buffer
, " %s", dump_probability (e
->probability
));
141 /* Print GIMPLE statement G to FILE using SPC indentation spaces and
142 FLAGS as in pp_gimple_stmt_1. */
145 print_gimple_stmt (FILE *file
, gimple
*g
, int spc
, dump_flags_t flags
)
147 pretty_printer buffer
;
148 pp_needs_newline (&buffer
) = true;
149 buffer
.buffer
->stream
= file
;
150 pp_gimple_stmt_1 (&buffer
, g
, spc
, flags
);
151 pp_newline_and_flush (&buffer
);
157 print_gimple_stmt (stderr
, &ref
, 0, TDF_NONE
);
166 fprintf (stderr
, "<nil>\n");
170 /* Print GIMPLE statement G to FILE using SPC indentation spaces and
171 FLAGS as in pp_gimple_stmt_1. Print only the right-hand side
175 print_gimple_expr (FILE *file
, gimple
*g
, int spc
, dump_flags_t flags
)
177 flags
|= TDF_RHS_ONLY
;
178 pretty_printer buffer
;
179 pp_needs_newline (&buffer
) = true;
180 buffer
.buffer
->stream
= file
;
181 pp_gimple_stmt_1 (&buffer
, g
, spc
, flags
);
186 /* Print the GIMPLE sequence SEQ on BUFFER using SPC indentation
187 spaces and FLAGS as in pp_gimple_stmt_1.
188 The caller is responsible for calling pp_flush on BUFFER to finalize
189 the pretty printer. */
192 dump_gimple_seq (pretty_printer
*buffer
, gimple_seq seq
, int spc
,
195 gimple_stmt_iterator i
;
197 for (i
= gsi_start (seq
); !gsi_end_p (i
); gsi_next (&i
))
199 gimple
*gs
= gsi_stmt (i
);
201 pp_gimple_stmt_1 (buffer
, gs
, spc
, flags
);
202 if (!gsi_one_before_end_p (i
))
208 /* Print GIMPLE sequence SEQ to FILE using SPC indentation spaces and
209 FLAGS as in pp_gimple_stmt_1. */
212 print_gimple_seq (FILE *file
, gimple_seq seq
, int spc
, dump_flags_t flags
)
214 pretty_printer buffer
;
215 pp_needs_newline (&buffer
) = true;
216 buffer
.buffer
->stream
= file
;
217 dump_gimple_seq (&buffer
, seq
, spc
, flags
);
218 pp_newline_and_flush (&buffer
);
222 /* Print the GIMPLE sequence SEQ on stderr. */
225 debug_gimple_seq (gimple_seq seq
)
227 print_gimple_seq (stderr
, seq
, 0, TDF_VOPS
|TDF_MEMSYMS
);
231 /* A simple helper to pretty-print some of the gimple tuples in the printf
232 style. The format modifiers are preceded by '%' and are:
233 'G' - outputs a string corresponding to the code of the given gimple,
234 'S' - outputs a gimple_seq with indent of spc + 2,
235 'T' - outputs the tree t,
236 'd' - outputs an int as a decimal,
237 's' - outputs a string,
238 'n' - outputs a newline,
239 'x' - outputs an int as hexadecimal,
240 '+' - increases indent by 2 then outputs a newline,
241 '-' - decreases indent by 2 then outputs a newline. */
244 dump_gimple_fmt (pretty_printer
*buffer
, int spc
, dump_flags_t flags
,
245 const char *fmt
, ...)
251 va_start (args
, fmt
);
252 for (c
= fmt
; *c
; c
++)
262 g
= va_arg (args
, gimple
*);
263 tmp
= gimple_code_name
[gimple_code (g
)];
264 pp_string (buffer
, tmp
);
268 seq
= va_arg (args
, gimple_seq
);
270 dump_gimple_seq (buffer
, seq
, spc
+ 2, flags
);
271 newline_and_indent (buffer
, spc
);
275 t
= va_arg (args
, tree
);
277 pp_string (buffer
, "NULL");
279 dump_generic_node (buffer
, t
, spc
, flags
, false);
283 pp_decimal_int (buffer
, va_arg (args
, int));
287 pp_string (buffer
, va_arg (args
, char *));
291 newline_and_indent (buffer
, spc
);
295 pp_scalar (buffer
, "%x", va_arg (args
, int));
300 newline_and_indent (buffer
, spc
);
305 newline_and_indent (buffer
, spc
);
313 pp_character (buffer
, *c
);
319 /* Helper for dump_gimple_assign. Print the unary RHS of the
320 assignment GS. BUFFER, SPC and FLAGS are as in pp_gimple_stmt_1. */
323 dump_unary_rhs (pretty_printer
*buffer
, gassign
*gs
, int spc
,
326 enum tree_code rhs_code
= gimple_assign_rhs_code (gs
);
327 tree lhs
= gimple_assign_lhs (gs
);
328 tree rhs
= gimple_assign_rhs1 (gs
);
332 case VIEW_CONVERT_EXPR
:
334 dump_generic_node (buffer
, rhs
, spc
, flags
, false);
337 case FIXED_CONVERT_EXPR
:
338 case ADDR_SPACE_CONVERT_EXPR
:
342 pp_left_paren (buffer
);
343 dump_generic_node (buffer
, TREE_TYPE (lhs
), spc
, flags
, false);
344 pp_string (buffer
, ") ");
345 if (op_prio (rhs
) < op_code_prio (rhs_code
))
347 pp_left_paren (buffer
);
348 dump_generic_node (buffer
, rhs
, spc
, flags
, false);
349 pp_right_paren (buffer
);
352 dump_generic_node (buffer
, rhs
, spc
, flags
, false);
356 pp_string (buffer
, "((");
357 dump_generic_node (buffer
, rhs
, spc
, flags
, false);
358 pp_string (buffer
, "))");
363 if (flags
& TDF_GIMPLE
)
366 rhs_code
== ABS_EXPR
? "__ABS " : "__ABSU ");
367 dump_generic_node (buffer
, rhs
, spc
, flags
, false);
372 rhs_code
== ABS_EXPR
? "ABS_EXPR <" : "ABSU_EXPR <");
373 dump_generic_node (buffer
, rhs
, spc
, flags
, false);
379 if (TREE_CODE_CLASS (rhs_code
) == tcc_declaration
380 || TREE_CODE_CLASS (rhs_code
) == tcc_constant
381 || TREE_CODE_CLASS (rhs_code
) == tcc_reference
382 || rhs_code
== SSA_NAME
383 || rhs_code
== ADDR_EXPR
384 || rhs_code
== CONSTRUCTOR
)
386 dump_generic_node (buffer
, rhs
, spc
, flags
, false);
389 else if (rhs_code
== BIT_NOT_EXPR
)
390 pp_complement (buffer
);
391 else if (rhs_code
== TRUTH_NOT_EXPR
)
392 pp_exclamation (buffer
);
393 else if (rhs_code
== NEGATE_EXPR
)
397 pp_left_bracket (buffer
);
398 pp_string (buffer
, get_tree_code_name (rhs_code
));
399 pp_string (buffer
, "] ");
402 if (op_prio (rhs
) < op_code_prio (rhs_code
))
404 pp_left_paren (buffer
);
405 dump_generic_node (buffer
, rhs
, spc
, flags
, false);
406 pp_right_paren (buffer
);
409 dump_generic_node (buffer
, rhs
, spc
, flags
, false);
415 /* Helper for dump_gimple_assign. Print the binary RHS of the
416 assignment GS. BUFFER, SPC and FLAGS are as in pp_gimple_stmt_1. */
419 dump_binary_rhs (pretty_printer
*buffer
, gassign
*gs
, int spc
,
423 enum tree_code code
= gimple_assign_rhs_code (gs
);
429 case VEC_WIDEN_MULT_HI_EXPR
:
430 case VEC_WIDEN_MULT_LO_EXPR
:
431 case VEC_WIDEN_MULT_EVEN_EXPR
:
432 case VEC_WIDEN_MULT_ODD_EXPR
:
433 case VEC_PACK_TRUNC_EXPR
:
434 case VEC_PACK_SAT_EXPR
:
435 case VEC_PACK_FIX_TRUNC_EXPR
:
436 case VEC_PACK_FLOAT_EXPR
:
437 case VEC_WIDEN_LSHIFT_HI_EXPR
:
438 case VEC_WIDEN_LSHIFT_LO_EXPR
:
439 case VEC_SERIES_EXPR
:
440 for (p
= get_tree_code_name (code
); *p
; p
++)
441 pp_character (buffer
, TOUPPER (*p
));
442 pp_string (buffer
, " <");
443 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
, false);
444 pp_string (buffer
, ", ");
445 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
, false);
450 if (op_prio (gimple_assign_rhs1 (gs
)) <= op_code_prio (code
))
452 pp_left_paren (buffer
);
453 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
,
455 pp_right_paren (buffer
);
458 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
, false);
460 pp_string (buffer
, op_symbol_code (gimple_assign_rhs_code (gs
)));
462 if (op_prio (gimple_assign_rhs2 (gs
)) <= op_code_prio (code
))
464 pp_left_paren (buffer
);
465 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
,
467 pp_right_paren (buffer
);
470 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
, false);
474 /* Helper for dump_gimple_assign. Print the ternary RHS of the
475 assignment GS. BUFFER, SPC and FLAGS are as in pp_gimple_stmt_1. */
478 dump_ternary_rhs (pretty_printer
*buffer
, gassign
*gs
, int spc
,
482 enum tree_code code
= gimple_assign_rhs_code (gs
);
485 case WIDEN_MULT_PLUS_EXPR
:
486 case WIDEN_MULT_MINUS_EXPR
:
487 for (p
= get_tree_code_name (code
); *p
; p
++)
488 pp_character (buffer
, TOUPPER (*p
));
489 pp_string (buffer
, " <");
490 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
, false);
491 pp_string (buffer
, ", ");
492 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
, false);
493 pp_string (buffer
, ", ");
494 dump_generic_node (buffer
, gimple_assign_rhs3 (gs
), spc
, flags
, false);
499 pp_string (buffer
, "DOT_PROD_EXPR <");
500 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
, false);
501 pp_string (buffer
, ", ");
502 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
, false);
503 pp_string (buffer
, ", ");
504 dump_generic_node (buffer
, gimple_assign_rhs3 (gs
), spc
, flags
, false);
509 pp_string (buffer
, "SAD_EXPR <");
510 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
, false);
511 pp_string (buffer
, ", ");
512 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
, false);
513 pp_string (buffer
, ", ");
514 dump_generic_node (buffer
, gimple_assign_rhs3 (gs
), spc
, flags
, false);
519 pp_string (buffer
, "VEC_PERM_EXPR <");
520 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
, false);
521 pp_string (buffer
, ", ");
522 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
, false);
523 pp_string (buffer
, ", ");
524 dump_generic_node (buffer
, gimple_assign_rhs3 (gs
), spc
, flags
, false);
528 case REALIGN_LOAD_EXPR
:
529 pp_string (buffer
, "REALIGN_LOAD <");
530 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
, false);
531 pp_string (buffer
, ", ");
532 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
, false);
533 pp_string (buffer
, ", ");
534 dump_generic_node (buffer
, gimple_assign_rhs3 (gs
), spc
, flags
, false);
539 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
, false);
540 pp_string (buffer
, " ? ");
541 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
, false);
542 pp_string (buffer
, " : ");
543 dump_generic_node (buffer
, gimple_assign_rhs3 (gs
), spc
, flags
, false);
547 pp_string (buffer
, "VEC_COND_EXPR <");
548 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
, false);
549 pp_string (buffer
, ", ");
550 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
, false);
551 pp_string (buffer
, ", ");
552 dump_generic_node (buffer
, gimple_assign_rhs3 (gs
), spc
, flags
, false);
556 case BIT_INSERT_EXPR
:
557 pp_string (buffer
, "BIT_INSERT_EXPR <");
558 dump_generic_node (buffer
, gimple_assign_rhs1 (gs
), spc
, flags
, false);
559 pp_string (buffer
, ", ");
560 dump_generic_node (buffer
, gimple_assign_rhs2 (gs
), spc
, flags
, false);
561 pp_string (buffer
, ", ");
562 dump_generic_node (buffer
, gimple_assign_rhs3 (gs
), spc
, flags
, false);
563 pp_string (buffer
, " (");
564 if (INTEGRAL_TYPE_P (TREE_TYPE (gimple_assign_rhs2 (gs
))))
565 pp_decimal_int (buffer
,
566 TYPE_PRECISION (TREE_TYPE (gimple_assign_rhs2 (gs
))));
568 dump_generic_node (buffer
,
569 TYPE_SIZE (TREE_TYPE (gimple_assign_rhs2 (gs
))),
571 pp_string (buffer
, " bits)>");
580 /* Dump the gimple assignment GS. BUFFER, SPC and FLAGS are as in
584 dump_gimple_assign (pretty_printer
*buffer
, gassign
*gs
, int spc
,
592 switch (gimple_num_ops (gs
))
595 arg3
= gimple_assign_rhs3 (gs
);
598 arg2
= gimple_assign_rhs2 (gs
);
601 arg1
= gimple_assign_rhs1 (gs
);
607 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%s, %T, %T, %T, %T>", gs
,
608 get_tree_code_name (gimple_assign_rhs_code (gs
)),
609 gimple_assign_lhs (gs
), arg1
, arg2
, arg3
);
613 if (!(flags
& TDF_RHS_ONLY
))
615 dump_generic_node (buffer
, gimple_assign_lhs (gs
), spc
, flags
, false);
619 if (gimple_assign_nontemporal_move_p (gs
))
620 pp_string (buffer
, "{nt}");
622 if (gimple_has_volatile_ops (gs
))
623 pp_string (buffer
, "{v}");
628 if (gimple_num_ops (gs
) == 2)
629 dump_unary_rhs (buffer
, gs
, spc
, flags
);
630 else if (gimple_num_ops (gs
) == 3)
631 dump_binary_rhs (buffer
, gs
, spc
, flags
);
632 else if (gimple_num_ops (gs
) == 4)
633 dump_ternary_rhs (buffer
, gs
, spc
, flags
);
636 if (!(flags
& TDF_RHS_ONLY
))
637 pp_semicolon (buffer
);
642 /* Dump the return statement GS. BUFFER, SPC and FLAGS are as in
646 dump_gimple_return (pretty_printer
*buffer
, greturn
*gs
, int spc
,
651 t
= gimple_return_retval (gs
);
653 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T>", gs
, t
);
656 pp_string (buffer
, "return");
660 dump_generic_node (buffer
, t
, spc
, flags
, false);
662 pp_semicolon (buffer
);
667 /* Dump the call arguments for a gimple call. BUFFER, FLAGS are as in
671 dump_gimple_call_args (pretty_printer
*buffer
, gcall
*gs
, dump_flags_t flags
)
675 /* Pretty print first arg to certain internal fns. */
676 if (gimple_call_internal_p (gs
))
678 const char *const *enums
= NULL
;
681 switch (gimple_call_internal_fn (gs
))
685 static const char *const unique_args
[] = {IFN_UNIQUE_CODES
};
689 limit
= ARRAY_SIZE (unique_args
);
694 static const char *const loop_args
[] = {IFN_GOACC_LOOP_CODES
};
697 limit
= ARRAY_SIZE (loop_args
);
700 case IFN_GOACC_REDUCTION
:
702 static const char *const reduction_args
[]
703 = {IFN_GOACC_REDUCTION_CODES
};
705 enums
= reduction_args
;
706 limit
= ARRAY_SIZE (reduction_args
);
711 static const char *const asan_mark_args
[] = {IFN_ASAN_MARK_FLAGS
};
713 enums
= asan_mark_args
;
714 limit
= ARRAY_SIZE (asan_mark_args
);
722 tree arg0
= gimple_call_arg (gs
, 0);
725 if (TREE_CODE (arg0
) == INTEGER_CST
726 && tree_fits_shwi_p (arg0
)
727 && (v
= tree_to_shwi (arg0
)) >= 0 && v
< limit
)
730 pp_string (buffer
, enums
[v
]);
735 for (; i
< gimple_call_num_args (gs
); i
++)
738 pp_string (buffer
, ", ");
739 dump_generic_node (buffer
, gimple_call_arg (gs
, i
), 0, flags
, false);
742 if (gimple_call_va_arg_pack_p (gs
))
745 pp_string (buffer
, ", ");
747 pp_string (buffer
, "__builtin_va_arg_pack ()");
751 /* Dump the points-to solution *PT to BUFFER. */
754 pp_points_to_solution (pretty_printer
*buffer
, struct pt_solution
*pt
)
758 pp_string (buffer
, "anything ");
762 pp_string (buffer
, "nonlocal ");
764 pp_string (buffer
, "escaped ");
766 pp_string (buffer
, "unit-escaped ");
768 pp_string (buffer
, "null ");
770 && !bitmap_empty_p (pt
->vars
))
774 pp_string (buffer
, "{ ");
775 EXECUTE_IF_SET_IN_BITMAP (pt
->vars
, 0, i
, bi
)
777 pp_string (buffer
, "D.");
778 pp_decimal_int (buffer
, i
);
781 pp_right_brace (buffer
);
782 if (pt
->vars_contains_nonlocal
783 || pt
->vars_contains_escaped
784 || pt
->vars_contains_escaped_heap
785 || pt
->vars_contains_restrict
)
787 const char *comma
= "";
788 pp_string (buffer
, " (");
789 if (pt
->vars_contains_nonlocal
)
791 pp_string (buffer
, "nonlocal");
794 if (pt
->vars_contains_escaped
)
796 pp_string (buffer
, comma
);
797 pp_string (buffer
, "escaped");
800 if (pt
->vars_contains_escaped_heap
)
802 pp_string (buffer
, comma
);
803 pp_string (buffer
, "escaped heap");
806 if (pt
->vars_contains_restrict
)
808 pp_string (buffer
, comma
);
809 pp_string (buffer
, "restrict");
812 if (pt
->vars_contains_interposable
)
814 pp_string (buffer
, comma
);
815 pp_string (buffer
, "interposable");
817 pp_string (buffer
, ")");
823 /* Dump the call statement GS. BUFFER, SPC and FLAGS are as in
827 dump_gimple_call (pretty_printer
*buffer
, gcall
*gs
, int spc
,
830 tree lhs
= gimple_call_lhs (gs
);
831 tree fn
= gimple_call_fn (gs
);
833 if (flags
& TDF_ALIAS
)
835 struct pt_solution
*pt
;
836 pt
= gimple_call_use_set (gs
);
837 if (!pt_solution_empty_p (pt
))
839 pp_string (buffer
, "# USE = ");
840 pp_points_to_solution (buffer
, pt
);
841 newline_and_indent (buffer
, spc
);
843 pt
= gimple_call_clobber_set (gs
);
844 if (!pt_solution_empty_p (pt
))
846 pp_string (buffer
, "# CLB = ");
847 pp_points_to_solution (buffer
, pt
);
848 newline_and_indent (buffer
, spc
);
854 if (gimple_call_internal_p (gs
))
855 dump_gimple_fmt (buffer
, spc
, flags
, "%G <.%s, %T", gs
,
856 internal_fn_name (gimple_call_internal_fn (gs
)), lhs
);
858 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T, %T", gs
, fn
, lhs
);
859 if (gimple_call_num_args (gs
) > 0)
861 pp_string (buffer
, ", ");
862 dump_gimple_call_args (buffer
, gs
, flags
);
868 if (lhs
&& !(flags
& TDF_RHS_ONLY
))
870 dump_generic_node (buffer
, lhs
, spc
, flags
, false);
871 pp_string (buffer
, " =");
873 if (gimple_has_volatile_ops (gs
))
874 pp_string (buffer
, "{v}");
878 if (gimple_call_internal_p (gs
))
881 pp_string (buffer
, internal_fn_name (gimple_call_internal_fn (gs
)));
884 print_call_name (buffer
, fn
, flags
);
885 pp_string (buffer
, " (");
886 dump_gimple_call_args (buffer
, gs
, flags
);
887 pp_right_paren (buffer
);
888 if (!(flags
& TDF_RHS_ONLY
))
889 pp_semicolon (buffer
);
892 if (gimple_call_chain (gs
))
894 pp_string (buffer
, " [static-chain: ");
895 dump_generic_node (buffer
, gimple_call_chain (gs
), spc
, flags
, false);
896 pp_right_bracket (buffer
);
899 if (gimple_call_return_slot_opt_p (gs
))
900 pp_string (buffer
, " [return slot optimization]");
901 if (gimple_call_tail_p (gs
))
902 pp_string (buffer
, " [tail call]");
903 if (gimple_call_must_tail_p (gs
))
904 pp_string (buffer
, " [must tail call]");
909 /* Dump the arguments of _ITM_beginTransaction sanely. */
910 if (TREE_CODE (fn
) == ADDR_EXPR
)
911 fn
= TREE_OPERAND (fn
, 0);
912 if (TREE_CODE (fn
) == FUNCTION_DECL
&& decl_is_tm_clone (fn
))
913 pp_string (buffer
, " [tm-clone]");
914 if (TREE_CODE (fn
) == FUNCTION_DECL
915 && fndecl_built_in_p (fn
, BUILT_IN_TM_START
)
916 && gimple_call_num_args (gs
) > 0)
918 tree t
= gimple_call_arg (gs
, 0);
919 unsigned HOST_WIDE_INT props
;
920 gcc_assert (TREE_CODE (t
) == INTEGER_CST
);
922 pp_string (buffer
, " [ ");
924 /* Get the transaction code properties. */
925 props
= TREE_INT_CST_LOW (t
);
927 if (props
& PR_INSTRUMENTEDCODE
)
928 pp_string (buffer
, "instrumentedCode ");
929 if (props
& PR_UNINSTRUMENTEDCODE
)
930 pp_string (buffer
, "uninstrumentedCode ");
931 if (props
& PR_HASNOXMMUPDATE
)
932 pp_string (buffer
, "hasNoXMMUpdate ");
933 if (props
& PR_HASNOABORT
)
934 pp_string (buffer
, "hasNoAbort ");
935 if (props
& PR_HASNOIRREVOCABLE
)
936 pp_string (buffer
, "hasNoIrrevocable ");
937 if (props
& PR_DOESGOIRREVOCABLE
)
938 pp_string (buffer
, "doesGoIrrevocable ");
939 if (props
& PR_HASNOSIMPLEREADS
)
940 pp_string (buffer
, "hasNoSimpleReads ");
941 if (props
& PR_AWBARRIERSOMITTED
)
942 pp_string (buffer
, "awBarriersOmitted ");
943 if (props
& PR_RARBARRIERSOMITTED
)
944 pp_string (buffer
, "RaRBarriersOmitted ");
945 if (props
& PR_UNDOLOGCODE
)
946 pp_string (buffer
, "undoLogCode ");
947 if (props
& PR_PREFERUNINSTRUMENTED
)
948 pp_string (buffer
, "preferUninstrumented ");
949 if (props
& PR_EXCEPTIONBLOCK
)
950 pp_string (buffer
, "exceptionBlock ");
951 if (props
& PR_HASELSE
)
952 pp_string (buffer
, "hasElse ");
953 if (props
& PR_READONLY
)
954 pp_string (buffer
, "readOnly ");
956 pp_right_bracket (buffer
);
961 /* Dump the switch statement GS. BUFFER, SPC and FLAGS are as in
965 dump_gimple_switch (pretty_printer
*buffer
, gswitch
*gs
, int spc
,
970 GIMPLE_CHECK (gs
, GIMPLE_SWITCH
);
972 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T, ", gs
,
973 gimple_switch_index (gs
));
976 pp_string (buffer
, "switch (");
977 dump_generic_node (buffer
, gimple_switch_index (gs
), spc
, flags
, true);
978 if (flags
& TDF_GIMPLE
)
979 pp_string (buffer
, ") {");
981 pp_string (buffer
, ") <");
984 for (i
= 0; i
< gimple_switch_num_labels (gs
); i
++)
986 tree case_label
= gimple_switch_label (gs
, i
);
987 gcc_checking_assert (case_label
!= NULL_TREE
);
988 dump_generic_node (buffer
, case_label
, spc
, flags
, false);
990 tree label
= CASE_LABEL (case_label
);
991 dump_generic_node (buffer
, label
, spc
, flags
, false);
993 if (cfun
&& cfun
->cfg
)
995 basic_block dest
= label_to_block (cfun
, label
);
998 edge label_edge
= find_edge (gimple_bb (gs
), dest
);
999 if (label_edge
&& !(flags
& TDF_GIMPLE
))
1000 dump_edge_probability (buffer
, label_edge
);
1004 if (i
< gimple_switch_num_labels (gs
) - 1)
1006 if (flags
& TDF_GIMPLE
)
1007 pp_string (buffer
, "; ");
1009 pp_string (buffer
, ", ");
1012 if (flags
& TDF_GIMPLE
)
1013 pp_string (buffer
, "; }");
1015 pp_greater (buffer
);
1019 /* Dump the gimple conditional GS. BUFFER, SPC and FLAGS are as in
1020 pp_gimple_stmt_1. */
1023 dump_gimple_cond (pretty_printer
*buffer
, gcond
*gs
, int spc
,
1026 if (flags
& TDF_RAW
)
1027 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%s, %T, %T, %T, %T>", gs
,
1028 get_tree_code_name (gimple_cond_code (gs
)),
1029 gimple_cond_lhs (gs
), gimple_cond_rhs (gs
),
1030 gimple_cond_true_label (gs
), gimple_cond_false_label (gs
));
1033 if (!(flags
& TDF_RHS_ONLY
))
1034 pp_string (buffer
, "if (");
1035 dump_generic_node (buffer
, gimple_cond_lhs (gs
), spc
, flags
, false);
1037 pp_string (buffer
, op_symbol_code (gimple_cond_code (gs
)));
1039 dump_generic_node (buffer
, gimple_cond_rhs (gs
), spc
, flags
, false);
1040 if (!(flags
& TDF_RHS_ONLY
))
1043 edge e
, true_edge
= NULL
, false_edge
= NULL
;
1044 basic_block bb
= gimple_bb (gs
);
1048 FOR_EACH_EDGE (e
, ei
, bb
->succs
)
1050 if (e
->flags
& EDGE_TRUE_VALUE
)
1052 else if (e
->flags
& EDGE_FALSE_VALUE
)
1057 bool has_edge_info
= true_edge
!= NULL
&& false_edge
!= NULL
;
1059 pp_right_paren (buffer
);
1061 if (gimple_cond_true_label (gs
))
1063 pp_string (buffer
, " goto ");
1064 dump_generic_node (buffer
, gimple_cond_true_label (gs
),
1066 if (has_edge_info
&& !(flags
& TDF_GIMPLE
))
1067 dump_edge_probability (buffer
, true_edge
);
1068 pp_semicolon (buffer
);
1070 if (gimple_cond_false_label (gs
))
1072 pp_string (buffer
, " else goto ");
1073 dump_generic_node (buffer
, gimple_cond_false_label (gs
),
1075 if (has_edge_info
&& !(flags
& TDF_GIMPLE
))
1076 dump_edge_probability (buffer
, false_edge
);
1078 pp_semicolon (buffer
);
1085 /* Dump a GIMPLE_LABEL tuple on the pretty_printer BUFFER, SPC
1086 spaces of indent. FLAGS specifies details to show in the dump (see
1087 TDF_* in dumpfils.h). */
1090 dump_gimple_label (pretty_printer
*buffer
, glabel
*gs
, int spc
,
1093 tree label
= gimple_label_label (gs
);
1094 if (flags
& TDF_RAW
)
1095 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T>", gs
, label
);
1098 dump_generic_node (buffer
, label
, spc
, flags
, false);
1101 if (flags
& TDF_GIMPLE
)
1103 if (DECL_NONLOCAL (label
))
1104 pp_string (buffer
, " [non-local]");
1105 if ((flags
& TDF_EH
) && EH_LANDING_PAD_NR (label
))
1106 pp_printf (buffer
, " [LP %d]", EH_LANDING_PAD_NR (label
));
1109 /* Dump a GIMPLE_GOTO tuple on the pretty_printer BUFFER, SPC
1110 spaces of indent. FLAGS specifies details to show in the dump (see
1111 TDF_* in dumpfile.h). */
1114 dump_gimple_goto (pretty_printer
*buffer
, ggoto
*gs
, int spc
,
1117 tree label
= gimple_goto_dest (gs
);
1118 if (flags
& TDF_RAW
)
1119 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T>", gs
, label
);
1121 dump_gimple_fmt (buffer
, spc
, flags
, "goto %T;", label
);
1125 /* Dump a GIMPLE_BIND tuple on the pretty_printer BUFFER, SPC
1126 spaces of indent. FLAGS specifies details to show in the dump (see
1127 TDF_* in dumpfile.h). */
1130 dump_gimple_bind (pretty_printer
*buffer
, gbind
*gs
, int spc
,
1133 if (flags
& TDF_RAW
)
1134 dump_gimple_fmt (buffer
, spc
, flags
, "%G <", gs
);
1136 pp_left_brace (buffer
);
1137 if (!(flags
& TDF_SLIM
))
1141 for (var
= gimple_bind_vars (gs
); var
; var
= DECL_CHAIN (var
))
1143 newline_and_indent (buffer
, 2);
1144 print_declaration (buffer
, var
, spc
, flags
);
1146 if (gimple_bind_vars (gs
))
1147 pp_newline (buffer
);
1149 pp_newline (buffer
);
1150 dump_gimple_seq (buffer
, gimple_bind_body (gs
), spc
+ 2, flags
);
1151 newline_and_indent (buffer
, spc
);
1152 if (flags
& TDF_RAW
)
1153 pp_greater (buffer
);
1155 pp_right_brace (buffer
);
1159 /* Dump a GIMPLE_TRY tuple on the pretty_printer BUFFER, SPC spaces of
1160 indent. FLAGS specifies details to show in the dump (see TDF_* in
1164 dump_gimple_try (pretty_printer
*buffer
, gtry
*gs
, int spc
,
1167 if (flags
& TDF_RAW
)
1170 if (gimple_try_kind (gs
) == GIMPLE_TRY_CATCH
)
1171 type
= "GIMPLE_TRY_CATCH";
1172 else if (gimple_try_kind (gs
) == GIMPLE_TRY_FINALLY
)
1173 type
= "GIMPLE_TRY_FINALLY";
1175 type
= "UNKNOWN GIMPLE_TRY";
1176 dump_gimple_fmt (buffer
, spc
, flags
,
1177 "%G <%s,%+EVAL <%S>%nCLEANUP <%S>%->", gs
, type
,
1178 gimple_try_eval (gs
), gimple_try_cleanup (gs
));
1182 pp_string (buffer
, "try");
1183 newline_and_indent (buffer
, spc
+ 2);
1184 pp_left_brace (buffer
);
1185 pp_newline (buffer
);
1187 dump_gimple_seq (buffer
, gimple_try_eval (gs
), spc
+ 4, flags
);
1188 newline_and_indent (buffer
, spc
+ 2);
1189 pp_right_brace (buffer
);
1191 if (gimple_try_kind (gs
) == GIMPLE_TRY_CATCH
)
1193 newline_and_indent (buffer
, spc
);
1194 pp_string (buffer
, "catch");
1195 newline_and_indent (buffer
, spc
+ 2);
1196 pp_left_brace (buffer
);
1198 else if (gimple_try_kind (gs
) == GIMPLE_TRY_FINALLY
)
1200 newline_and_indent (buffer
, spc
);
1201 pp_string (buffer
, "finally");
1202 newline_and_indent (buffer
, spc
+ 2);
1203 pp_left_brace (buffer
);
1206 pp_string (buffer
, " <UNKNOWN GIMPLE_TRY> {");
1208 pp_newline (buffer
);
1209 dump_gimple_seq (buffer
, gimple_try_cleanup (gs
), spc
+ 4, flags
);
1210 newline_and_indent (buffer
, spc
+ 2);
1211 pp_right_brace (buffer
);
1216 /* Dump a GIMPLE_CATCH tuple on the pretty_printer BUFFER, SPC spaces of
1217 indent. FLAGS specifies details to show in the dump (see TDF_* in
1221 dump_gimple_catch (pretty_printer
*buffer
, gcatch
*gs
, int spc
,
1224 if (flags
& TDF_RAW
)
1225 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T, %+CATCH <%S>%->", gs
,
1226 gimple_catch_types (gs
), gimple_catch_handler (gs
));
1228 dump_gimple_fmt (buffer
, spc
, flags
, "catch (%T)%+{%S}",
1229 gimple_catch_types (gs
), gimple_catch_handler (gs
));
1233 /* Dump a GIMPLE_EH_FILTER tuple on the pretty_printer BUFFER, SPC spaces of
1234 indent. FLAGS specifies details to show in the dump (see TDF_* in
1238 dump_gimple_eh_filter (pretty_printer
*buffer
, geh_filter
*gs
, int spc
,
1241 if (flags
& TDF_RAW
)
1242 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T, %+FAILURE <%S>%->", gs
,
1243 gimple_eh_filter_types (gs
),
1244 gimple_eh_filter_failure (gs
));
1246 dump_gimple_fmt (buffer
, spc
, flags
, "<<<eh_filter (%T)>>>%+{%+%S%-}",
1247 gimple_eh_filter_types (gs
),
1248 gimple_eh_filter_failure (gs
));
1252 /* Dump a GIMPLE_EH_MUST_NOT_THROW tuple. */
1255 dump_gimple_eh_must_not_throw (pretty_printer
*buffer
,
1256 geh_mnt
*gs
, int spc
, dump_flags_t flags
)
1258 if (flags
& TDF_RAW
)
1259 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T>", gs
,
1260 gimple_eh_must_not_throw_fndecl (gs
));
1262 dump_gimple_fmt (buffer
, spc
, flags
, "<<<eh_must_not_throw (%T)>>>",
1263 gimple_eh_must_not_throw_fndecl (gs
));
1267 /* Dump a GIMPLE_EH_ELSE tuple on the pretty_printer BUFFER, SPC spaces of
1268 indent. FLAGS specifies details to show in the dump (see TDF_* in
1272 dump_gimple_eh_else (pretty_printer
*buffer
, geh_else
*gs
, int spc
,
1275 if (flags
& TDF_RAW
)
1276 dump_gimple_fmt (buffer
, spc
, flags
,
1277 "%G <%+N_BODY <%S>%nE_BODY <%S>%->", gs
,
1278 gimple_eh_else_n_body (gs
), gimple_eh_else_e_body (gs
));
1280 dump_gimple_fmt (buffer
, spc
, flags
,
1281 "<<<if_normal_exit>>>%+{%S}%-<<<else_eh_exit>>>%+{%S}",
1282 gimple_eh_else_n_body (gs
), gimple_eh_else_e_body (gs
));
1286 /* Dump a GIMPLE_RESX tuple on the pretty_printer BUFFER, SPC spaces of
1287 indent. FLAGS specifies details to show in the dump (see TDF_* in
1291 dump_gimple_resx (pretty_printer
*buffer
, gresx
*gs
, int spc
,
1294 if (flags
& TDF_RAW
)
1295 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%d>", gs
,
1296 gimple_resx_region (gs
));
1298 dump_gimple_fmt (buffer
, spc
, flags
, "resx %d", gimple_resx_region (gs
));
1301 /* Dump a GIMPLE_EH_DISPATCH tuple on the pretty_printer BUFFER. */
1304 dump_gimple_eh_dispatch (pretty_printer
*buffer
, geh_dispatch
*gs
, int spc
,
1307 if (flags
& TDF_RAW
)
1308 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%d>", gs
,
1309 gimple_eh_dispatch_region (gs
));
1311 dump_gimple_fmt (buffer
, spc
, flags
, "eh_dispatch %d",
1312 gimple_eh_dispatch_region (gs
));
1315 /* Dump a GIMPLE_DEBUG tuple on the pretty_printer BUFFER, SPC spaces
1316 of indent. FLAGS specifies details to show in the dump (see TDF_*
1320 dump_gimple_debug (pretty_printer
*buffer
, gdebug
*gs
, int spc
,
1323 switch (gs
->subcode
)
1325 case GIMPLE_DEBUG_BIND
:
1326 if (flags
& TDF_RAW
)
1327 dump_gimple_fmt (buffer
, spc
, flags
, "%G BIND <%T, %T>", gs
,
1328 gimple_debug_bind_get_var (gs
),
1329 gimple_debug_bind_get_value (gs
));
1331 dump_gimple_fmt (buffer
, spc
, flags
, "# DEBUG %T => %T",
1332 gimple_debug_bind_get_var (gs
),
1333 gimple_debug_bind_get_value (gs
));
1336 case GIMPLE_DEBUG_SOURCE_BIND
:
1337 if (flags
& TDF_RAW
)
1338 dump_gimple_fmt (buffer
, spc
, flags
, "%G SRCBIND <%T, %T>", gs
,
1339 gimple_debug_source_bind_get_var (gs
),
1340 gimple_debug_source_bind_get_value (gs
));
1342 dump_gimple_fmt (buffer
, spc
, flags
, "# DEBUG %T s=> %T",
1343 gimple_debug_source_bind_get_var (gs
),
1344 gimple_debug_source_bind_get_value (gs
));
1347 case GIMPLE_DEBUG_BEGIN_STMT
:
1348 if (flags
& TDF_RAW
)
1349 dump_gimple_fmt (buffer
, spc
, flags
, "%G BEGIN_STMT", gs
);
1351 dump_gimple_fmt (buffer
, spc
, flags
, "# DEBUG BEGIN_STMT");
1354 case GIMPLE_DEBUG_INLINE_ENTRY
:
1355 if (flags
& TDF_RAW
)
1356 dump_gimple_fmt (buffer
, spc
, flags
, "%G INLINE_ENTRY %T", gs
,
1358 ? block_ultimate_origin (gimple_block (gs
))
1361 dump_gimple_fmt (buffer
, spc
, flags
, "# DEBUG INLINE_ENTRY %T",
1363 ? block_ultimate_origin (gimple_block (gs
))
1372 /* Dump a GIMPLE_OMP_FOR tuple on the pretty_printer BUFFER. */
1374 dump_gimple_omp_for (pretty_printer
*buffer
, gomp_for
*gs
, int spc
,
1379 if (flags
& TDF_RAW
)
1382 switch (gimple_omp_for_kind (gs
))
1384 case GF_OMP_FOR_KIND_FOR
:
1387 case GF_OMP_FOR_KIND_DISTRIBUTE
:
1388 kind
= " distribute";
1390 case GF_OMP_FOR_KIND_TASKLOOP
:
1393 case GF_OMP_FOR_KIND_OACC_LOOP
:
1394 kind
= " oacc_loop";
1396 case GF_OMP_FOR_KIND_SIMD
:
1402 dump_gimple_fmt (buffer
, spc
, flags
, "%G%s <%+BODY <%S>%nCLAUSES <", gs
,
1403 kind
, gimple_omp_body (gs
));
1404 dump_omp_clauses (buffer
, gimple_omp_for_clauses (gs
), spc
, flags
);
1405 dump_gimple_fmt (buffer
, spc
, flags
, " >,");
1406 for (i
= 0; i
< gimple_omp_for_collapse (gs
); i
++)
1407 dump_gimple_fmt (buffer
, spc
, flags
,
1408 "%+%T, %T, %T, %s, %T,%n",
1409 gimple_omp_for_index (gs
, i
),
1410 gimple_omp_for_initial (gs
, i
),
1411 gimple_omp_for_final (gs
, i
),
1412 get_tree_code_name (gimple_omp_for_cond (gs
, i
)),
1413 gimple_omp_for_incr (gs
, i
));
1414 dump_gimple_fmt (buffer
, spc
, flags
, "PRE_BODY <%S>%->",
1415 gimple_omp_for_pre_body (gs
));
1419 switch (gimple_omp_for_kind (gs
))
1421 case GF_OMP_FOR_KIND_FOR
:
1422 pp_string (buffer
, "#pragma omp for");
1424 case GF_OMP_FOR_KIND_DISTRIBUTE
:
1425 pp_string (buffer
, "#pragma omp distribute");
1427 case GF_OMP_FOR_KIND_TASKLOOP
:
1428 pp_string (buffer
, "#pragma omp taskloop");
1430 case GF_OMP_FOR_KIND_OACC_LOOP
:
1431 pp_string (buffer
, "#pragma acc loop");
1433 case GF_OMP_FOR_KIND_SIMD
:
1434 pp_string (buffer
, "#pragma omp simd");
1436 case GF_OMP_FOR_KIND_GRID_LOOP
:
1437 pp_string (buffer
, "#pragma omp for grid_loop");
1442 dump_omp_clauses (buffer
, gimple_omp_for_clauses (gs
), spc
, flags
);
1443 for (i
= 0; i
< gimple_omp_for_collapse (gs
); i
++)
1447 newline_and_indent (buffer
, spc
);
1448 pp_string (buffer
, "for (");
1449 dump_generic_node (buffer
, gimple_omp_for_index (gs
, i
), spc
,
1451 pp_string (buffer
, " = ");
1452 dump_generic_node (buffer
, gimple_omp_for_initial (gs
, i
), spc
,
1454 pp_string (buffer
, "; ");
1456 dump_generic_node (buffer
, gimple_omp_for_index (gs
, i
), spc
,
1459 switch (gimple_omp_for_cond (gs
, i
))
1465 pp_greater (buffer
);
1468 pp_less_equal (buffer
);
1471 pp_greater_equal (buffer
);
1474 pp_string (buffer
, "!=");
1480 dump_generic_node (buffer
, gimple_omp_for_final (gs
, i
), spc
,
1482 pp_string (buffer
, "; ");
1484 dump_generic_node (buffer
, gimple_omp_for_index (gs
, i
), spc
,
1486 pp_string (buffer
, " = ");
1487 dump_generic_node (buffer
, gimple_omp_for_incr (gs
, i
), spc
,
1489 pp_right_paren (buffer
);
1492 if (!gimple_seq_empty_p (gimple_omp_body (gs
)))
1494 newline_and_indent (buffer
, spc
+ 2);
1495 pp_left_brace (buffer
);
1496 pp_newline (buffer
);
1497 dump_gimple_seq (buffer
, gimple_omp_body (gs
), spc
+ 4, flags
);
1498 newline_and_indent (buffer
, spc
+ 2);
1499 pp_right_brace (buffer
);
1504 /* Dump a GIMPLE_OMP_CONTINUE tuple on the pretty_printer BUFFER. */
1507 dump_gimple_omp_continue (pretty_printer
*buffer
, gomp_continue
*gs
,
1508 int spc
, dump_flags_t flags
)
1510 if (flags
& TDF_RAW
)
1512 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T, %T>", gs
,
1513 gimple_omp_continue_control_def (gs
),
1514 gimple_omp_continue_control_use (gs
));
1518 pp_string (buffer
, "#pragma omp continue (");
1519 dump_generic_node (buffer
, gimple_omp_continue_control_def (gs
),
1523 dump_generic_node (buffer
, gimple_omp_continue_control_use (gs
),
1525 pp_right_paren (buffer
);
1529 /* Dump a GIMPLE_OMP_SINGLE tuple on the pretty_printer BUFFER. */
1532 dump_gimple_omp_single (pretty_printer
*buffer
, gomp_single
*gs
,
1533 int spc
, dump_flags_t flags
)
1535 if (flags
& TDF_RAW
)
1537 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%+BODY <%S>%nCLAUSES <", gs
,
1538 gimple_omp_body (gs
));
1539 dump_omp_clauses (buffer
, gimple_omp_single_clauses (gs
), spc
, flags
);
1540 dump_gimple_fmt (buffer
, spc
, flags
, " >");
1544 pp_string (buffer
, "#pragma omp single");
1545 dump_omp_clauses (buffer
, gimple_omp_single_clauses (gs
), spc
, flags
);
1546 if (!gimple_seq_empty_p (gimple_omp_body (gs
)))
1548 newline_and_indent (buffer
, spc
+ 2);
1549 pp_left_brace (buffer
);
1550 pp_newline (buffer
);
1551 dump_gimple_seq (buffer
, gimple_omp_body (gs
), spc
+ 4, flags
);
1552 newline_and_indent (buffer
, spc
+ 2);
1553 pp_right_brace (buffer
);
1558 /* Dump a GIMPLE_OMP_TASKGROUP tuple on the pretty_printer BUFFER. */
1561 dump_gimple_omp_taskgroup (pretty_printer
*buffer
, gimple
*gs
,
1562 int spc
, dump_flags_t flags
)
1564 if (flags
& TDF_RAW
)
1566 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%+BODY <%S>%nCLAUSES <", gs
,
1567 gimple_omp_body (gs
));
1568 dump_omp_clauses (buffer
, gimple_omp_taskgroup_clauses (gs
), spc
, flags
);
1569 dump_gimple_fmt (buffer
, spc
, flags
, " >");
1573 pp_string (buffer
, "#pragma omp taskgroup");
1574 dump_omp_clauses (buffer
, gimple_omp_taskgroup_clauses (gs
), spc
, flags
);
1575 if (!gimple_seq_empty_p (gimple_omp_body (gs
)))
1577 newline_and_indent (buffer
, spc
+ 2);
1578 pp_left_brace (buffer
);
1579 pp_newline (buffer
);
1580 dump_gimple_seq (buffer
, gimple_omp_body (gs
), spc
+ 4, flags
);
1581 newline_and_indent (buffer
, spc
+ 2);
1582 pp_right_brace (buffer
);
1587 /* Dump a GIMPLE_OMP_TARGET tuple on the pretty_printer BUFFER. */
1590 dump_gimple_omp_target (pretty_printer
*buffer
, gomp_target
*gs
,
1591 int spc
, dump_flags_t flags
)
1594 switch (gimple_omp_target_kind (gs
))
1596 case GF_OMP_TARGET_KIND_REGION
:
1599 case GF_OMP_TARGET_KIND_DATA
:
1602 case GF_OMP_TARGET_KIND_UPDATE
:
1605 case GF_OMP_TARGET_KIND_ENTER_DATA
:
1606 kind
= " enter data";
1608 case GF_OMP_TARGET_KIND_EXIT_DATA
:
1609 kind
= " exit data";
1611 case GF_OMP_TARGET_KIND_OACC_KERNELS
:
1612 kind
= " oacc_kernels";
1614 case GF_OMP_TARGET_KIND_OACC_PARALLEL
:
1615 kind
= " oacc_parallel";
1617 case GF_OMP_TARGET_KIND_OACC_DATA
:
1618 kind
= " oacc_data";
1620 case GF_OMP_TARGET_KIND_OACC_UPDATE
:
1621 kind
= " oacc_update";
1623 case GF_OMP_TARGET_KIND_OACC_ENTER_EXIT_DATA
:
1624 kind
= " oacc_enter_exit_data";
1626 case GF_OMP_TARGET_KIND_OACC_DECLARE
:
1627 kind
= " oacc_declare";
1629 case GF_OMP_TARGET_KIND_OACC_HOST_DATA
:
1630 kind
= " oacc_host_data";
1635 if (flags
& TDF_RAW
)
1637 dump_gimple_fmt (buffer
, spc
, flags
, "%G%s <%+BODY <%S>%nCLAUSES <", gs
,
1638 kind
, gimple_omp_body (gs
));
1639 dump_omp_clauses (buffer
, gimple_omp_target_clauses (gs
), spc
, flags
);
1640 dump_gimple_fmt (buffer
, spc
, flags
, " >, %T, %T%n>",
1641 gimple_omp_target_child_fn (gs
),
1642 gimple_omp_target_data_arg (gs
));
1646 pp_string (buffer
, "#pragma omp target");
1647 pp_string (buffer
, kind
);
1648 dump_omp_clauses (buffer
, gimple_omp_target_clauses (gs
), spc
, flags
);
1649 if (gimple_omp_target_child_fn (gs
))
1651 pp_string (buffer
, " [child fn: ");
1652 dump_generic_node (buffer
, gimple_omp_target_child_fn (gs
),
1654 pp_string (buffer
, " (");
1655 if (gimple_omp_target_data_arg (gs
))
1656 dump_generic_node (buffer
, gimple_omp_target_data_arg (gs
),
1659 pp_string (buffer
, "???");
1660 pp_string (buffer
, ")]");
1662 gimple_seq body
= gimple_omp_body (gs
);
1663 if (body
&& gimple_code (gimple_seq_first_stmt (body
)) != GIMPLE_BIND
)
1665 newline_and_indent (buffer
, spc
+ 2);
1666 pp_left_brace (buffer
);
1667 pp_newline (buffer
);
1668 dump_gimple_seq (buffer
, body
, spc
+ 4, flags
);
1669 newline_and_indent (buffer
, spc
+ 2);
1670 pp_right_brace (buffer
);
1674 pp_newline (buffer
);
1675 dump_gimple_seq (buffer
, body
, spc
+ 2, flags
);
1680 /* Dump a GIMPLE_OMP_TEAMS tuple on the pretty_printer BUFFER. */
1683 dump_gimple_omp_teams (pretty_printer
*buffer
, gomp_teams
*gs
, int spc
,
1686 if (flags
& TDF_RAW
)
1688 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%+BODY <%S>%nCLAUSES <", gs
,
1689 gimple_omp_body (gs
));
1690 dump_omp_clauses (buffer
, gimple_omp_teams_clauses (gs
), spc
, flags
);
1691 dump_gimple_fmt (buffer
, spc
, flags
, " >");
1695 pp_string (buffer
, "#pragma omp teams");
1696 dump_omp_clauses (buffer
, gimple_omp_teams_clauses (gs
), spc
, flags
);
1697 if (!gimple_seq_empty_p (gimple_omp_body (gs
)))
1699 newline_and_indent (buffer
, spc
+ 2);
1700 pp_character (buffer
, '{');
1701 pp_newline (buffer
);
1702 dump_gimple_seq (buffer
, gimple_omp_body (gs
), spc
+ 4, flags
);
1703 newline_and_indent (buffer
, spc
+ 2);
1704 pp_character (buffer
, '}');
1709 /* Dump a GIMPLE_OMP_SECTIONS tuple on the pretty_printer BUFFER. */
1712 dump_gimple_omp_sections (pretty_printer
*buffer
, gomp_sections
*gs
,
1713 int spc
, dump_flags_t flags
)
1715 if (flags
& TDF_RAW
)
1717 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%+BODY <%S>%nCLAUSES <", gs
,
1718 gimple_omp_body (gs
));
1719 dump_omp_clauses (buffer
, gimple_omp_sections_clauses (gs
), spc
, flags
);
1720 dump_gimple_fmt (buffer
, spc
, flags
, " >");
1724 pp_string (buffer
, "#pragma omp sections");
1725 if (gimple_omp_sections_control (gs
))
1727 pp_string (buffer
, " <");
1728 dump_generic_node (buffer
, gimple_omp_sections_control (gs
), spc
,
1730 pp_greater (buffer
);
1732 dump_omp_clauses (buffer
, gimple_omp_sections_clauses (gs
), spc
, flags
);
1733 if (!gimple_seq_empty_p (gimple_omp_body (gs
)))
1735 newline_and_indent (buffer
, spc
+ 2);
1736 pp_left_brace (buffer
);
1737 pp_newline (buffer
);
1738 dump_gimple_seq (buffer
, gimple_omp_body (gs
), spc
+ 4, flags
);
1739 newline_and_indent (buffer
, spc
+ 2);
1740 pp_right_brace (buffer
);
1745 /* Dump a GIMPLE_OMP_{MASTER,ORDERED,SECTION} tuple on the
1746 pretty_printer BUFFER. */
1749 dump_gimple_omp_block (pretty_printer
*buffer
, gimple
*gs
, int spc
,
1752 if (flags
& TDF_RAW
)
1753 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%+BODY <%S> >", gs
,
1754 gimple_omp_body (gs
));
1757 switch (gimple_code (gs
))
1759 case GIMPLE_OMP_MASTER
:
1760 pp_string (buffer
, "#pragma omp master");
1762 case GIMPLE_OMP_TASKGROUP
:
1763 pp_string (buffer
, "#pragma omp taskgroup");
1765 case GIMPLE_OMP_SECTION
:
1766 pp_string (buffer
, "#pragma omp section");
1768 case GIMPLE_OMP_GRID_BODY
:
1769 pp_string (buffer
, "#pragma omp gridified body");
1774 if (!gimple_seq_empty_p (gimple_omp_body (gs
)))
1776 newline_and_indent (buffer
, spc
+ 2);
1777 pp_left_brace (buffer
);
1778 pp_newline (buffer
);
1779 dump_gimple_seq (buffer
, gimple_omp_body (gs
), spc
+ 4, flags
);
1780 newline_and_indent (buffer
, spc
+ 2);
1781 pp_right_brace (buffer
);
1786 /* Dump a GIMPLE_OMP_CRITICAL tuple on the pretty_printer BUFFER. */
1789 dump_gimple_omp_critical (pretty_printer
*buffer
, gomp_critical
*gs
,
1790 int spc
, dump_flags_t flags
)
1792 if (flags
& TDF_RAW
)
1793 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%+BODY <%S> >", gs
,
1794 gimple_omp_body (gs
));
1797 pp_string (buffer
, "#pragma omp critical");
1798 if (gimple_omp_critical_name (gs
))
1800 pp_string (buffer
, " (");
1801 dump_generic_node (buffer
, gimple_omp_critical_name (gs
), spc
,
1803 pp_right_paren (buffer
);
1805 dump_omp_clauses (buffer
, gimple_omp_critical_clauses (gs
), spc
, flags
);
1806 if (!gimple_seq_empty_p (gimple_omp_body (gs
)))
1808 newline_and_indent (buffer
, spc
+ 2);
1809 pp_left_brace (buffer
);
1810 pp_newline (buffer
);
1811 dump_gimple_seq (buffer
, gimple_omp_body (gs
), spc
+ 4, flags
);
1812 newline_and_indent (buffer
, spc
+ 2);
1813 pp_right_brace (buffer
);
1818 /* Dump a GIMPLE_OMP_ORDERED tuple on the pretty_printer BUFFER. */
1821 dump_gimple_omp_ordered (pretty_printer
*buffer
, gomp_ordered
*gs
,
1822 int spc
, dump_flags_t flags
)
1824 if (flags
& TDF_RAW
)
1825 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%+BODY <%S> >", gs
,
1826 gimple_omp_body (gs
));
1829 pp_string (buffer
, "#pragma omp ordered");
1830 dump_omp_clauses (buffer
, gimple_omp_ordered_clauses (gs
), spc
, flags
);
1831 if (!gimple_seq_empty_p (gimple_omp_body (gs
)))
1833 newline_and_indent (buffer
, spc
+ 2);
1834 pp_left_brace (buffer
);
1835 pp_newline (buffer
);
1836 dump_gimple_seq (buffer
, gimple_omp_body (gs
), spc
+ 4, flags
);
1837 newline_and_indent (buffer
, spc
+ 2);
1838 pp_right_brace (buffer
);
1843 /* Dump a GIMPLE_OMP_RETURN tuple on the pretty_printer BUFFER. */
1846 dump_gimple_omp_return (pretty_printer
*buffer
, gimple
*gs
, int spc
,
1849 if (flags
& TDF_RAW
)
1851 dump_gimple_fmt (buffer
, spc
, flags
, "%G <nowait=%d", gs
,
1852 (int) gimple_omp_return_nowait_p (gs
));
1853 if (gimple_omp_return_lhs (gs
))
1854 dump_gimple_fmt (buffer
, spc
, flags
, ", lhs=%T>",
1855 gimple_omp_return_lhs (gs
));
1857 dump_gimple_fmt (buffer
, spc
, flags
, ">");
1861 pp_string (buffer
, "#pragma omp return");
1862 if (gimple_omp_return_nowait_p (gs
))
1863 pp_string (buffer
, "(nowait)");
1864 if (gimple_omp_return_lhs (gs
))
1866 pp_string (buffer
, " (set ");
1867 dump_generic_node (buffer
, gimple_omp_return_lhs (gs
),
1869 pp_character (buffer
, ')');
1874 /* Dump a GIMPLE_TRANSACTION tuple on the pretty_printer BUFFER. */
1877 dump_gimple_transaction (pretty_printer
*buffer
, gtransaction
*gs
,
1878 int spc
, dump_flags_t flags
)
1880 unsigned subcode
= gimple_transaction_subcode (gs
);
1882 if (flags
& TDF_RAW
)
1884 dump_gimple_fmt (buffer
, spc
, flags
,
1885 "%G [SUBCODE=%x,NORM=%T,UNINST=%T,OVER=%T] "
1887 gs
, subcode
, gimple_transaction_label_norm (gs
),
1888 gimple_transaction_label_uninst (gs
),
1889 gimple_transaction_label_over (gs
),
1890 gimple_transaction_body (gs
));
1894 if (subcode
& GTMA_IS_OUTER
)
1895 pp_string (buffer
, "__transaction_atomic [[outer]]");
1896 else if (subcode
& GTMA_IS_RELAXED
)
1897 pp_string (buffer
, "__transaction_relaxed");
1899 pp_string (buffer
, "__transaction_atomic");
1900 subcode
&= ~GTMA_DECLARATION_MASK
;
1902 if (gimple_transaction_body (gs
))
1904 newline_and_indent (buffer
, spc
+ 2);
1905 pp_left_brace (buffer
);
1906 pp_newline (buffer
);
1907 dump_gimple_seq (buffer
, gimple_transaction_body (gs
),
1909 newline_and_indent (buffer
, spc
+ 2);
1910 pp_right_brace (buffer
);
1914 pp_string (buffer
, " //");
1915 if (gimple_transaction_label_norm (gs
))
1917 pp_string (buffer
, " NORM=");
1918 dump_generic_node (buffer
, gimple_transaction_label_norm (gs
),
1921 if (gimple_transaction_label_uninst (gs
))
1923 pp_string (buffer
, " UNINST=");
1924 dump_generic_node (buffer
, gimple_transaction_label_uninst (gs
),
1927 if (gimple_transaction_label_over (gs
))
1929 pp_string (buffer
, " OVER=");
1930 dump_generic_node (buffer
, gimple_transaction_label_over (gs
),
1935 pp_string (buffer
, " SUBCODE=[ ");
1936 if (subcode
& GTMA_HAVE_ABORT
)
1938 pp_string (buffer
, "GTMA_HAVE_ABORT ");
1939 subcode
&= ~GTMA_HAVE_ABORT
;
1941 if (subcode
& GTMA_HAVE_LOAD
)
1943 pp_string (buffer
, "GTMA_HAVE_LOAD ");
1944 subcode
&= ~GTMA_HAVE_LOAD
;
1946 if (subcode
& GTMA_HAVE_STORE
)
1948 pp_string (buffer
, "GTMA_HAVE_STORE ");
1949 subcode
&= ~GTMA_HAVE_STORE
;
1951 if (subcode
& GTMA_MAY_ENTER_IRREVOCABLE
)
1953 pp_string (buffer
, "GTMA_MAY_ENTER_IRREVOCABLE ");
1954 subcode
&= ~GTMA_MAY_ENTER_IRREVOCABLE
;
1956 if (subcode
& GTMA_DOES_GO_IRREVOCABLE
)
1958 pp_string (buffer
, "GTMA_DOES_GO_IRREVOCABLE ");
1959 subcode
&= ~GTMA_DOES_GO_IRREVOCABLE
;
1961 if (subcode
& GTMA_HAS_NO_INSTRUMENTATION
)
1963 pp_string (buffer
, "GTMA_HAS_NO_INSTRUMENTATION ");
1964 subcode
&= ~GTMA_HAS_NO_INSTRUMENTATION
;
1967 pp_printf (buffer
, "0x%x ", subcode
);
1968 pp_right_bracket (buffer
);
1974 /* Dump a GIMPLE_ASM tuple on the pretty_printer BUFFER, SPC spaces of
1975 indent. FLAGS specifies details to show in the dump (see TDF_* in
1979 dump_gimple_asm (pretty_printer
*buffer
, gasm
*gs
, int spc
, dump_flags_t flags
)
1981 unsigned int i
, n
, f
, fields
;
1983 if (flags
& TDF_RAW
)
1985 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%+STRING <%n%s%n>", gs
,
1986 gimple_asm_string (gs
));
1988 n
= gimple_asm_noutputs (gs
);
1991 newline_and_indent (buffer
, spc
+ 2);
1992 pp_string (buffer
, "OUTPUT: ");
1993 for (i
= 0; i
< n
; i
++)
1995 dump_generic_node (buffer
, gimple_asm_output_op (gs
, i
),
1998 pp_string (buffer
, ", ");
2002 n
= gimple_asm_ninputs (gs
);
2005 newline_and_indent (buffer
, spc
+ 2);
2006 pp_string (buffer
, "INPUT: ");
2007 for (i
= 0; i
< n
; i
++)
2009 dump_generic_node (buffer
, gimple_asm_input_op (gs
, i
),
2012 pp_string (buffer
, ", ");
2016 n
= gimple_asm_nclobbers (gs
);
2019 newline_and_indent (buffer
, spc
+ 2);
2020 pp_string (buffer
, "CLOBBER: ");
2021 for (i
= 0; i
< n
; i
++)
2023 dump_generic_node (buffer
, gimple_asm_clobber_op (gs
, i
),
2026 pp_string (buffer
, ", ");
2030 n
= gimple_asm_nlabels (gs
);
2033 newline_and_indent (buffer
, spc
+ 2);
2034 pp_string (buffer
, "LABEL: ");
2035 for (i
= 0; i
< n
; i
++)
2037 dump_generic_node (buffer
, gimple_asm_label_op (gs
, i
),
2040 pp_string (buffer
, ", ");
2044 newline_and_indent (buffer
, spc
);
2045 pp_greater (buffer
);
2049 pp_string (buffer
, "__asm__");
2050 if (gimple_asm_volatile_p (gs
))
2051 pp_string (buffer
, " __volatile__");
2052 if (gimple_asm_inline_p (gs
))
2053 pp_string (buffer
, " __inline__");
2054 if (gimple_asm_nlabels (gs
))
2055 pp_string (buffer
, " goto");
2056 pp_string (buffer
, "(\"");
2057 pp_string (buffer
, gimple_asm_string (gs
));
2058 pp_string (buffer
, "\"");
2060 if (gimple_asm_nlabels (gs
))
2062 else if (gimple_asm_nclobbers (gs
))
2064 else if (gimple_asm_ninputs (gs
))
2066 else if (gimple_asm_noutputs (gs
))
2071 for (f
= 0; f
< fields
; ++f
)
2073 pp_string (buffer
, " : ");
2078 n
= gimple_asm_noutputs (gs
);
2079 for (i
= 0; i
< n
; i
++)
2081 dump_generic_node (buffer
, gimple_asm_output_op (gs
, i
),
2084 pp_string (buffer
, ", ");
2089 n
= gimple_asm_ninputs (gs
);
2090 for (i
= 0; i
< n
; i
++)
2092 dump_generic_node (buffer
, gimple_asm_input_op (gs
, i
),
2095 pp_string (buffer
, ", ");
2100 n
= gimple_asm_nclobbers (gs
);
2101 for (i
= 0; i
< n
; i
++)
2103 dump_generic_node (buffer
, gimple_asm_clobber_op (gs
, i
),
2106 pp_string (buffer
, ", ");
2111 n
= gimple_asm_nlabels (gs
);
2112 for (i
= 0; i
< n
; i
++)
2114 dump_generic_node (buffer
, gimple_asm_label_op (gs
, i
),
2117 pp_string (buffer
, ", ");
2126 pp_string (buffer
, ");");
2130 /* Dump ptr_info and range_info for NODE on pretty_printer BUFFER with
2131 SPC spaces of indent. */
2134 dump_ssaname_info (pretty_printer
*buffer
, tree node
, int spc
)
2136 if (TREE_CODE (node
) != SSA_NAME
)
2139 if (POINTER_TYPE_P (TREE_TYPE (node
))
2140 && SSA_NAME_PTR_INFO (node
))
2142 unsigned int align
, misalign
;
2143 struct ptr_info_def
*pi
= SSA_NAME_PTR_INFO (node
);
2144 pp_string (buffer
, "# PT = ");
2145 pp_points_to_solution (buffer
, &pi
->pt
);
2146 newline_and_indent (buffer
, spc
);
2147 if (get_ptr_info_alignment (pi
, &align
, &misalign
))
2149 pp_printf (buffer
, "# ALIGN = %u, MISALIGN = %u", align
, misalign
);
2150 newline_and_indent (buffer
, spc
);
2154 if (!POINTER_TYPE_P (TREE_TYPE (node
))
2155 && SSA_NAME_RANGE_INFO (node
))
2157 wide_int min
, max
, nonzero_bits
;
2158 value_range_kind range_type
= get_range_info (node
, &min
, &max
);
2160 if (range_type
== VR_VARYING
)
2161 pp_printf (buffer
, "# RANGE VR_VARYING");
2162 else if (range_type
== VR_RANGE
|| range_type
== VR_ANTI_RANGE
)
2164 pp_printf (buffer
, "# RANGE ");
2165 pp_printf (buffer
, "%s[", range_type
== VR_RANGE
? "" : "~");
2166 pp_wide_int (buffer
, min
, TYPE_SIGN (TREE_TYPE (node
)));
2167 pp_printf (buffer
, ", ");
2168 pp_wide_int (buffer
, max
, TYPE_SIGN (TREE_TYPE (node
)));
2169 pp_printf (buffer
, "]");
2171 nonzero_bits
= get_nonzero_bits (node
);
2172 if (nonzero_bits
!= -1)
2174 pp_string (buffer
, " NONZERO ");
2175 pp_wide_int (buffer
, nonzero_bits
, UNSIGNED
);
2177 newline_and_indent (buffer
, spc
);
2181 /* As dump_ssaname_info, but dump to FILE. */
2184 dump_ssaname_info_to_file (FILE *file
, tree node
, int spc
)
2186 pretty_printer buffer
;
2187 pp_needs_newline (&buffer
) = true;
2188 buffer
.buffer
->stream
= file
;
2189 dump_ssaname_info (&buffer
, node
, spc
);
2193 /* Dump a PHI node PHI. BUFFER, SPC and FLAGS are as in pp_gimple_stmt_1.
2194 The caller is responsible for calling pp_flush on BUFFER to finalize
2195 pretty printer. If COMMENT is true, print this after #. */
2198 dump_gimple_phi (pretty_printer
*buffer
, gphi
*phi
, int spc
, bool comment
,
2202 tree lhs
= gimple_phi_result (phi
);
2204 if (flags
& TDF_ALIAS
)
2205 dump_ssaname_info (buffer
, lhs
, spc
);
2208 pp_string (buffer
, "# ");
2210 if (flags
& TDF_RAW
)
2211 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T, ", phi
,
2212 gimple_phi_result (phi
));
2215 dump_generic_node (buffer
, lhs
, spc
, flags
, false);
2216 if (flags
& TDF_GIMPLE
)
2217 pp_string (buffer
, " = __PHI (");
2219 pp_string (buffer
, " = PHI <");
2221 for (i
= 0; i
< gimple_phi_num_args (phi
); i
++)
2223 if ((flags
& TDF_LINENO
) && gimple_phi_arg_has_location (phi
, i
))
2224 dump_location (buffer
, gimple_phi_arg_location (phi
, i
));
2225 basic_block src
= gimple_phi_arg_edge (phi
, i
)->src
;
2226 if (flags
& TDF_GIMPLE
)
2228 pp_string (buffer
, "__BB");
2229 pp_decimal_int (buffer
, src
->index
);
2230 pp_string (buffer
, ": ");
2232 dump_generic_node (buffer
, gimple_phi_arg_def (phi
, i
), spc
, flags
,
2234 if (! (flags
& TDF_GIMPLE
))
2236 pp_left_paren (buffer
);
2237 pp_decimal_int (buffer
, src
->index
);
2238 pp_right_paren (buffer
);
2240 if (i
< gimple_phi_num_args (phi
) - 1)
2241 pp_string (buffer
, ", ");
2243 if (flags
& TDF_GIMPLE
)
2244 pp_string (buffer
, ");");
2246 pp_greater (buffer
);
2250 /* Dump a GIMPLE_OMP_PARALLEL tuple on the pretty_printer BUFFER, SPC spaces
2251 of indent. FLAGS specifies details to show in the dump (see TDF_* in
2255 dump_gimple_omp_parallel (pretty_printer
*buffer
, gomp_parallel
*gs
,
2256 int spc
, dump_flags_t flags
)
2258 if (flags
& TDF_RAW
)
2260 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%+BODY <%S>%nCLAUSES <", gs
,
2261 gimple_omp_body (gs
));
2262 dump_omp_clauses (buffer
, gimple_omp_parallel_clauses (gs
), spc
, flags
);
2263 dump_gimple_fmt (buffer
, spc
, flags
, " >, %T, %T%n>",
2264 gimple_omp_parallel_child_fn (gs
),
2265 gimple_omp_parallel_data_arg (gs
));
2270 pp_string (buffer
, "#pragma omp parallel");
2271 dump_omp_clauses (buffer
, gimple_omp_parallel_clauses (gs
), spc
, flags
);
2272 if (gimple_omp_parallel_child_fn (gs
))
2274 pp_string (buffer
, " [child fn: ");
2275 dump_generic_node (buffer
, gimple_omp_parallel_child_fn (gs
),
2277 pp_string (buffer
, " (");
2278 if (gimple_omp_parallel_data_arg (gs
))
2279 dump_generic_node (buffer
, gimple_omp_parallel_data_arg (gs
),
2282 pp_string (buffer
, "???");
2283 pp_string (buffer
, ")]");
2285 body
= gimple_omp_body (gs
);
2286 if (body
&& gimple_code (gimple_seq_first_stmt (body
)) != GIMPLE_BIND
)
2288 newline_and_indent (buffer
, spc
+ 2);
2289 pp_left_brace (buffer
);
2290 pp_newline (buffer
);
2291 dump_gimple_seq (buffer
, body
, spc
+ 4, flags
);
2292 newline_and_indent (buffer
, spc
+ 2);
2293 pp_right_brace (buffer
);
2297 pp_newline (buffer
);
2298 dump_gimple_seq (buffer
, body
, spc
+ 2, flags
);
2304 /* Dump a GIMPLE_OMP_TASK tuple on the pretty_printer BUFFER, SPC spaces
2305 of indent. FLAGS specifies details to show in the dump (see TDF_* in
2309 dump_gimple_omp_task (pretty_printer
*buffer
, gomp_task
*gs
, int spc
,
2312 if (flags
& TDF_RAW
)
2314 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%+BODY <%S>%nCLAUSES <", gs
,
2315 gimple_omp_body (gs
));
2316 dump_omp_clauses (buffer
, gimple_omp_task_clauses (gs
), spc
, flags
);
2317 dump_gimple_fmt (buffer
, spc
, flags
, " >, %T, %T, %T, %T, %T%n>",
2318 gimple_omp_task_child_fn (gs
),
2319 gimple_omp_task_data_arg (gs
),
2320 gimple_omp_task_copy_fn (gs
),
2321 gimple_omp_task_arg_size (gs
),
2322 gimple_omp_task_arg_size (gs
));
2327 if (gimple_omp_task_taskloop_p (gs
))
2328 pp_string (buffer
, "#pragma omp taskloop");
2329 else if (gimple_omp_task_taskwait_p (gs
))
2330 pp_string (buffer
, "#pragma omp taskwait");
2332 pp_string (buffer
, "#pragma omp task");
2333 dump_omp_clauses (buffer
, gimple_omp_task_clauses (gs
), spc
, flags
);
2334 if (gimple_omp_task_child_fn (gs
))
2336 pp_string (buffer
, " [child fn: ");
2337 dump_generic_node (buffer
, gimple_omp_task_child_fn (gs
),
2339 pp_string (buffer
, " (");
2340 if (gimple_omp_task_data_arg (gs
))
2341 dump_generic_node (buffer
, gimple_omp_task_data_arg (gs
),
2344 pp_string (buffer
, "???");
2345 pp_string (buffer
, ")]");
2347 body
= gimple_omp_body (gs
);
2348 if (body
&& gimple_code (gimple_seq_first_stmt (body
)) != GIMPLE_BIND
)
2350 newline_and_indent (buffer
, spc
+ 2);
2351 pp_left_brace (buffer
);
2352 pp_newline (buffer
);
2353 dump_gimple_seq (buffer
, body
, spc
+ 4, flags
);
2354 newline_and_indent (buffer
, spc
+ 2);
2355 pp_right_brace (buffer
);
2359 pp_newline (buffer
);
2360 dump_gimple_seq (buffer
, body
, spc
+ 2, flags
);
2366 /* Dump a GIMPLE_OMP_ATOMIC_LOAD tuple on the pretty_printer BUFFER, SPC
2367 spaces of indent. FLAGS specifies details to show in the dump (see TDF_*
2371 dump_gimple_omp_atomic_load (pretty_printer
*buffer
, gomp_atomic_load
*gs
,
2372 int spc
, dump_flags_t flags
)
2374 if (flags
& TDF_RAW
)
2376 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T, %T>", gs
,
2377 gimple_omp_atomic_load_lhs (gs
),
2378 gimple_omp_atomic_load_rhs (gs
));
2382 pp_string (buffer
, "#pragma omp atomic_load");
2383 dump_omp_atomic_memory_order (buffer
,
2384 gimple_omp_atomic_memory_order (gs
));
2385 if (gimple_omp_atomic_need_value_p (gs
))
2386 pp_string (buffer
, " [needed]");
2387 newline_and_indent (buffer
, spc
+ 2);
2388 dump_generic_node (buffer
, gimple_omp_atomic_load_lhs (gs
),
2394 dump_generic_node (buffer
, gimple_omp_atomic_load_rhs (gs
),
2399 /* Dump a GIMPLE_OMP_ATOMIC_STORE tuple on the pretty_printer BUFFER, SPC
2400 spaces of indent. FLAGS specifies details to show in the dump (see TDF_*
2404 dump_gimple_omp_atomic_store (pretty_printer
*buffer
,
2405 gomp_atomic_store
*gs
, int spc
,
2408 if (flags
& TDF_RAW
)
2410 dump_gimple_fmt (buffer
, spc
, flags
, "%G <%T>", gs
,
2411 gimple_omp_atomic_store_val (gs
));
2415 pp_string (buffer
, "#pragma omp atomic_store");
2416 dump_omp_atomic_memory_order (buffer
,
2417 gimple_omp_atomic_memory_order (gs
));
2419 if (gimple_omp_atomic_need_value_p (gs
))
2420 pp_string (buffer
, "[needed] ");
2421 pp_left_paren (buffer
);
2422 dump_generic_node (buffer
, gimple_omp_atomic_store_val (gs
),
2424 pp_right_paren (buffer
);
2429 /* Dump all the memory operands for statement GS. BUFFER, SPC and
2430 FLAGS are as in pp_gimple_stmt_1. */
2433 dump_gimple_mem_ops (pretty_printer
*buffer
, gimple
*gs
, int spc
,
2436 tree vdef
= gimple_vdef (gs
);
2437 tree vuse
= gimple_vuse (gs
);
2439 if (vdef
!= NULL_TREE
)
2441 pp_string (buffer
, "# ");
2442 dump_generic_node (buffer
, vdef
, spc
+ 2, flags
, false);
2443 pp_string (buffer
, " = VDEF <");
2444 dump_generic_node (buffer
, vuse
, spc
+ 2, flags
, false);
2445 pp_greater (buffer
);
2446 newline_and_indent (buffer
, spc
);
2448 else if (vuse
!= NULL_TREE
)
2450 pp_string (buffer
, "# VUSE <");
2451 dump_generic_node (buffer
, vuse
, spc
+ 2, flags
, false);
2452 pp_greater (buffer
);
2453 newline_and_indent (buffer
, spc
);
2458 /* Print the gimple statement GS on the pretty printer BUFFER, SPC
2459 spaces of indent. FLAGS specifies details to show in the dump (see
2460 TDF_* in dumpfile.h). The caller is responsible for calling
2461 pp_flush on BUFFER to finalize the pretty printer. */
2464 pp_gimple_stmt_1 (pretty_printer
*buffer
, gimple
*gs
, int spc
,
2470 if (flags
& TDF_STMTADDR
)
2471 pp_printf (buffer
, "<&%p> ", (void *) gs
);
2473 if ((flags
& TDF_LINENO
) && gimple_has_location (gs
))
2474 dump_location (buffer
, gimple_location (gs
));
2478 int lp_nr
= lookup_stmt_eh_lp (gs
);
2480 pp_printf (buffer
, "[LP %d] ", lp_nr
);
2482 pp_printf (buffer
, "[MNT %d] ", -lp_nr
);
2485 if ((flags
& (TDF_VOPS
|TDF_MEMSYMS
))
2486 && gimple_has_mem_ops (gs
))
2487 dump_gimple_mem_ops (buffer
, gs
, spc
, flags
);
2489 if (gimple_has_lhs (gs
)
2490 && (flags
& TDF_ALIAS
))
2491 dump_ssaname_info (buffer
, gimple_get_lhs (gs
), spc
);
2493 switch (gimple_code (gs
))
2496 dump_gimple_asm (buffer
, as_a
<gasm
*> (gs
), spc
, flags
);
2500 dump_gimple_assign (buffer
, as_a
<gassign
*> (gs
), spc
, flags
);
2504 dump_gimple_bind (buffer
, as_a
<gbind
*> (gs
), spc
, flags
);
2508 dump_gimple_call (buffer
, as_a
<gcall
*> (gs
), spc
, flags
);
2512 dump_gimple_cond (buffer
, as_a
<gcond
*> (gs
), spc
, flags
);
2516 dump_gimple_label (buffer
, as_a
<glabel
*> (gs
), spc
, flags
);
2520 dump_gimple_goto (buffer
, as_a
<ggoto
*> (gs
), spc
, flags
);
2524 pp_string (buffer
, "GIMPLE_NOP");
2528 dump_gimple_return (buffer
, as_a
<greturn
*> (gs
), spc
, flags
);
2532 dump_gimple_switch (buffer
, as_a
<gswitch
*> (gs
), spc
, flags
);
2536 dump_gimple_try (buffer
, as_a
<gtry
*> (gs
), spc
, flags
);
2540 dump_gimple_phi (buffer
, as_a
<gphi
*> (gs
), spc
, false, flags
);
2543 case GIMPLE_OMP_PARALLEL
:
2544 dump_gimple_omp_parallel (buffer
, as_a
<gomp_parallel
*> (gs
), spc
,
2548 case GIMPLE_OMP_TASK
:
2549 dump_gimple_omp_task (buffer
, as_a
<gomp_task
*> (gs
), spc
, flags
);
2552 case GIMPLE_OMP_ATOMIC_LOAD
:
2553 dump_gimple_omp_atomic_load (buffer
, as_a
<gomp_atomic_load
*> (gs
),
2557 case GIMPLE_OMP_ATOMIC_STORE
:
2558 dump_gimple_omp_atomic_store (buffer
,
2559 as_a
<gomp_atomic_store
*> (gs
),
2563 case GIMPLE_OMP_FOR
:
2564 dump_gimple_omp_for (buffer
, as_a
<gomp_for
*> (gs
), spc
, flags
);
2567 case GIMPLE_OMP_CONTINUE
:
2568 dump_gimple_omp_continue (buffer
, as_a
<gomp_continue
*> (gs
), spc
,
2572 case GIMPLE_OMP_SINGLE
:
2573 dump_gimple_omp_single (buffer
, as_a
<gomp_single
*> (gs
), spc
,
2577 case GIMPLE_OMP_TARGET
:
2578 dump_gimple_omp_target (buffer
, as_a
<gomp_target
*> (gs
), spc
,
2582 case GIMPLE_OMP_TEAMS
:
2583 dump_gimple_omp_teams (buffer
, as_a
<gomp_teams
*> (gs
), spc
,
2587 case GIMPLE_OMP_RETURN
:
2588 dump_gimple_omp_return (buffer
, gs
, spc
, flags
);
2591 case GIMPLE_OMP_SECTIONS
:
2592 dump_gimple_omp_sections (buffer
, as_a
<gomp_sections
*> (gs
),
2596 case GIMPLE_OMP_SECTIONS_SWITCH
:
2597 pp_string (buffer
, "GIMPLE_SECTIONS_SWITCH");
2600 case GIMPLE_OMP_TASKGROUP
:
2601 dump_gimple_omp_taskgroup (buffer
, gs
, spc
, flags
);
2604 case GIMPLE_OMP_MASTER
:
2605 case GIMPLE_OMP_SECTION
:
2606 case GIMPLE_OMP_GRID_BODY
:
2607 dump_gimple_omp_block (buffer
, gs
, spc
, flags
);
2610 case GIMPLE_OMP_ORDERED
:
2611 dump_gimple_omp_ordered (buffer
, as_a
<gomp_ordered
*> (gs
), spc
,
2615 case GIMPLE_OMP_CRITICAL
:
2616 dump_gimple_omp_critical (buffer
, as_a
<gomp_critical
*> (gs
), spc
,
2621 dump_gimple_catch (buffer
, as_a
<gcatch
*> (gs
), spc
, flags
);
2624 case GIMPLE_EH_FILTER
:
2625 dump_gimple_eh_filter (buffer
, as_a
<geh_filter
*> (gs
), spc
, flags
);
2628 case GIMPLE_EH_MUST_NOT_THROW
:
2629 dump_gimple_eh_must_not_throw (buffer
,
2630 as_a
<geh_mnt
*> (gs
),
2634 case GIMPLE_EH_ELSE
:
2635 dump_gimple_eh_else (buffer
, as_a
<geh_else
*> (gs
), spc
, flags
);
2639 dump_gimple_resx (buffer
, as_a
<gresx
*> (gs
), spc
, flags
);
2642 case GIMPLE_EH_DISPATCH
:
2643 dump_gimple_eh_dispatch (buffer
, as_a
<geh_dispatch
*> (gs
), spc
,
2648 dump_gimple_debug (buffer
, as_a
<gdebug
*> (gs
), spc
, flags
);
2651 case GIMPLE_PREDICT
:
2652 pp_string (buffer
, "// predicted ");
2653 if (gimple_predict_outcome (gs
))
2654 pp_string (buffer
, "likely by ");
2656 pp_string (buffer
, "unlikely by ");
2657 pp_string (buffer
, predictor_name (gimple_predict_predictor (gs
)));
2658 pp_string (buffer
, " predictor.");
2661 case GIMPLE_TRANSACTION
:
2662 dump_gimple_transaction (buffer
, as_a
<gtransaction
*> (gs
), spc
,
2672 /* Dumps header of basic block BB to OUTF indented by INDENT
2673 spaces and details described by flags. */
2676 dump_gimple_bb_header (FILE *outf
, basic_block bb
, int indent
,
2679 if (flags
& TDF_BLOCKS
)
2681 if (flags
& TDF_LINENO
)
2683 gimple_stmt_iterator gsi
;
2685 fputs (";; ", outf
);
2687 for (gsi
= gsi_start_bb (bb
); !gsi_end_p (gsi
); gsi_next (&gsi
))
2688 if (!is_gimple_debug (gsi_stmt (gsi
))
2689 && get_lineno (gsi_stmt (gsi
)) != UNKNOWN_LOCATION
)
2691 fprintf (outf
, "%*sstarting at line %d",
2692 indent
, "", get_lineno (gsi_stmt (gsi
)));
2695 if (bb
->discriminator
)
2696 fprintf (outf
, ", discriminator %i", bb
->discriminator
);
2702 if (flags
& TDF_GIMPLE
)
2704 fprintf (outf
, "%*s__BB(%d", indent
, "", bb
->index
);
2705 if (bb
->loop_father
->header
== bb
)
2706 fprintf (outf
, ",loop_header(%d)", bb
->loop_father
->num
);
2707 fprintf (outf
, "):\n");
2710 fprintf (outf
, "%*s<bb %d> %s:\n",
2711 indent
, "", bb
->index
, dump_profile (bb
->count
));
2716 /* Dumps end of basic block BB to buffer BUFFER indented by INDENT
2720 dump_gimple_bb_footer (FILE *outf ATTRIBUTE_UNUSED
,
2721 basic_block bb ATTRIBUTE_UNUSED
,
2722 int indent ATTRIBUTE_UNUSED
,
2723 dump_flags_t flags ATTRIBUTE_UNUSED
)
2725 /* There is currently no GIMPLE-specific basic block info to dump. */
2730 /* Dump PHI nodes of basic block BB to BUFFER with details described
2731 by FLAGS and indented by INDENT spaces. */
2734 dump_phi_nodes (pretty_printer
*buffer
, basic_block bb
, int indent
,
2739 for (i
= gsi_start_phis (bb
); !gsi_end_p (i
); gsi_next (&i
))
2741 gphi
*phi
= i
.phi ();
2742 if (!virtual_operand_p (gimple_phi_result (phi
)) || (flags
& TDF_VOPS
))
2745 dump_gimple_phi (buffer
, phi
, indent
,
2746 (flags
& TDF_GIMPLE
) ? false : true, flags
);
2747 pp_newline (buffer
);
2753 /* Dump jump to basic block BB that is represented implicitly in the cfg
2757 pp_cfg_jump (pretty_printer
*buffer
, edge e
, dump_flags_t flags
)
2759 if (flags
& TDF_GIMPLE
)
2761 pp_string (buffer
, "goto __BB");
2762 pp_decimal_int (buffer
, e
->dest
->index
);
2763 pp_semicolon (buffer
);
2767 pp_string (buffer
, "goto <bb ");
2768 pp_decimal_int (buffer
, e
->dest
->index
);
2769 pp_greater (buffer
);
2770 pp_semicolon (buffer
);
2772 dump_edge_probability (buffer
, e
);
2777 /* Dump edges represented implicitly in basic block BB to BUFFER, indented
2778 by INDENT spaces, with details given by FLAGS. */
2781 dump_implicit_edges (pretty_printer
*buffer
, basic_block bb
, int indent
,
2787 stmt
= last_stmt (bb
);
2789 if (stmt
&& gimple_code (stmt
) == GIMPLE_COND
)
2791 edge true_edge
, false_edge
;
2793 /* When we are emitting the code or changing CFG, it is possible that
2794 the edges are not yet created. When we are using debug_bb in such
2795 a situation, we do not want it to crash. */
2796 if (EDGE_COUNT (bb
->succs
) != 2)
2798 extract_true_false_edges_from_block (bb
, &true_edge
, &false_edge
);
2800 INDENT (indent
+ 2);
2801 pp_cfg_jump (buffer
, true_edge
, flags
);
2802 newline_and_indent (buffer
, indent
);
2803 pp_string (buffer
, "else");
2804 newline_and_indent (buffer
, indent
+ 2);
2805 pp_cfg_jump (buffer
, false_edge
, flags
);
2806 pp_newline (buffer
);
2810 /* If there is a fallthru edge, we may need to add an artificial
2811 goto to the dump. */
2812 e
= find_fallthru_edge (bb
->succs
);
2814 if (e
&& (e
->dest
!= bb
->next_bb
|| (flags
& TDF_GIMPLE
)))
2818 if ((flags
& TDF_LINENO
)
2819 && e
->goto_locus
!= UNKNOWN_LOCATION
)
2820 dump_location (buffer
, e
->goto_locus
);
2822 pp_cfg_jump (buffer
, e
, flags
);
2823 pp_newline (buffer
);
2828 /* Dumps basic block BB to buffer BUFFER with details described by FLAGS and
2829 indented by INDENT spaces. */
2832 gimple_dump_bb_buff (pretty_printer
*buffer
, basic_block bb
, int indent
,
2835 gimple_stmt_iterator gsi
;
2837 int label_indent
= indent
- 2;
2839 if (label_indent
< 0)
2842 dump_phi_nodes (buffer
, bb
, indent
, flags
);
2844 for (gsi
= gsi_start_bb (bb
); !gsi_end_p (gsi
); gsi_next (&gsi
))
2848 stmt
= gsi_stmt (gsi
);
2850 curr_indent
= gimple_code (stmt
) == GIMPLE_LABEL
? label_indent
: indent
;
2852 INDENT (curr_indent
);
2853 pp_gimple_stmt_1 (buffer
, stmt
, curr_indent
, flags
);
2854 pp_newline_and_flush (buffer
);
2855 gcc_checking_assert (DECL_STRUCT_FUNCTION (current_function_decl
));
2856 dump_histograms_for_stmt (DECL_STRUCT_FUNCTION (current_function_decl
),
2857 pp_buffer (buffer
)->stream
, stmt
);
2860 dump_implicit_edges (buffer
, bb
, indent
, flags
);
2865 /* Dumps basic block BB to FILE with details described by FLAGS and
2866 indented by INDENT spaces. */
2869 gimple_dump_bb (FILE *file
, basic_block bb
, int indent
, dump_flags_t flags
)
2871 dump_gimple_bb_header (file
, bb
, indent
, flags
);
2872 if (bb
->index
>= NUM_FIXED_BLOCKS
)
2874 pretty_printer buffer
;
2875 pp_needs_newline (&buffer
) = true;
2876 buffer
.buffer
->stream
= file
;
2877 gimple_dump_bb_buff (&buffer
, bb
, indent
, flags
);
2879 dump_gimple_bb_footer (file
, bb
, indent
, flags
);
2882 /* Dumps basic block BB to pretty-printer PP with default dump flags and
2883 no indentation, for use as a label of a DOT graph record-node.
2884 ??? Should just use gimple_dump_bb_buff here, except that value profiling
2885 histogram dumping doesn't know about pretty-printers. */
2888 gimple_dump_bb_for_graph (pretty_printer
*pp
, basic_block bb
)
2890 pp_printf (pp
, "<bb %d>:\n", bb
->index
);
2891 pp_write_text_as_dot_label_to_stream (pp
, /*for_record=*/true);
2893 for (gphi_iterator gsi
= gsi_start_phis (bb
); !gsi_end_p (gsi
);
2896 gphi
*phi
= gsi
.phi ();
2897 if (!virtual_operand_p (gimple_phi_result (phi
))
2898 || (dump_flags
& TDF_VOPS
))
2901 pp_write_text_to_stream (pp
);
2902 pp_string (pp
, "# ");
2903 pp_gimple_stmt_1 (pp
, phi
, 0, dump_flags
);
2905 pp_write_text_as_dot_label_to_stream (pp
, /*for_record=*/true);
2909 for (gimple_stmt_iterator gsi
= gsi_start_bb (bb
); !gsi_end_p (gsi
);
2912 gimple
*stmt
= gsi_stmt (gsi
);
2914 pp_write_text_to_stream (pp
);
2915 pp_gimple_stmt_1 (pp
, stmt
, 0, dump_flags
);
2917 pp_write_text_as_dot_label_to_stream (pp
, /*for_record=*/true);
2919 dump_implicit_edges (pp
, bb
, 0, dump_flags
);
2920 pp_write_text_as_dot_label_to_stream (pp
, /*for_record=*/true);
2924 /* Handle the %G format for TEXT. Same as %K in handle_K_format in
2925 tree-pretty-print.c but with a Gimple statement as an argument. */
2928 percent_G_format (text_info
*text
)
2930 gimple
*stmt
= va_arg (*text
->args_ptr
, gimple
*);
2932 tree block
= gimple_block (stmt
);
2933 percent_K_format (text
, gimple_location (stmt
), block
);