]> git.ipfire.org Git - thirdparty/gcc.git/blame - gcc/gimple-pretty-print.c
Enhance analyze_brprob script
[thirdparty/gcc.git] / gcc / gimple-pretty-print.c
CommitLineData
726a989a 1/* Pretty formatting of GIMPLE statements and expressions.
818ab71a 2 Copyright (C) 2001-2016 Free Software Foundation, Inc.
726a989a
RB
3 Contributed by Aldy Hernandez <aldyh@redhat.com> and
4 Diego Novillo <dnovillo@google.com>
5
6This file is part of GCC.
7
8GCC is free software; you can redistribute it and/or modify it under
9the terms of the GNU General Public License as published by the Free
10Software Foundation; either version 3, or (at your option) any later
11version.
12
13GCC is distributed in the hope that it will be useful, but WITHOUT ANY
14WARRANTY; without even the implied warranty of MERCHANTABILITY or
15FITNESS FOR A PARTICULAR PURPOSE. See the GNU General Public License
16for more details.
17
18You should have received a copy of the GNU General Public License
19along with GCC; see the file COPYING3. If not see
20<http://www.gnu.org/licenses/>. */
21
22#include "config.h"
23#include "system.h"
24#include "coretypes.h"
c7131fb2 25#include "backend.h"
726a989a 26#include "tree.h"
c7131fb2 27#include "gimple.h"
9fdcd34e 28#include "gimple-predict.h"
c7131fb2 29#include "ssa.h"
957060b5 30#include "cgraph.h"
cf835838 31#include "gimple-pretty-print.h"
2fb9a547
AM
32#include "internal-fn.h"
33#include "tree-eh.h"
5be5c238 34#include "gimple-iterator.h"
442b4905 35#include "tree-cfg.h"
442b4905 36#include "dumpfile.h" /* for dump_flags */
726a989a 37#include "value-prof.h"
0a35513e 38#include "trans-mem.h"
0d56d3c1 39#include "cfganal.h"
56b7aede 40#include "asan.h"
726a989a
RB
41
42#define INDENT(SPACE) \
43 do { int i; for (i = 0; i < SPACE; i++) pp_space (buffer); } while (0)
44
726a989a
RB
45#define GIMPLE_NIY do_niy (buffer,gs)
46
47/* Try to print on BUFFER a default message for the unrecognized
48 gimple statement GS. */
49
50static void
355fe088 51do_niy (pretty_printer *buffer, gimple *gs)
726a989a
RB
52{
53 pp_printf (buffer, "<<< Unknown GIMPLE statement: %s >>>\n",
54 gimple_code_name[(int) gimple_code (gs)]);
55}
56
57
b5f47924 58/* Emit a newline and SPC indentation spaces to BUFFER. */
726a989a
RB
59
60static void
61newline_and_indent (pretty_printer *buffer, int spc)
62{
63 pp_newline (buffer);
64 INDENT (spc);
65}
66
67
68/* Print the GIMPLE statement GS on stderr. */
69
24e47c76 70DEBUG_FUNCTION void
355fe088 71debug_gimple_stmt (gimple *gs)
726a989a
RB
72{
73 print_gimple_stmt (stderr, gs, 0, TDF_VOPS|TDF_MEMSYMS);
726a989a
RB
74}
75
0d56d3c1
ML
76/* Dump E probability to BUFFER. */
77
78static void
79dump_edge_probability (pretty_printer *buffer, edge e)
80{
81 pp_scalar (buffer, " [%.1f%%]",
82 e->probability * 100.0 / REG_BR_PROB_BASE);
83}
726a989a 84
b5f47924
SS
85/* Print GIMPLE statement G to FILE using SPC indentation spaces and
86 FLAGS as in pp_gimple_stmt_1. */
726a989a
RB
87
88void
355fe088 89print_gimple_stmt (FILE *file, gimple *g, int spc, int flags)
726a989a 90{
b3f80694 91 pretty_printer buffer;
b3f80694
GDR
92 pp_needs_newline (&buffer) = true;
93 buffer.buffer->stream = file;
b5f47924 94 pp_gimple_stmt_1 (&buffer, g, spc, flags);
f8923f7e 95 pp_newline_and_flush (&buffer);
726a989a
RB
96}
97
7b3b6ae4 98DEBUG_FUNCTION void
355fe088 99debug (gimple &ref)
7b3b6ae4
LC
100{
101 print_gimple_stmt (stderr, &ref, 0, 0);
102}
103
104DEBUG_FUNCTION void
355fe088 105debug (gimple *ptr)
7b3b6ae4
LC
106{
107 if (ptr)
108 debug (*ptr);
109 else
110 fprintf (stderr, "<nil>\n");
111}
112
726a989a 113
b5f47924
SS
114/* Print GIMPLE statement G to FILE using SPC indentation spaces and
115 FLAGS as in pp_gimple_stmt_1. Print only the right-hand side
726a989a
RB
116 of the statement. */
117
118void
355fe088 119print_gimple_expr (FILE *file, gimple *g, int spc, int flags)
726a989a
RB
120{
121 flags |= TDF_RHS_ONLY;
b3f80694 122 pretty_printer buffer;
b3f80694
GDR
123 pp_needs_newline (&buffer) = true;
124 buffer.buffer->stream = file;
b5f47924 125 pp_gimple_stmt_1 (&buffer, g, spc, flags);
41222ddf 126 pp_flush (&buffer);
726a989a
RB
127}
128
129
b5f47924
SS
130/* Print the GIMPLE sequence SEQ on BUFFER using SPC indentation
131 spaces and FLAGS as in pp_gimple_stmt_1.
c4669594
SB
132 The caller is responsible for calling pp_flush on BUFFER to finalize
133 the pretty printer. */
726a989a
RB
134
135static void
136dump_gimple_seq (pretty_printer *buffer, gimple_seq seq, int spc, int flags)
137{
138 gimple_stmt_iterator i;
139
140 for (i = gsi_start (seq); !gsi_end_p (i); gsi_next (&i))
141 {
355fe088 142 gimple *gs = gsi_stmt (i);
726a989a 143 INDENT (spc);
b5f47924 144 pp_gimple_stmt_1 (buffer, gs, spc, flags);
726a989a
RB
145 if (!gsi_one_before_end_p (i))
146 pp_newline (buffer);
147 }
148}
149
150
b5f47924
SS
151/* Print GIMPLE sequence SEQ to FILE using SPC indentation spaces and
152 FLAGS as in pp_gimple_stmt_1. */
726a989a
RB
153
154void
155print_gimple_seq (FILE *file, gimple_seq seq, int spc, int flags)
156{
b3f80694 157 pretty_printer buffer;
b3f80694
GDR
158 pp_needs_newline (&buffer) = true;
159 buffer.buffer->stream = file;
726a989a 160 dump_gimple_seq (&buffer, seq, spc, flags);
f8923f7e 161 pp_newline_and_flush (&buffer);
726a989a
RB
162}
163
164
165/* Print the GIMPLE sequence SEQ on stderr. */
166
24e47c76 167DEBUG_FUNCTION void
726a989a
RB
168debug_gimple_seq (gimple_seq seq)
169{
170 print_gimple_seq (stderr, seq, 0, TDF_VOPS|TDF_MEMSYMS);
171}
172
173
174/* A simple helper to pretty-print some of the gimple tuples in the printf
073a8998 175 style. The format modifiers are preceded by '%' and are:
726a989a
RB
176 'G' - outputs a string corresponding to the code of the given gimple,
177 'S' - outputs a gimple_seq with indent of spc + 2,
178 'T' - outputs the tree t,
179 'd' - outputs an int as a decimal,
180 's' - outputs a string,
181 'n' - outputs a newline,
0a35513e 182 'x' - outputs an int as hexadecimal,
726a989a
RB
183 '+' - increases indent by 2 then outputs a newline,
184 '-' - decreases indent by 2 then outputs a newline. */
185
186static void
187dump_gimple_fmt (pretty_printer *buffer, int spc, int flags,
188 const char *fmt, ...)
189{
190 va_list args;
191 const char *c;
192 const char *tmp;
193
194 va_start (args, fmt);
195 for (c = fmt; *c; c++)
196 {
197 if (*c == '%')
198 {
199 gimple_seq seq;
200 tree t;
355fe088 201 gimple *g;
726a989a
RB
202 switch (*++c)
203 {
204 case 'G':
355fe088 205 g = va_arg (args, gimple *);
726a989a
RB
206 tmp = gimple_code_name[gimple_code (g)];
207 pp_string (buffer, tmp);
208 break;
209
210 case 'S':
211 seq = va_arg (args, gimple_seq);
212 pp_newline (buffer);
213 dump_gimple_seq (buffer, seq, spc + 2, flags);
214 newline_and_indent (buffer, spc);
215 break;
216
217 case 'T':
218 t = va_arg (args, tree);
219 if (t == NULL_TREE)
220 pp_string (buffer, "NULL");
221 else
222 dump_generic_node (buffer, t, spc, flags, false);
223 break;
224
225 case 'd':
226 pp_decimal_int (buffer, va_arg (args, int));
227 break;
228
229 case 's':
230 pp_string (buffer, va_arg (args, char *));
231 break;
232
233 case 'n':
234 newline_and_indent (buffer, spc);
235 break;
236
0a35513e
AH
237 case 'x':
238 pp_scalar (buffer, "%x", va_arg (args, int));
239 break;
240
726a989a
RB
241 case '+':
242 spc += 2;
243 newline_and_indent (buffer, spc);
244 break;
245
246 case '-':
247 spc -= 2;
248 newline_and_indent (buffer, spc);
249 break;
250
251 default:
252 gcc_unreachable ();
253 }
b8698a0f 254 }
726a989a
RB
255 else
256 pp_character (buffer, *c);
257 }
258 va_end (args);
259}
260
261
262/* Helper for dump_gimple_assign. Print the unary RHS of the
b5f47924 263 assignment GS. BUFFER, SPC and FLAGS are as in pp_gimple_stmt_1. */
726a989a
RB
264
265static void
538dd0b7 266dump_unary_rhs (pretty_printer *buffer, gassign *gs, int spc, int flags)
726a989a
RB
267{
268 enum tree_code rhs_code = gimple_assign_rhs_code (gs);
269 tree lhs = gimple_assign_lhs (gs);
270 tree rhs = gimple_assign_rhs1 (gs);
271
272 switch (rhs_code)
273 {
274 case VIEW_CONVERT_EXPR:
275 case ASSERT_EXPR:
276 dump_generic_node (buffer, rhs, spc, flags, false);
277 break;
278
279 case FIXED_CONVERT_EXPR:
09e881c9 280 case ADDR_SPACE_CONVERT_EXPR:
726a989a
RB
281 case FIX_TRUNC_EXPR:
282 case FLOAT_EXPR:
283 CASE_CONVERT:
07838b13 284 pp_left_paren (buffer);
726a989a
RB
285 dump_generic_node (buffer, TREE_TYPE (lhs), spc, flags, false);
286 pp_string (buffer, ") ");
0cf0d02b
JJ
287 if (op_prio (rhs) < op_code_prio (rhs_code))
288 {
07838b13 289 pp_left_paren (buffer);
0cf0d02b 290 dump_generic_node (buffer, rhs, spc, flags, false);
07838b13 291 pp_right_paren (buffer);
0cf0d02b
JJ
292 }
293 else
294 dump_generic_node (buffer, rhs, spc, flags, false);
726a989a 295 break;
b8698a0f 296
726a989a
RB
297 case PAREN_EXPR:
298 pp_string (buffer, "((");
299 dump_generic_node (buffer, rhs, spc, flags, false);
300 pp_string (buffer, "))");
301 break;
b8698a0f 302
726a989a
RB
303 case ABS_EXPR:
304 pp_string (buffer, "ABS_EXPR <");
305 dump_generic_node (buffer, rhs, spc, flags, false);
07838b13 306 pp_greater (buffer);
726a989a
RB
307 break;
308
309 default:
310 if (TREE_CODE_CLASS (rhs_code) == tcc_declaration
311 || TREE_CODE_CLASS (rhs_code) == tcc_constant
312 || TREE_CODE_CLASS (rhs_code) == tcc_reference
313 || rhs_code == SSA_NAME
314 || rhs_code == ADDR_EXPR
315 || rhs_code == CONSTRUCTOR)
0cf0d02b
JJ
316 {
317 dump_generic_node (buffer, rhs, spc, flags, false);
318 break;
319 }
726a989a 320 else if (rhs_code == BIT_NOT_EXPR)
07838b13 321 pp_complement (buffer);
726a989a 322 else if (rhs_code == TRUTH_NOT_EXPR)
07838b13 323 pp_exclamation (buffer);
726a989a 324 else if (rhs_code == NEGATE_EXPR)
07838b13 325 pp_minus (buffer);
726a989a
RB
326 else
327 {
07838b13 328 pp_left_bracket (buffer);
5806f481 329 pp_string (buffer, get_tree_code_name (rhs_code));
726a989a
RB
330 pp_string (buffer, "] ");
331 }
332
0cf0d02b
JJ
333 if (op_prio (rhs) < op_code_prio (rhs_code))
334 {
07838b13 335 pp_left_paren (buffer);
0cf0d02b 336 dump_generic_node (buffer, rhs, spc, flags, false);
07838b13 337 pp_right_paren (buffer);
0cf0d02b
JJ
338 }
339 else
340 dump_generic_node (buffer, rhs, spc, flags, false);
726a989a
RB
341 break;
342 }
343}
344
345
346/* Helper for dump_gimple_assign. Print the binary RHS of the
b5f47924 347 assignment GS. BUFFER, SPC and FLAGS are as in pp_gimple_stmt_1. */
726a989a
RB
348
349static void
538dd0b7 350dump_binary_rhs (pretty_printer *buffer, gassign *gs, int spc, int flags)
726a989a 351{
2603276e
JJ
352 const char *p;
353 enum tree_code code = gimple_assign_rhs_code (gs);
354 switch (code)
726a989a
RB
355 {
356 case COMPLEX_EXPR:
726a989a 357 case MIN_EXPR:
726a989a 358 case MAX_EXPR:
2603276e
JJ
359 case VEC_WIDEN_MULT_HI_EXPR:
360 case VEC_WIDEN_MULT_LO_EXPR:
3f30a9a6
RH
361 case VEC_WIDEN_MULT_EVEN_EXPR:
362 case VEC_WIDEN_MULT_ODD_EXPR:
2603276e
JJ
363 case VEC_PACK_TRUNC_EXPR:
364 case VEC_PACK_SAT_EXPR:
365 case VEC_PACK_FIX_TRUNC_EXPR:
36ba4aae
IR
366 case VEC_WIDEN_LSHIFT_HI_EXPR:
367 case VEC_WIDEN_LSHIFT_LO_EXPR:
5806f481 368 for (p = get_tree_code_name (code); *p; p++)
2603276e
JJ
369 pp_character (buffer, TOUPPER (*p));
370 pp_string (buffer, " <");
726a989a
RB
371 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
372 pp_string (buffer, ", ");
373 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
07838b13 374 pp_greater (buffer);
726a989a
RB
375 break;
376
377 default:
0cf0d02b
JJ
378 if (op_prio (gimple_assign_rhs1 (gs)) <= op_code_prio (code))
379 {
07838b13 380 pp_left_paren (buffer);
0cf0d02b
JJ
381 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags,
382 false);
07838b13 383 pp_right_paren (buffer);
0cf0d02b
JJ
384 }
385 else
386 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
726a989a
RB
387 pp_space (buffer);
388 pp_string (buffer, op_symbol_code (gimple_assign_rhs_code (gs)));
389 pp_space (buffer);
0cf0d02b
JJ
390 if (op_prio (gimple_assign_rhs2 (gs)) <= op_code_prio (code))
391 {
07838b13 392 pp_left_paren (buffer);
0cf0d02b
JJ
393 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags,
394 false);
07838b13 395 pp_right_paren (buffer);
0cf0d02b
JJ
396 }
397 else
398 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
726a989a
RB
399 }
400}
401
0354c0c7 402/* Helper for dump_gimple_assign. Print the ternary RHS of the
b5f47924 403 assignment GS. BUFFER, SPC and FLAGS are as in pp_gimple_stmt_1. */
0354c0c7
BS
404
405static void
538dd0b7 406dump_ternary_rhs (pretty_printer *buffer, gassign *gs, int spc, int flags)
0354c0c7
BS
407{
408 const char *p;
409 enum tree_code code = gimple_assign_rhs_code (gs);
410 switch (code)
411 {
412 case WIDEN_MULT_PLUS_EXPR:
413 case WIDEN_MULT_MINUS_EXPR:
5806f481 414 for (p = get_tree_code_name (code); *p; p++)
0354c0c7
BS
415 pp_character (buffer, TOUPPER (*p));
416 pp_string (buffer, " <");
417 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
418 pp_string (buffer, ", ");
419 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
420 pp_string (buffer, ", ");
421 dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
07838b13 422 pp_greater (buffer);
0354c0c7
BS
423 break;
424
16949072
RG
425 case FMA_EXPR:
426 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
427 pp_string (buffer, " * ");
428 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
429 pp_string (buffer, " + ");
430 dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
431 break;
432
f471fe72
RG
433 case DOT_PROD_EXPR:
434 pp_string (buffer, "DOT_PROD_EXPR <");
435 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
436 pp_string (buffer, ", ");
437 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
438 pp_string (buffer, ", ");
439 dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
79d652a5
CH
440 pp_greater (buffer);
441 break;
442
443 case SAD_EXPR:
444 pp_string (buffer, "SAD_EXPR <");
445 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
446 pp_string (buffer, ", ");
447 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
448 pp_string (buffer, ", ");
449 dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
137a1a27 450 pp_greater (buffer);
f471fe72 451 break;
f90e8e2e 452
2205ed25
RH
453 case VEC_PERM_EXPR:
454 pp_string (buffer, "VEC_PERM_EXPR <");
f90e8e2e
AS
455 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
456 pp_string (buffer, ", ");
457 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
458 pp_string (buffer, ", ");
459 dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
137a1a27 460 pp_greater (buffer);
f90e8e2e 461 break;
f471fe72
RG
462
463 case REALIGN_LOAD_EXPR:
464 pp_string (buffer, "REALIGN_LOAD <");
465 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
466 pp_string (buffer, ", ");
467 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
468 pp_string (buffer, ", ");
469 dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
137a1a27 470 pp_greater (buffer);
4e71066d
RG
471 break;
472
473 case COND_EXPR:
474 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
475 pp_string (buffer, " ? ");
476 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
477 pp_string (buffer, " : ");
478 dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
479 break;
480
481 case VEC_COND_EXPR:
482 pp_string (buffer, "VEC_COND_EXPR <");
483 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
484 pp_string (buffer, ", ");
485 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
486 pp_string (buffer, ", ");
487 dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
137a1a27 488 pp_greater (buffer);
f471fe72
RG
489 break;
490
483c6429
RG
491 case BIT_INSERT_EXPR:
492 pp_string (buffer, "BIT_INSERT_EXPR <");
493 dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
494 pp_string (buffer, ", ");
495 dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
496 pp_string (buffer, ", ");
497 dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
498 pp_string (buffer, " (");
499 if (INTEGRAL_TYPE_P (TREE_TYPE (gimple_assign_rhs2 (gs))))
500 pp_decimal_int (buffer,
501 TYPE_PRECISION (TREE_TYPE (gimple_assign_rhs2 (gs))));
502 else
503 dump_generic_node (buffer,
504 TYPE_SIZE (TREE_TYPE (gimple_assign_rhs2 (gs))),
505 spc, flags, false);
506 pp_string (buffer, " bits)>");
507 break;
508
0354c0c7
BS
509 default:
510 gcc_unreachable ();
511 }
512}
513
726a989a
RB
514
515/* Dump the gimple assignment GS. BUFFER, SPC and FLAGS are as in
b5f47924 516 pp_gimple_stmt_1. */
726a989a
RB
517
518static void
538dd0b7 519dump_gimple_assign (pretty_printer *buffer, gassign *gs, int spc, int flags)
726a989a
RB
520{
521 if (flags & TDF_RAW)
522 {
874a3756
MG
523 tree arg1 = NULL;
524 tree arg2 = NULL;
525 tree arg3 = NULL;
526 switch (gimple_num_ops (gs))
527 {
528 case 4:
529 arg3 = gimple_assign_rhs3 (gs);
191816a3 530 /* FALLTHRU */
874a3756
MG
531 case 3:
532 arg2 = gimple_assign_rhs2 (gs);
191816a3 533 /* FALLTHRU */
874a3756
MG
534 case 2:
535 arg1 = gimple_assign_rhs1 (gs);
536 break;
537 default:
538 gcc_unreachable ();
539 }
726a989a 540
874a3756 541 dump_gimple_fmt (buffer, spc, flags, "%G <%s, %T, %T, %T, %T>", gs,
5806f481 542 get_tree_code_name (gimple_assign_rhs_code (gs)),
874a3756 543 gimple_assign_lhs (gs), arg1, arg2, arg3);
726a989a
RB
544 }
545 else
546 {
547 if (!(flags & TDF_RHS_ONLY))
548 {
549 dump_generic_node (buffer, gimple_assign_lhs (gs), spc, flags, false);
550 pp_space (buffer);
07838b13 551 pp_equal (buffer);
726a989a
RB
552
553 if (gimple_assign_nontemporal_move_p (gs))
554 pp_string (buffer, "{nt}");
555
556 if (gimple_has_volatile_ops (gs))
557 pp_string (buffer, "{v}");
558
559 pp_space (buffer);
560 }
561
562 if (gimple_num_ops (gs) == 2)
563 dump_unary_rhs (buffer, gs, spc, flags);
564 else if (gimple_num_ops (gs) == 3)
565 dump_binary_rhs (buffer, gs, spc, flags);
0354c0c7
BS
566 else if (gimple_num_ops (gs) == 4)
567 dump_ternary_rhs (buffer, gs, spc, flags);
726a989a
RB
568 else
569 gcc_unreachable ();
570 if (!(flags & TDF_RHS_ONLY))
c3284718 571 pp_semicolon (buffer);
726a989a
RB
572 }
573}
574
575
576/* Dump the return statement GS. BUFFER, SPC and FLAGS are as in
b5f47924 577 pp_gimple_stmt_1. */
726a989a
RB
578
579static void
538dd0b7 580dump_gimple_return (pretty_printer *buffer, greturn *gs, int spc, int flags)
726a989a 581{
d5e254e1 582 tree t, t2;
726a989a
RB
583
584 t = gimple_return_retval (gs);
d5e254e1 585 t2 = gimple_return_retbnd (gs);
726a989a 586 if (flags & TDF_RAW)
d5e254e1 587 dump_gimple_fmt (buffer, spc, flags, "%G <%T %T>", gs, t, t2);
726a989a
RB
588 else
589 {
590 pp_string (buffer, "return");
591 if (t)
592 {
593 pp_space (buffer);
594 dump_generic_node (buffer, t, spc, flags, false);
595 }
d5e254e1
IE
596 if (t2)
597 {
598 pp_string (buffer, ", ");
599 dump_generic_node (buffer, t2, spc, flags, false);
600 }
726a989a
RB
601 pp_semicolon (buffer);
602 }
603}
604
605
606/* Dump the call arguments for a gimple call. BUFFER, FLAGS are as in
607 dump_gimple_call. */
608
609static void
538dd0b7 610dump_gimple_call_args (pretty_printer *buffer, gcall *gs, int flags)
726a989a 611{
4d58c533 612 size_t i = 0;
726a989a 613
4d58c533
NS
614 /* Pretty print first arg to certain internal fns. */
615 if (gimple_call_internal_p (gs))
616 {
617 const char *const *enums = NULL;
618 unsigned limit = 0;
619
620 switch (gimple_call_internal_fn (gs))
621 {
622 case IFN_UNIQUE:
623#define DEF(X) #X
624 static const char *const unique_args[] = {IFN_UNIQUE_CODES};
625#undef DEF
626 enums = unique_args;
627
628 limit = ARRAY_SIZE (unique_args);
629 break;
630
631 case IFN_GOACC_LOOP:
632#define DEF(X) #X
633 static const char *const loop_args[] = {IFN_GOACC_LOOP_CODES};
634#undef DEF
635 enums = loop_args;
636 limit = ARRAY_SIZE (loop_args);
637 break;
638
639 case IFN_GOACC_REDUCTION:
640#define DEF(X) #X
641 static const char *const reduction_args[]
642 = {IFN_GOACC_REDUCTION_CODES};
643#undef DEF
644 enums = reduction_args;
645 limit = ARRAY_SIZE (reduction_args);
646 break;
647
56b7aede
ML
648 case IFN_ASAN_MARK:
649#define DEF(X) #X
650 static const char *const asan_mark_args[] = {IFN_ASAN_MARK_FLAGS};
651#undef DEF
652 enums = asan_mark_args;
653 limit = ARRAY_SIZE (asan_mark_args);
654 break;
655
4d58c533
NS
656 default:
657 break;
658 }
659 if (limit)
660 {
661 tree arg0 = gimple_call_arg (gs, 0);
662 HOST_WIDE_INT v;
663
664 if (TREE_CODE (arg0) == INTEGER_CST
665 && tree_fits_shwi_p (arg0)
666 && (v = tree_to_shwi (arg0)) >= 0 && v < limit)
667 {
668 i++;
669 pp_string (buffer, enums[v]);
4d58c533
NS
670 }
671 }
672 }
673
674 for (; i < gimple_call_num_args (gs); i++)
726a989a 675 {
bc43e0ec 676 if (i)
726a989a 677 pp_string (buffer, ", ");
bc43e0ec 678 dump_generic_node (buffer, gimple_call_arg (gs, i), 0, flags, false);
726a989a
RB
679 }
680
681 if (gimple_call_va_arg_pack_p (gs))
682 {
bc43e0ec
NS
683 if (i)
684 pp_string (buffer, ", ");
726a989a
RB
685
686 pp_string (buffer, "__builtin_va_arg_pack ()");
687 }
688}
689
25a6a873
RG
690/* Dump the points-to solution *PT to BUFFER. */
691
692static void
693pp_points_to_solution (pretty_printer *buffer, struct pt_solution *pt)
694{
695 if (pt->anything)
696 {
697 pp_string (buffer, "anything ");
698 return;
699 }
700 if (pt->nonlocal)
701 pp_string (buffer, "nonlocal ");
702 if (pt->escaped)
703 pp_string (buffer, "escaped ");
704 if (pt->ipa_escaped)
705 pp_string (buffer, "unit-escaped ");
706 if (pt->null)
707 pp_string (buffer, "null ");
708 if (pt->vars
709 && !bitmap_empty_p (pt->vars))
710 {
711 bitmap_iterator bi;
712 unsigned i;
713 pp_string (buffer, "{ ");
714 EXECUTE_IF_SET_IN_BITMAP (pt->vars, 0, i, bi)
715 {
46eb666a
RG
716 pp_string (buffer, "D.");
717 pp_decimal_int (buffer, i);
07838b13 718 pp_space (buffer);
25a6a873 719 }
07838b13 720 pp_right_brace (buffer);
11924f8b 721 if (pt->vars_contains_nonlocal
763baff6
RB
722 || pt->vars_contains_escaped
723 || pt->vars_contains_escaped_heap
724 || pt->vars_contains_restrict)
725 {
726 const char *comma = "";
727 pp_string (buffer, " (");
728 if (pt->vars_contains_nonlocal)
729 {
730 pp_string (buffer, "nonlocal");
731 comma = ", ";
732 }
733 if (pt->vars_contains_escaped)
734 {
735 pp_string (buffer, comma);
736 pp_string (buffer, "escaped");
737 comma = ", ";
738 }
739 if (pt->vars_contains_escaped_heap)
740 {
741 pp_string (buffer, comma);
742 pp_string (buffer, "escaped heap");
743 comma = ", ";
744 }
745 if (pt->vars_contains_restrict)
746 {
747 pp_string (buffer, comma);
748 pp_string (buffer, "restrict");
da42ac7b
RB
749 comma = ", ";
750 }
751 if (pt->vars_contains_interposable)
752 {
753 pp_string (buffer, comma);
754 pp_string (buffer, "interposable");
763baff6
RB
755 }
756 pp_string (buffer, ")");
757 }
758
25a6a873
RG
759 }
760}
726a989a
RB
761
762/* Dump the call statement GS. BUFFER, SPC and FLAGS are as in
b5f47924 763 pp_gimple_stmt_1. */
726a989a
RB
764
765static void
538dd0b7 766dump_gimple_call (pretty_printer *buffer, gcall *gs, int spc, int flags)
726a989a
RB
767{
768 tree lhs = gimple_call_lhs (gs);
0a35513e 769 tree fn = gimple_call_fn (gs);
726a989a 770
25a6a873
RG
771 if (flags & TDF_ALIAS)
772 {
773 struct pt_solution *pt;
774 pt = gimple_call_use_set (gs);
775 if (!pt_solution_empty_p (pt))
776 {
777 pp_string (buffer, "# USE = ");
778 pp_points_to_solution (buffer, pt);
779 newline_and_indent (buffer, spc);
780 }
781 pt = gimple_call_clobber_set (gs);
782 if (!pt_solution_empty_p (pt))
783 {
784 pp_string (buffer, "# CLB = ");
785 pp_points_to_solution (buffer, pt);
786 newline_and_indent (buffer, spc);
787 }
788 }
789
726a989a
RB
790 if (flags & TDF_RAW)
791 {
25583c4f
RS
792 if (gimple_call_internal_p (gs))
793 dump_gimple_fmt (buffer, spc, flags, "%G <%s, %T", gs,
794 internal_fn_name (gimple_call_internal_fn (gs)), lhs);
795 else
0a35513e 796 dump_gimple_fmt (buffer, spc, flags, "%G <%T, %T", gs, fn, lhs);
726a989a
RB
797 if (gimple_call_num_args (gs) > 0)
798 {
799 pp_string (buffer, ", ");
800 dump_gimple_call_args (buffer, gs, flags);
801 }
07838b13 802 pp_greater (buffer);
726a989a
RB
803 }
804 else
805 {
806 if (lhs && !(flags & TDF_RHS_ONLY))
807 {
808 dump_generic_node (buffer, lhs, spc, flags, false);
809 pp_string (buffer, " =");
810
811 if (gimple_has_volatile_ops (gs))
812 pp_string (buffer, "{v}");
813
814 pp_space (buffer);
815 }
25583c4f
RS
816 if (gimple_call_internal_p (gs))
817 pp_string (buffer, internal_fn_name (gimple_call_internal_fn (gs)));
818 else
0a35513e 819 print_call_name (buffer, fn, flags);
726a989a
RB
820 pp_string (buffer, " (");
821 dump_gimple_call_args (buffer, gs, flags);
07838b13 822 pp_right_paren (buffer);
726a989a
RB
823 if (!(flags & TDF_RHS_ONLY))
824 pp_semicolon (buffer);
825 }
826
827 if (gimple_call_chain (gs))
828 {
829 pp_string (buffer, " [static-chain: ");
830 dump_generic_node (buffer, gimple_call_chain (gs), spc, flags, false);
07838b13 831 pp_right_bracket (buffer);
726a989a
RB
832 }
833
834 if (gimple_call_return_slot_opt_p (gs))
835 pp_string (buffer, " [return slot optimization]");
726a989a
RB
836 if (gimple_call_tail_p (gs))
837 pp_string (buffer, " [tail call]");
9a385c2d
DM
838 if (gimple_call_must_tail_p (gs))
839 pp_string (buffer, " [must tail call]");
0a35513e 840
cbe9d630
SD
841 if (fn == NULL)
842 return;
843
0a35513e
AH
844 /* Dump the arguments of _ITM_beginTransaction sanely. */
845 if (TREE_CODE (fn) == ADDR_EXPR)
846 fn = TREE_OPERAND (fn, 0);
847 if (TREE_CODE (fn) == FUNCTION_DECL && decl_is_tm_clone (fn))
848 pp_string (buffer, " [tm-clone]");
849 if (TREE_CODE (fn) == FUNCTION_DECL
850 && DECL_BUILT_IN_CLASS (fn) == BUILT_IN_NORMAL
851 && DECL_FUNCTION_CODE (fn) == BUILT_IN_TM_START
852 && gimple_call_num_args (gs) > 0)
853 {
854 tree t = gimple_call_arg (gs, 0);
855 unsigned HOST_WIDE_INT props;
856 gcc_assert (TREE_CODE (t) == INTEGER_CST);
857
858 pp_string (buffer, " [ ");
859
860 /* Get the transaction code properties. */
861 props = TREE_INT_CST_LOW (t);
862
863 if (props & PR_INSTRUMENTEDCODE)
864 pp_string (buffer, "instrumentedCode ");
865 if (props & PR_UNINSTRUMENTEDCODE)
866 pp_string (buffer, "uninstrumentedCode ");
867 if (props & PR_HASNOXMMUPDATE)
868 pp_string (buffer, "hasNoXMMUpdate ");
869 if (props & PR_HASNOABORT)
870 pp_string (buffer, "hasNoAbort ");
871 if (props & PR_HASNOIRREVOCABLE)
872 pp_string (buffer, "hasNoIrrevocable ");
873 if (props & PR_DOESGOIRREVOCABLE)
874 pp_string (buffer, "doesGoIrrevocable ");
875 if (props & PR_HASNOSIMPLEREADS)
876 pp_string (buffer, "hasNoSimpleReads ");
877 if (props & PR_AWBARRIERSOMITTED)
878 pp_string (buffer, "awBarriersOmitted ");
879 if (props & PR_RARBARRIERSOMITTED)
880 pp_string (buffer, "RaRBarriersOmitted ");
881 if (props & PR_UNDOLOGCODE)
882 pp_string (buffer, "undoLogCode ");
883 if (props & PR_PREFERUNINSTRUMENTED)
884 pp_string (buffer, "preferUninstrumented ");
885 if (props & PR_EXCEPTIONBLOCK)
886 pp_string (buffer, "exceptionBlock ");
887 if (props & PR_HASELSE)
888 pp_string (buffer, "hasElse ");
889 if (props & PR_READONLY)
890 pp_string (buffer, "readOnly ");
891
137a1a27 892 pp_right_bracket (buffer);
0a35513e 893 }
726a989a
RB
894}
895
896
897/* Dump the switch statement GS. BUFFER, SPC and FLAGS are as in
b5f47924 898 pp_gimple_stmt_1. */
726a989a
RB
899
900static void
538dd0b7
DM
901dump_gimple_switch (pretty_printer *buffer, gswitch *gs, int spc,
902 int flags)
726a989a
RB
903{
904 unsigned int i;
905
906 GIMPLE_CHECK (gs, GIMPLE_SWITCH);
907 if (flags & TDF_RAW)
908 dump_gimple_fmt (buffer, spc, flags, "%G <%T, ", gs,
909 gimple_switch_index (gs));
910 else
911 {
912 pp_string (buffer, "switch (");
913 dump_generic_node (buffer, gimple_switch_index (gs), spc, flags, true);
1ee62b92
PG
914 if (flags & TDF_GIMPLE)
915 pp_string (buffer, ") {");
916 else
917 pp_string (buffer, ") <");
726a989a
RB
918 }
919
920 for (i = 0; i < gimple_switch_num_labels (gs); i++)
921 {
922 tree case_label = gimple_switch_label (gs, i);
fd8d363e 923 gcc_checking_assert (case_label != NULL_TREE);
726a989a 924 dump_generic_node (buffer, case_label, spc, flags, false);
07838b13 925 pp_space (buffer);
0d56d3c1
ML
926 tree label = CASE_LABEL (case_label);
927 dump_generic_node (buffer, label, spc, flags, false);
928
929 if (cfun && cfun->cfg)
930 {
931 basic_block dest = label_to_block (label);
932 if (dest)
933 {
934 edge label_edge = find_edge (gimple_bb (gs), dest);
935 if (label_edge && !(flags & TDF_GIMPLE))
936 dump_edge_probability (buffer, label_edge);
937 }
938 }
939
726a989a 940 if (i < gimple_switch_num_labels (gs) - 1)
1ee62b92
PG
941 {
942 if (flags & TDF_GIMPLE)
943 pp_string (buffer, "; ");
944 else
945 pp_string (buffer, ", ");
946 }
726a989a 947 }
1ee62b92
PG
948 if (flags & TDF_GIMPLE)
949 pp_string (buffer, "; }");
950 else
951 pp_greater (buffer);
726a989a
RB
952}
953
954
955/* Dump the gimple conditional GS. BUFFER, SPC and FLAGS are as in
b5f47924 956 pp_gimple_stmt_1. */
726a989a
RB
957
958static void
538dd0b7 959dump_gimple_cond (pretty_printer *buffer, gcond *gs, int spc, int flags)
726a989a
RB
960{
961 if (flags & TDF_RAW)
962 dump_gimple_fmt (buffer, spc, flags, "%G <%s, %T, %T, %T, %T>", gs,
5806f481
PM
963 get_tree_code_name (gimple_cond_code (gs)),
964 gimple_cond_lhs (gs), gimple_cond_rhs (gs),
965 gimple_cond_true_label (gs), gimple_cond_false_label (gs));
726a989a
RB
966 else
967 {
968 if (!(flags & TDF_RHS_ONLY))
969 pp_string (buffer, "if (");
970 dump_generic_node (buffer, gimple_cond_lhs (gs), spc, flags, false);
971 pp_space (buffer);
972 pp_string (buffer, op_symbol_code (gimple_cond_code (gs)));
973 pp_space (buffer);
974 dump_generic_node (buffer, gimple_cond_rhs (gs), spc, flags, false);
975 if (!(flags & TDF_RHS_ONLY))
976 {
0d56d3c1
ML
977 edge_iterator ei;
978 edge e, true_edge = NULL, false_edge = NULL;
979 basic_block bb = gimple_bb (gs);
980
981 if (bb)
982 {
983 FOR_EACH_EDGE (e, ei, bb->succs)
984 {
985 if (e->flags & EDGE_TRUE_VALUE)
986 true_edge = e;
987 else if (e->flags & EDGE_FALSE_VALUE)
988 false_edge = e;
989 }
990 }
991
992 bool has_edge_info = true_edge != NULL && false_edge != NULL;
993
07838b13 994 pp_right_paren (buffer);
726a989a
RB
995
996 if (gimple_cond_true_label (gs))
997 {
998 pp_string (buffer, " goto ");
999 dump_generic_node (buffer, gimple_cond_true_label (gs),
1000 spc, flags, false);
0d56d3c1
ML
1001 if (has_edge_info && !(flags & TDF_GIMPLE))
1002 dump_edge_probability (buffer, true_edge);
726a989a
RB
1003 pp_semicolon (buffer);
1004 }
1005 if (gimple_cond_false_label (gs))
1006 {
1007 pp_string (buffer, " else goto ");
1008 dump_generic_node (buffer, gimple_cond_false_label (gs),
1009 spc, flags, false);
0d56d3c1
ML
1010 if (has_edge_info && !(flags & TDF_GIMPLE))
1011 dump_edge_probability (buffer, false_edge);
1012
726a989a
RB
1013 pp_semicolon (buffer);
1014 }
1015 }
1016 }
1017}
1018
1019
1020/* Dump a GIMPLE_LABEL tuple on the pretty_printer BUFFER, SPC
1021 spaces of indent. FLAGS specifies details to show in the dump (see
7ee2468b 1022 TDF_* in dumpfils.h). */
726a989a
RB
1023
1024static void
538dd0b7 1025dump_gimple_label (pretty_printer *buffer, glabel *gs, int spc, int flags)
726a989a
RB
1026{
1027 tree label = gimple_label_label (gs);
1028 if (flags & TDF_RAW)
1ee62b92 1029 dump_gimple_fmt (buffer, spc, flags, "%G <%T>", gs, label);
726a989a
RB
1030 else
1031 {
1032 dump_generic_node (buffer, label, spc, flags, false);
0d56d3c1
ML
1033 basic_block bb = gimple_bb (gs);
1034 if (bb && !(flags & TDF_GIMPLE))
1035 pp_scalar (buffer, " [%.1f%%]",
1036 bb->frequency * 100.0 / REG_BR_PROB_BASE);
07838b13 1037 pp_colon (buffer);
726a989a 1038 }
1ee62b92
PG
1039 if (flags & TDF_GIMPLE)
1040 return;
726a989a
RB
1041 if (DECL_NONLOCAL (label))
1042 pp_string (buffer, " [non-local]");
1d65f45c
RH
1043 if ((flags & TDF_EH) && EH_LANDING_PAD_NR (label))
1044 pp_printf (buffer, " [LP %d]", EH_LANDING_PAD_NR (label));
726a989a
RB
1045}
1046
1047/* Dump a GIMPLE_GOTO tuple on the pretty_printer BUFFER, SPC
1048 spaces of indent. FLAGS specifies details to show in the dump (see
7ee2468b 1049 TDF_* in dumpfile.h). */
726a989a
RB
1050
1051static void
538dd0b7 1052dump_gimple_goto (pretty_printer *buffer, ggoto *gs, int spc, int flags)
726a989a
RB
1053{
1054 tree label = gimple_goto_dest (gs);
1055 if (flags & TDF_RAW)
1056 dump_gimple_fmt (buffer, spc, flags, "%G <%T>", gs, label);
1057 else
1058 dump_gimple_fmt (buffer, spc, flags, "goto %T;", label);
1059}
1060
1061
1062/* Dump a GIMPLE_BIND tuple on the pretty_printer BUFFER, SPC
1063 spaces of indent. FLAGS specifies details to show in the dump (see
7ee2468b 1064 TDF_* in dumpfile.h). */
726a989a
RB
1065
1066static void
538dd0b7 1067dump_gimple_bind (pretty_printer *buffer, gbind *gs, int spc, int flags)
726a989a
RB
1068{
1069 if (flags & TDF_RAW)
1070 dump_gimple_fmt (buffer, spc, flags, "%G <", gs);
1071 else
07838b13 1072 pp_left_brace (buffer);
726a989a
RB
1073 if (!(flags & TDF_SLIM))
1074 {
1075 tree var;
1076
910ad8de 1077 for (var = gimple_bind_vars (gs); var; var = DECL_CHAIN (var))
726a989a
RB
1078 {
1079 newline_and_indent (buffer, 2);
1080 print_declaration (buffer, var, spc, flags);
1081 }
1082 if (gimple_bind_vars (gs))
1083 pp_newline (buffer);
1084 }
1085 pp_newline (buffer);
1086 dump_gimple_seq (buffer, gimple_bind_body (gs), spc + 2, flags);
1087 newline_and_indent (buffer, spc);
1088 if (flags & TDF_RAW)
07838b13 1089 pp_greater (buffer);
726a989a 1090 else
07838b13 1091 pp_right_brace (buffer);
726a989a
RB
1092}
1093
1094
1095/* Dump a GIMPLE_TRY tuple on the pretty_printer BUFFER, SPC spaces of
1096 indent. FLAGS specifies details to show in the dump (see TDF_* in
7ee2468b 1097 dumpfile.h). */
726a989a
RB
1098
1099static void
538dd0b7 1100dump_gimple_try (pretty_printer *buffer, gtry *gs, int spc, int flags)
726a989a
RB
1101{
1102 if (flags & TDF_RAW)
1103 {
1104 const char *type;
1105 if (gimple_try_kind (gs) == GIMPLE_TRY_CATCH)
1106 type = "GIMPLE_TRY_CATCH";
1107 else if (gimple_try_kind (gs) == GIMPLE_TRY_FINALLY)
1108 type = "GIMPLE_TRY_FINALLY";
1109 else
1110 type = "UNKNOWN GIMPLE_TRY";
1111 dump_gimple_fmt (buffer, spc, flags,
1112 "%G <%s,%+EVAL <%S>%nCLEANUP <%S>%->", gs, type,
1113 gimple_try_eval (gs), gimple_try_cleanup (gs));
1114 }
1115 else
1116 {
1117 pp_string (buffer, "try");
1118 newline_and_indent (buffer, spc + 2);
07838b13 1119 pp_left_brace (buffer);
726a989a
RB
1120 pp_newline (buffer);
1121
1122 dump_gimple_seq (buffer, gimple_try_eval (gs), spc + 4, flags);
1123 newline_and_indent (buffer, spc + 2);
07838b13 1124 pp_right_brace (buffer);
726a989a
RB
1125
1126 if (gimple_try_kind (gs) == GIMPLE_TRY_CATCH)
1127 {
1128 newline_and_indent (buffer, spc);
1129 pp_string (buffer, "catch");
1130 newline_and_indent (buffer, spc + 2);
07838b13 1131 pp_left_brace (buffer);
726a989a
RB
1132 }
1133 else if (gimple_try_kind (gs) == GIMPLE_TRY_FINALLY)
1134 {
1135 newline_and_indent (buffer, spc);
1136 pp_string (buffer, "finally");
1137 newline_and_indent (buffer, spc + 2);
07838b13 1138 pp_left_brace (buffer);
726a989a
RB
1139 }
1140 else
1141 pp_string (buffer, " <UNKNOWN GIMPLE_TRY> {");
1142
1143 pp_newline (buffer);
1144 dump_gimple_seq (buffer, gimple_try_cleanup (gs), spc + 4, flags);
1145 newline_and_indent (buffer, spc + 2);
07838b13 1146 pp_right_brace (buffer);
726a989a
RB
1147 }
1148}
1149
1150
1151/* Dump a GIMPLE_CATCH tuple on the pretty_printer BUFFER, SPC spaces of
1152 indent. FLAGS specifies details to show in the dump (see TDF_* in
7ee2468b 1153 dumpfile.h). */
726a989a
RB
1154
1155static void
538dd0b7 1156dump_gimple_catch (pretty_printer *buffer, gcatch *gs, int spc, int flags)
726a989a
RB
1157{
1158 if (flags & TDF_RAW)
1159 dump_gimple_fmt (buffer, spc, flags, "%G <%T, %+CATCH <%S>%->", gs,
1160 gimple_catch_types (gs), gimple_catch_handler (gs));
1161 else
1162 dump_gimple_fmt (buffer, spc, flags, "catch (%T)%+{%S}",
1163 gimple_catch_types (gs), gimple_catch_handler (gs));
1164}
1165
1166
1167/* Dump a GIMPLE_EH_FILTER tuple on the pretty_printer BUFFER, SPC spaces of
1168 indent. FLAGS specifies details to show in the dump (see TDF_* in
7ee2468b 1169 dumpfile.h). */
726a989a
RB
1170
1171static void
538dd0b7
DM
1172dump_gimple_eh_filter (pretty_printer *buffer, geh_filter *gs, int spc,
1173 int flags)
726a989a
RB
1174{
1175 if (flags & TDF_RAW)
1176 dump_gimple_fmt (buffer, spc, flags, "%G <%T, %+FAILURE <%S>%->", gs,
1177 gimple_eh_filter_types (gs),
1178 gimple_eh_filter_failure (gs));
1179 else
1180 dump_gimple_fmt (buffer, spc, flags, "<<<eh_filter (%T)>>>%+{%+%S%-}",
1181 gimple_eh_filter_types (gs),
1182 gimple_eh_filter_failure (gs));
1183}
1184
1185
1d65f45c
RH
1186/* Dump a GIMPLE_EH_MUST_NOT_THROW tuple. */
1187
1188static void
538dd0b7
DM
1189dump_gimple_eh_must_not_throw (pretty_printer *buffer,
1190 geh_mnt *gs, int spc, int flags)
1d65f45c
RH
1191{
1192 if (flags & TDF_RAW)
1193 dump_gimple_fmt (buffer, spc, flags, "%G <%T>", gs,
1194 gimple_eh_must_not_throw_fndecl (gs));
1195 else
1196 dump_gimple_fmt (buffer, spc, flags, "<<<eh_must_not_throw (%T)>>>",
1197 gimple_eh_must_not_throw_fndecl (gs));
1198}
1199
1200
0a35513e
AH
1201/* Dump a GIMPLE_EH_ELSE tuple on the pretty_printer BUFFER, SPC spaces of
1202 indent. FLAGS specifies details to show in the dump (see TDF_* in
7ee2468b 1203 dumpfile.h). */
0a35513e
AH
1204
1205static void
538dd0b7
DM
1206dump_gimple_eh_else (pretty_printer *buffer, geh_else *gs, int spc,
1207 int flags)
0a35513e
AH
1208{
1209 if (flags & TDF_RAW)
1210 dump_gimple_fmt (buffer, spc, flags,
1211 "%G <%+N_BODY <%S>%nE_BODY <%S>%->", gs,
1212 gimple_eh_else_n_body (gs), gimple_eh_else_e_body (gs));
1213 else
1214 dump_gimple_fmt (buffer, spc, flags,
1215 "<<<if_normal_exit>>>%+{%S}%-<<<else_eh_exit>>>%+{%S}",
1216 gimple_eh_else_n_body (gs), gimple_eh_else_e_body (gs));
1217}
1218
1219
726a989a
RB
1220/* Dump a GIMPLE_RESX tuple on the pretty_printer BUFFER, SPC spaces of
1221 indent. FLAGS specifies details to show in the dump (see TDF_* in
7ee2468b 1222 dumpfile.h). */
726a989a
RB
1223
1224static void
538dd0b7 1225dump_gimple_resx (pretty_printer *buffer, gresx *gs, int spc, int flags)
726a989a
RB
1226{
1227 if (flags & TDF_RAW)
1228 dump_gimple_fmt (buffer, spc, flags, "%G <%d>", gs,
1d65f45c 1229 gimple_resx_region (gs));
726a989a
RB
1230 else
1231 dump_gimple_fmt (buffer, spc, flags, "resx %d", gimple_resx_region (gs));
1232}
1233
1d65f45c
RH
1234/* Dump a GIMPLE_EH_DISPATCH tuple on the pretty_printer BUFFER. */
1235
1236static void
538dd0b7 1237dump_gimple_eh_dispatch (pretty_printer *buffer, geh_dispatch *gs, int spc, int flags)
1d65f45c
RH
1238{
1239 if (flags & TDF_RAW)
1240 dump_gimple_fmt (buffer, spc, flags, "%G <%d>", gs,
1241 gimple_eh_dispatch_region (gs));
1242 else
1243 dump_gimple_fmt (buffer, spc, flags, "eh_dispatch %d",
1244 gimple_eh_dispatch_region (gs));
1245}
1246
b5b8b0ac
AO
1247/* Dump a GIMPLE_DEBUG tuple on the pretty_printer BUFFER, SPC spaces
1248 of indent. FLAGS specifies details to show in the dump (see TDF_*
7ee2468b 1249 in dumpfile.h). */
b5b8b0ac
AO
1250
1251static void
538dd0b7 1252dump_gimple_debug (pretty_printer *buffer, gdebug *gs, int spc, int flags)
b5b8b0ac 1253{
daa6e488 1254 switch (gs->subcode)
b5b8b0ac
AO
1255 {
1256 case GIMPLE_DEBUG_BIND:
1257 if (flags & TDF_RAW)
1258 dump_gimple_fmt (buffer, spc, flags, "%G BIND <%T, %T>", gs,
1259 gimple_debug_bind_get_var (gs),
1260 gimple_debug_bind_get_value (gs));
1261 else
1262 dump_gimple_fmt (buffer, spc, flags, "# DEBUG %T => %T",
1263 gimple_debug_bind_get_var (gs),
1264 gimple_debug_bind_get_value (gs));
1265 break;
1266
ddb555ed
JJ
1267 case GIMPLE_DEBUG_SOURCE_BIND:
1268 if (flags & TDF_RAW)
1269 dump_gimple_fmt (buffer, spc, flags, "%G SRCBIND <%T, %T>", gs,
1270 gimple_debug_source_bind_get_var (gs),
1271 gimple_debug_source_bind_get_value (gs));
1272 else
1273 dump_gimple_fmt (buffer, spc, flags, "# DEBUG %T s=> %T",
1274 gimple_debug_source_bind_get_var (gs),
1275 gimple_debug_source_bind_get_value (gs));
1276 break;
1277
b5b8b0ac
AO
1278 default:
1279 gcc_unreachable ();
1280 }
1281}
1282
726a989a
RB
1283/* Dump a GIMPLE_OMP_FOR tuple on the pretty_printer BUFFER. */
1284static void
538dd0b7 1285dump_gimple_omp_for (pretty_printer *buffer, gomp_for *gs, int spc, int flags)
726a989a
RB
1286{
1287 size_t i;
1288
1289 if (flags & TDF_RAW)
1290 {
74bf76ed
JJ
1291 const char *kind;
1292 switch (gimple_omp_for_kind (gs))
1293 {
1294 case GF_OMP_FOR_KIND_FOR:
1295 kind = "";
1296 break;
acf0174b
JJ
1297 case GF_OMP_FOR_KIND_DISTRIBUTE:
1298 kind = " distribute";
1299 break;
d9a6bd32
JJ
1300 case GF_OMP_FOR_KIND_TASKLOOP:
1301 kind = " taskloop";
1302 break;
9a771876
JJ
1303 case GF_OMP_FOR_KIND_CILKFOR:
1304 kind = " _Cilk_for";
1305 break;
41dbbb37
TS
1306 case GF_OMP_FOR_KIND_OACC_LOOP:
1307 kind = " oacc_loop";
1308 break;
1309 case GF_OMP_FOR_KIND_SIMD:
1310 kind = " simd";
1311 break;
1312 case GF_OMP_FOR_KIND_CILKSIMD:
1313 kind = " cilksimd";
1314 break;
74bf76ed
JJ
1315 default:
1316 gcc_unreachable ();
1317 }
1318 dump_gimple_fmt (buffer, spc, flags, "%G%s <%+BODY <%S>%nCLAUSES <", gs,
1319 kind, gimple_omp_body (gs));
726a989a
RB
1320 dump_omp_clauses (buffer, gimple_omp_for_clauses (gs), spc, flags);
1321 dump_gimple_fmt (buffer, spc, flags, " >,");
1322 for (i = 0; i < gimple_omp_for_collapse (gs); i++)
1323 dump_gimple_fmt (buffer, spc, flags,
1324 "%+%T, %T, %T, %s, %T,%n",
1325 gimple_omp_for_index (gs, i),
1326 gimple_omp_for_initial (gs, i),
1327 gimple_omp_for_final (gs, i),
5806f481 1328 get_tree_code_name (gimple_omp_for_cond (gs, i)),
726a989a
RB
1329 gimple_omp_for_incr (gs, i));
1330 dump_gimple_fmt (buffer, spc, flags, "PRE_BODY <%S>%->",
1331 gimple_omp_for_pre_body (gs));
1332 }
1333 else
1334 {
74bf76ed
JJ
1335 switch (gimple_omp_for_kind (gs))
1336 {
1337 case GF_OMP_FOR_KIND_FOR:
1338 pp_string (buffer, "#pragma omp for");
1339 break;
41dbbb37
TS
1340 case GF_OMP_FOR_KIND_DISTRIBUTE:
1341 pp_string (buffer, "#pragma omp distribute");
1342 break;
d9a6bd32
JJ
1343 case GF_OMP_FOR_KIND_TASKLOOP:
1344 pp_string (buffer, "#pragma omp taskloop");
1345 break;
41dbbb37
TS
1346 case GF_OMP_FOR_KIND_CILKFOR:
1347 break;
1348 case GF_OMP_FOR_KIND_OACC_LOOP:
1349 pp_string (buffer, "#pragma acc loop");
1350 break;
74bf76ed
JJ
1351 case GF_OMP_FOR_KIND_SIMD:
1352 pp_string (buffer, "#pragma omp simd");
1353 break;
c02065fc
AH
1354 case GF_OMP_FOR_KIND_CILKSIMD:
1355 pp_string (buffer, "#pragma simd");
1356 break;
b2b40051
MJ
1357 case GF_OMP_FOR_KIND_GRID_LOOP:
1358 pp_string (buffer, "#pragma omp for grid_loop");
1359 break;
74bf76ed
JJ
1360 default:
1361 gcc_unreachable ();
1362 }
9a771876
JJ
1363 if (gimple_omp_for_kind (gs) != GF_OMP_FOR_KIND_CILKFOR)
1364 dump_omp_clauses (buffer, gimple_omp_for_clauses (gs), spc, flags);
726a989a
RB
1365 for (i = 0; i < gimple_omp_for_collapse (gs); i++)
1366 {
1367 if (i)
1368 spc += 2;
9a771876
JJ
1369 if (gimple_omp_for_kind (gs) == GF_OMP_FOR_KIND_CILKFOR)
1370 pp_string (buffer, "_Cilk_for (");
1371 else
1372 {
1373 newline_and_indent (buffer, spc);
1374 pp_string (buffer, "for (");
1375 }
726a989a
RB
1376 dump_generic_node (buffer, gimple_omp_for_index (gs, i), spc,
1377 flags, false);
1378 pp_string (buffer, " = ");
1379 dump_generic_node (buffer, gimple_omp_for_initial (gs, i), spc,
1380 flags, false);
1381 pp_string (buffer, "; ");
1382
1383 dump_generic_node (buffer, gimple_omp_for_index (gs, i), spc,
1384 flags, false);
1385 pp_space (buffer);
1386 switch (gimple_omp_for_cond (gs, i))
1387 {
1388 case LT_EXPR:
07838b13 1389 pp_less (buffer);
726a989a
RB
1390 break;
1391 case GT_EXPR:
07838b13 1392 pp_greater (buffer);
726a989a
RB
1393 break;
1394 case LE_EXPR:
137a1a27 1395 pp_less_equal (buffer);
726a989a
RB
1396 break;
1397 case GE_EXPR:
137a1a27 1398 pp_greater_equal (buffer);
726a989a 1399 break;
9a771876
JJ
1400 case NE_EXPR:
1401 pp_string (buffer, "!=");
1402 break;
726a989a
RB
1403 default:
1404 gcc_unreachable ();
1405 }
1406 pp_space (buffer);
1407 dump_generic_node (buffer, gimple_omp_for_final (gs, i), spc,
1408 flags, false);
1409 pp_string (buffer, "; ");
1410
1411 dump_generic_node (buffer, gimple_omp_for_index (gs, i), spc,
1412 flags, false);
1413 pp_string (buffer, " = ");
1414 dump_generic_node (buffer, gimple_omp_for_incr (gs, i), spc,
1415 flags, false);
07838b13 1416 pp_right_paren (buffer);
726a989a
RB
1417 }
1418
1419 if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1420 {
9a771876
JJ
1421 if (gimple_omp_for_kind (gs) == GF_OMP_FOR_KIND_CILKFOR)
1422 dump_omp_clauses (buffer, gimple_omp_for_clauses (gs), spc, flags);
726a989a 1423 newline_and_indent (buffer, spc + 2);
07838b13 1424 pp_left_brace (buffer);
726a989a
RB
1425 pp_newline (buffer);
1426 dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1427 newline_and_indent (buffer, spc + 2);
07838b13 1428 pp_right_brace (buffer);
726a989a
RB
1429 }
1430 }
1431}
1432
1433/* Dump a GIMPLE_OMP_CONTINUE tuple on the pretty_printer BUFFER. */
1434
1435static void
538dd0b7
DM
1436dump_gimple_omp_continue (pretty_printer *buffer, gomp_continue *gs,
1437 int spc, int flags)
726a989a
RB
1438{
1439 if (flags & TDF_RAW)
1440 {
1441 dump_gimple_fmt (buffer, spc, flags, "%G <%T, %T>", gs,
1442 gimple_omp_continue_control_def (gs),
1443 gimple_omp_continue_control_use (gs));
1444 }
1445 else
1446 {
1447 pp_string (buffer, "#pragma omp continue (");
1448 dump_generic_node (buffer, gimple_omp_continue_control_def (gs),
1449 spc, flags, false);
07838b13 1450 pp_comma (buffer);
726a989a
RB
1451 pp_space (buffer);
1452 dump_generic_node (buffer, gimple_omp_continue_control_use (gs),
1453 spc, flags, false);
07838b13 1454 pp_right_paren (buffer);
726a989a
RB
1455 }
1456}
1457
1458/* Dump a GIMPLE_OMP_SINGLE tuple on the pretty_printer BUFFER. */
1459
1460static void
538dd0b7
DM
1461dump_gimple_omp_single (pretty_printer *buffer, gomp_single *gs,
1462 int spc, int flags)
726a989a
RB
1463{
1464 if (flags & TDF_RAW)
1465 {
1466 dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S>%nCLAUSES <", gs,
1467 gimple_omp_body (gs));
1468 dump_omp_clauses (buffer, gimple_omp_single_clauses (gs), spc, flags);
1469 dump_gimple_fmt (buffer, spc, flags, " >");
1470 }
1471 else
1472 {
1473 pp_string (buffer, "#pragma omp single");
1474 dump_omp_clauses (buffer, gimple_omp_single_clauses (gs), spc, flags);
1475 if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1476 {
1477 newline_and_indent (buffer, spc + 2);
07838b13 1478 pp_left_brace (buffer);
726a989a
RB
1479 pp_newline (buffer);
1480 dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1481 newline_and_indent (buffer, spc + 2);
07838b13 1482 pp_right_brace (buffer);
726a989a
RB
1483 }
1484 }
1485}
1486
acf0174b
JJ
1487/* Dump a GIMPLE_OMP_TARGET tuple on the pretty_printer BUFFER. */
1488
1489static void
538dd0b7
DM
1490dump_gimple_omp_target (pretty_printer *buffer, gomp_target *gs,
1491 int spc, int flags)
acf0174b
JJ
1492{
1493 const char *kind;
1494 switch (gimple_omp_target_kind (gs))
1495 {
1496 case GF_OMP_TARGET_KIND_REGION:
1497 kind = "";
1498 break;
1499 case GF_OMP_TARGET_KIND_DATA:
1500 kind = " data";
1501 break;
1502 case GF_OMP_TARGET_KIND_UPDATE:
1503 kind = " update";
1504 break;
d9a6bd32
JJ
1505 case GF_OMP_TARGET_KIND_ENTER_DATA:
1506 kind = " enter data";
1507 break;
1508 case GF_OMP_TARGET_KIND_EXIT_DATA:
1509 kind = " exit data";
1510 break;
41dbbb37
TS
1511 case GF_OMP_TARGET_KIND_OACC_KERNELS:
1512 kind = " oacc_kernels";
1513 break;
1514 case GF_OMP_TARGET_KIND_OACC_PARALLEL:
1515 kind = " oacc_parallel";
1516 break;
1517 case GF_OMP_TARGET_KIND_OACC_DATA:
1518 kind = " oacc_data";
1519 break;
1520 case GF_OMP_TARGET_KIND_OACC_UPDATE:
1521 kind = " oacc_update";
1522 break;
1523 case GF_OMP_TARGET_KIND_OACC_ENTER_EXIT_DATA:
1524 kind = " oacc_enter_exit_data";
1525 break;
6e232ba4
JN
1526 case GF_OMP_TARGET_KIND_OACC_DECLARE:
1527 kind = " oacc_declare";
1528 break;
37d5ad46
JB
1529 case GF_OMP_TARGET_KIND_OACC_HOST_DATA:
1530 kind = " oacc_host_data";
1531 break;
acf0174b
JJ
1532 default:
1533 gcc_unreachable ();
1534 }
1535 if (flags & TDF_RAW)
1536 {
1537 dump_gimple_fmt (buffer, spc, flags, "%G%s <%+BODY <%S>%nCLAUSES <", gs,
1538 kind, gimple_omp_body (gs));
1539 dump_omp_clauses (buffer, gimple_omp_target_clauses (gs), spc, flags);
41dbbb37
TS
1540 dump_gimple_fmt (buffer, spc, flags, " >, %T, %T%n>",
1541 gimple_omp_target_child_fn (gs),
1542 gimple_omp_target_data_arg (gs));
acf0174b
JJ
1543 }
1544 else
1545 {
1546 pp_string (buffer, "#pragma omp target");
1547 pp_string (buffer, kind);
1548 dump_omp_clauses (buffer, gimple_omp_target_clauses (gs), spc, flags);
1549 if (gimple_omp_target_child_fn (gs))
1550 {
1551 pp_string (buffer, " [child fn: ");
1552 dump_generic_node (buffer, gimple_omp_target_child_fn (gs),
1553 spc, flags, false);
41dbbb37
TS
1554 pp_string (buffer, " (");
1555 if (gimple_omp_target_data_arg (gs))
1556 dump_generic_node (buffer, gimple_omp_target_data_arg (gs),
1557 spc, flags, false);
1558 else
1559 pp_string (buffer, "???");
1560 pp_string (buffer, ")]");
acf0174b 1561 }
41dbbb37
TS
1562 gimple_seq body = gimple_omp_body (gs);
1563 if (body && gimple_code (gimple_seq_first_stmt (body)) != GIMPLE_BIND)
acf0174b
JJ
1564 {
1565 newline_and_indent (buffer, spc + 2);
41dbbb37 1566 pp_left_brace (buffer);
acf0174b 1567 pp_newline (buffer);
41dbbb37 1568 dump_gimple_seq (buffer, body, spc + 4, flags);
acf0174b 1569 newline_and_indent (buffer, spc + 2);
41dbbb37
TS
1570 pp_right_brace (buffer);
1571 }
1572 else if (body)
1573 {
1574 pp_newline (buffer);
1575 dump_gimple_seq (buffer, body, spc + 2, flags);
acf0174b
JJ
1576 }
1577 }
1578}
1579
1580/* Dump a GIMPLE_OMP_TEAMS tuple on the pretty_printer BUFFER. */
1581
1582static void
538dd0b7
DM
1583dump_gimple_omp_teams (pretty_printer *buffer, gomp_teams *gs, int spc,
1584 int flags)
acf0174b
JJ
1585{
1586 if (flags & TDF_RAW)
1587 {
1588 dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S>%nCLAUSES <", gs,
1589 gimple_omp_body (gs));
1590 dump_omp_clauses (buffer, gimple_omp_teams_clauses (gs), spc, flags);
1591 dump_gimple_fmt (buffer, spc, flags, " >");
1592 }
1593 else
1594 {
1595 pp_string (buffer, "#pragma omp teams");
1596 dump_omp_clauses (buffer, gimple_omp_teams_clauses (gs), spc, flags);
1597 if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1598 {
1599 newline_and_indent (buffer, spc + 2);
1600 pp_character (buffer, '{');
1601 pp_newline (buffer);
1602 dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1603 newline_and_indent (buffer, spc + 2);
1604 pp_character (buffer, '}');
1605 }
1606 }
1607}
1608
726a989a
RB
1609/* Dump a GIMPLE_OMP_SECTIONS tuple on the pretty_printer BUFFER. */
1610
1611static void
538dd0b7
DM
1612dump_gimple_omp_sections (pretty_printer *buffer, gomp_sections *gs,
1613 int spc, int flags)
726a989a
RB
1614{
1615 if (flags & TDF_RAW)
1616 {
1617 dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S>%nCLAUSES <", gs,
1618 gimple_omp_body (gs));
1619 dump_omp_clauses (buffer, gimple_omp_sections_clauses (gs), spc, flags);
1620 dump_gimple_fmt (buffer, spc, flags, " >");
1621 }
1622 else
1623 {
1624 pp_string (buffer, "#pragma omp sections");
1625 if (gimple_omp_sections_control (gs))
1626 {
1627 pp_string (buffer, " <");
1628 dump_generic_node (buffer, gimple_omp_sections_control (gs), spc,
1629 flags, false);
07838b13 1630 pp_greater (buffer);
726a989a
RB
1631 }
1632 dump_omp_clauses (buffer, gimple_omp_sections_clauses (gs), spc, flags);
1633 if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1634 {
1635 newline_and_indent (buffer, spc + 2);
07838b13 1636 pp_left_brace (buffer);
726a989a
RB
1637 pp_newline (buffer);
1638 dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1639 newline_and_indent (buffer, spc + 2);
07838b13 1640 pp_right_brace (buffer);
726a989a
RB
1641 }
1642 }
1643}
1644
acf0174b
JJ
1645/* Dump a GIMPLE_OMP_{MASTER,TASKGROUP,ORDERED,SECTION} tuple on the
1646 pretty_printer BUFFER. */
726a989a
RB
1647
1648static void
355fe088 1649dump_gimple_omp_block (pretty_printer *buffer, gimple *gs, int spc, int flags)
726a989a
RB
1650{
1651 if (flags & TDF_RAW)
1652 dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S> >", gs,
1653 gimple_omp_body (gs));
1654 else
1655 {
1656 switch (gimple_code (gs))
1657 {
1658 case GIMPLE_OMP_MASTER:
1659 pp_string (buffer, "#pragma omp master");
1660 break;
acf0174b
JJ
1661 case GIMPLE_OMP_TASKGROUP:
1662 pp_string (buffer, "#pragma omp taskgroup");
1663 break;
726a989a
RB
1664 case GIMPLE_OMP_SECTION:
1665 pp_string (buffer, "#pragma omp section");
1666 break;
b2b40051
MJ
1667 case GIMPLE_OMP_GRID_BODY:
1668 pp_string (buffer, "#pragma omp gridified body");
1669 break;
726a989a
RB
1670 default:
1671 gcc_unreachable ();
1672 }
1673 if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1674 {
1675 newline_and_indent (buffer, spc + 2);
07838b13 1676 pp_left_brace (buffer);
726a989a
RB
1677 pp_newline (buffer);
1678 dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1679 newline_and_indent (buffer, spc + 2);
07838b13 1680 pp_right_brace (buffer);
726a989a
RB
1681 }
1682 }
1683}
1684
1685/* Dump a GIMPLE_OMP_CRITICAL tuple on the pretty_printer BUFFER. */
1686
1687static void
538dd0b7
DM
1688dump_gimple_omp_critical (pretty_printer *buffer, gomp_critical *gs,
1689 int spc, int flags)
726a989a
RB
1690{
1691 if (flags & TDF_RAW)
1692 dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S> >", gs,
1693 gimple_omp_body (gs));
1694 else
1695 {
1696 pp_string (buffer, "#pragma omp critical");
1697 if (gimple_omp_critical_name (gs))
1698 {
1699 pp_string (buffer, " (");
1700 dump_generic_node (buffer, gimple_omp_critical_name (gs), spc,
1701 flags, false);
07838b13 1702 pp_right_paren (buffer);
726a989a 1703 }
d9a6bd32
JJ
1704 dump_omp_clauses (buffer, gimple_omp_critical_clauses (gs), spc, flags);
1705 if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1706 {
1707 newline_and_indent (buffer, spc + 2);
1708 pp_left_brace (buffer);
1709 pp_newline (buffer);
1710 dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1711 newline_and_indent (buffer, spc + 2);
1712 pp_right_brace (buffer);
1713 }
1714 }
1715}
1716
1717/* Dump a GIMPLE_OMP_ORDERED tuple on the pretty_printer BUFFER. */
1718
1719static void
1720dump_gimple_omp_ordered (pretty_printer *buffer, gomp_ordered *gs,
1721 int spc, int flags)
1722{
1723 if (flags & TDF_RAW)
1724 dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S> >", gs,
1725 gimple_omp_body (gs));
1726 else
1727 {
1728 pp_string (buffer, "#pragma omp ordered");
1729 dump_omp_clauses (buffer, gimple_omp_ordered_clauses (gs), spc, flags);
726a989a
RB
1730 if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1731 {
1732 newline_and_indent (buffer, spc + 2);
07838b13 1733 pp_left_brace (buffer);
726a989a
RB
1734 pp_newline (buffer);
1735 dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1736 newline_and_indent (buffer, spc + 2);
07838b13 1737 pp_right_brace (buffer);
726a989a
RB
1738 }
1739 }
1740}
1741
1742/* Dump a GIMPLE_OMP_RETURN tuple on the pretty_printer BUFFER. */
1743
1744static void
355fe088 1745dump_gimple_omp_return (pretty_printer *buffer, gimple *gs, int spc, int flags)
726a989a
RB
1746{
1747 if (flags & TDF_RAW)
1748 {
acf0174b 1749 dump_gimple_fmt (buffer, spc, flags, "%G <nowait=%d", gs,
726a989a 1750 (int) gimple_omp_return_nowait_p (gs));
acf0174b
JJ
1751 if (gimple_omp_return_lhs (gs))
1752 dump_gimple_fmt (buffer, spc, flags, ", lhs=%T>",
1753 gimple_omp_return_lhs (gs));
1754 else
1755 dump_gimple_fmt (buffer, spc, flags, ">");
726a989a
RB
1756 }
1757 else
1758 {
1759 pp_string (buffer, "#pragma omp return");
1760 if (gimple_omp_return_nowait_p (gs))
1761 pp_string (buffer, "(nowait)");
acf0174b
JJ
1762 if (gimple_omp_return_lhs (gs))
1763 {
1764 pp_string (buffer, " (set ");
1765 dump_generic_node (buffer, gimple_omp_return_lhs (gs),
1766 spc, flags, false);
1767 pp_character (buffer, ')');
1768 }
726a989a
RB
1769 }
1770}
1771
0a35513e
AH
1772/* Dump a GIMPLE_TRANSACTION tuple on the pretty_printer BUFFER. */
1773
1774static void
538dd0b7
DM
1775dump_gimple_transaction (pretty_printer *buffer, gtransaction *gs,
1776 int spc, int flags)
0a35513e
AH
1777{
1778 unsigned subcode = gimple_transaction_subcode (gs);
1779
1780 if (flags & TDF_RAW)
1781 {
1782 dump_gimple_fmt (buffer, spc, flags,
7c11b0fe
RH
1783 "%G [SUBCODE=%x,NORM=%T,UNINST=%T,OVER=%T] "
1784 "<%+BODY <%S> >",
1785 gs, subcode, gimple_transaction_label_norm (gs),
1786 gimple_transaction_label_uninst (gs),
1787 gimple_transaction_label_over (gs),
0a35513e
AH
1788 gimple_transaction_body (gs));
1789 }
1790 else
1791 {
1792 if (subcode & GTMA_IS_OUTER)
1793 pp_string (buffer, "__transaction_atomic [[outer]]");
1794 else if (subcode & GTMA_IS_RELAXED)
1795 pp_string (buffer, "__transaction_relaxed");
1796 else
1797 pp_string (buffer, "__transaction_atomic");
1798 subcode &= ~GTMA_DECLARATION_MASK;
1799
7c11b0fe
RH
1800 if (gimple_transaction_body (gs))
1801 {
1802 newline_and_indent (buffer, spc + 2);
1803 pp_left_brace (buffer);
1804 pp_newline (buffer);
1805 dump_gimple_seq (buffer, gimple_transaction_body (gs),
1806 spc + 4, flags);
1807 newline_and_indent (buffer, spc + 2);
1808 pp_right_brace (buffer);
1809 }
1810 else
0a35513e
AH
1811 {
1812 pp_string (buffer, " //");
7c11b0fe
RH
1813 if (gimple_transaction_label_norm (gs))
1814 {
1815 pp_string (buffer, " NORM=");
1816 dump_generic_node (buffer, gimple_transaction_label_norm (gs),
1817 spc, flags, false);
1818 }
1819 if (gimple_transaction_label_uninst (gs))
0a35513e 1820 {
7c11b0fe
RH
1821 pp_string (buffer, " UNINST=");
1822 dump_generic_node (buffer, gimple_transaction_label_uninst (gs),
1823 spc, flags, false);
1824 }
1825 if (gimple_transaction_label_over (gs))
1826 {
1827 pp_string (buffer, " OVER=");
1828 dump_generic_node (buffer, gimple_transaction_label_over (gs),
0a35513e
AH
1829 spc, flags, false);
1830 }
1831 if (subcode)
1832 {
1833 pp_string (buffer, " SUBCODE=[ ");
1834 if (subcode & GTMA_HAVE_ABORT)
1835 {
1836 pp_string (buffer, "GTMA_HAVE_ABORT ");
1837 subcode &= ~GTMA_HAVE_ABORT;
1838 }
1839 if (subcode & GTMA_HAVE_LOAD)
1840 {
1841 pp_string (buffer, "GTMA_HAVE_LOAD ");
1842 subcode &= ~GTMA_HAVE_LOAD;
1843 }
1844 if (subcode & GTMA_HAVE_STORE)
1845 {
1846 pp_string (buffer, "GTMA_HAVE_STORE ");
1847 subcode &= ~GTMA_HAVE_STORE;
1848 }
1849 if (subcode & GTMA_MAY_ENTER_IRREVOCABLE)
1850 {
1851 pp_string (buffer, "GTMA_MAY_ENTER_IRREVOCABLE ");
1852 subcode &= ~GTMA_MAY_ENTER_IRREVOCABLE;
1853 }
1854 if (subcode & GTMA_DOES_GO_IRREVOCABLE)
1855 {
1856 pp_string (buffer, "GTMA_DOES_GO_IRREVOCABLE ");
1857 subcode &= ~GTMA_DOES_GO_IRREVOCABLE;
1858 }
b7a78683
AH
1859 if (subcode & GTMA_HAS_NO_INSTRUMENTATION)
1860 {
1861 pp_string (buffer, "GTMA_HAS_NO_INSTRUMENTATION ");
1862 subcode &= ~GTMA_HAS_NO_INSTRUMENTATION;
1863 }
0a35513e
AH
1864 if (subcode)
1865 pp_printf (buffer, "0x%x ", subcode);
137a1a27 1866 pp_right_bracket (buffer);
0a35513e
AH
1867 }
1868 }
0a35513e
AH
1869 }
1870}
1871
726a989a
RB
1872/* Dump a GIMPLE_ASM tuple on the pretty_printer BUFFER, SPC spaces of
1873 indent. FLAGS specifies details to show in the dump (see TDF_* in
7ee2468b 1874 dumpfile.h). */
726a989a
RB
1875
1876static void
538dd0b7 1877dump_gimple_asm (pretty_printer *buffer, gasm *gs, int spc, int flags)
726a989a 1878{
1c384bf1 1879 unsigned int i, n, f, fields;
726a989a
RB
1880
1881 if (flags & TDF_RAW)
1c384bf1
RH
1882 {
1883 dump_gimple_fmt (buffer, spc, flags, "%G <%+STRING <%n%s%n>", gs,
1884 gimple_asm_string (gs));
1885
1886 n = gimple_asm_noutputs (gs);
1887 if (n)
1888 {
1889 newline_and_indent (buffer, spc + 2);
1890 pp_string (buffer, "OUTPUT: ");
1891 for (i = 0; i < n; i++)
1892 {
1893 dump_generic_node (buffer, gimple_asm_output_op (gs, i),
1894 spc, flags, false);
1895 if (i < n - 1)
1896 pp_string (buffer, ", ");
1897 }
1898 }
1899
1900 n = gimple_asm_ninputs (gs);
1901 if (n)
1902 {
1903 newline_and_indent (buffer, spc + 2);
1904 pp_string (buffer, "INPUT: ");
1905 for (i = 0; i < n; i++)
1906 {
1907 dump_generic_node (buffer, gimple_asm_input_op (gs, i),
1908 spc, flags, false);
1909 if (i < n - 1)
1910 pp_string (buffer, ", ");
1911 }
1912 }
1913
1914 n = gimple_asm_nclobbers (gs);
1915 if (n)
1916 {
1917 newline_and_indent (buffer, spc + 2);
1918 pp_string (buffer, "CLOBBER: ");
1919 for (i = 0; i < n; i++)
1920 {
1921 dump_generic_node (buffer, gimple_asm_clobber_op (gs, i),
1922 spc, flags, false);
1923 if (i < n - 1)
1924 pp_string (buffer, ", ");
1925 }
1926 }
1927
1928 n = gimple_asm_nlabels (gs);
1929 if (n)
1930 {
1931 newline_and_indent (buffer, spc + 2);
1932 pp_string (buffer, "LABEL: ");
1933 for (i = 0; i < n; i++)
1934 {
1935 dump_generic_node (buffer, gimple_asm_label_op (gs, i),
1936 spc, flags, false);
1937 if (i < n - 1)
1938 pp_string (buffer, ", ");
1939 }
1940 }
1941
1942 newline_and_indent (buffer, spc);
07838b13 1943 pp_greater (buffer);
1c384bf1 1944 }
726a989a
RB
1945 else
1946 {
1947 pp_string (buffer, "__asm__");
1948 if (gimple_asm_volatile_p (gs))
1949 pp_string (buffer, " __volatile__");
1c384bf1
RH
1950 if (gimple_asm_nlabels (gs))
1951 pp_string (buffer, " goto");
726a989a
RB
1952 pp_string (buffer, "(\"");
1953 pp_string (buffer, gimple_asm_string (gs));
1954 pp_string (buffer, "\"");
726a989a 1955
1c384bf1
RH
1956 if (gimple_asm_nlabels (gs))
1957 fields = 4;
1958 else if (gimple_asm_nclobbers (gs))
1959 fields = 3;
1960 else if (gimple_asm_ninputs (gs))
1961 fields = 2;
1962 else if (gimple_asm_noutputs (gs))
1963 fields = 1;
1964 else
1965 fields = 0;
726a989a 1966
1c384bf1
RH
1967 for (f = 0; f < fields; ++f)
1968 {
1969 pp_string (buffer, " : ");
726a989a 1970
1c384bf1
RH
1971 switch (f)
1972 {
1973 case 0:
1974 n = gimple_asm_noutputs (gs);
1975 for (i = 0; i < n; i++)
1976 {
1977 dump_generic_node (buffer, gimple_asm_output_op (gs, i),
1978 spc, flags, false);
1979 if (i < n - 1)
1980 pp_string (buffer, ", ");
1981 }
1982 break;
726a989a 1983
1c384bf1
RH
1984 case 1:
1985 n = gimple_asm_ninputs (gs);
1986 for (i = 0; i < n; i++)
1987 {
1988 dump_generic_node (buffer, gimple_asm_input_op (gs, i),
1989 spc, flags, false);
1990 if (i < n - 1)
1991 pp_string (buffer, ", ");
1992 }
1993 break;
726a989a 1994
1c384bf1
RH
1995 case 2:
1996 n = gimple_asm_nclobbers (gs);
1997 for (i = 0; i < n; i++)
1998 {
1999 dump_generic_node (buffer, gimple_asm_clobber_op (gs, i),
2000 spc, flags, false);
2001 if (i < n - 1)
2002 pp_string (buffer, ", ");
2003 }
2004 break;
726a989a 2005
1c384bf1
RH
2006 case 3:
2007 n = gimple_asm_nlabels (gs);
2008 for (i = 0; i < n; i++)
2009 {
2010 dump_generic_node (buffer, gimple_asm_label_op (gs, i),
2011 spc, flags, false);
2012 if (i < n - 1)
2013 pp_string (buffer, ", ");
2014 }
2015 break;
2016
2017 default:
2018 gcc_unreachable ();
2019 }
2020 }
2021
2022 pp_string (buffer, ");");
726a989a 2023 }
726a989a
RB
2024}
2025
a895a2b8
KV
2026/* Dump ptr_info and range_info for NODE on pretty_printer BUFFER with
2027 SPC spaces of indent. */
726a989a
RB
2028
2029static void
a895a2b8 2030dump_ssaname_info (pretty_printer *buffer, tree node, int spc)
726a989a 2031{
a895a2b8
KV
2032 if (TREE_CODE (node) != SSA_NAME)
2033 return;
f0107145 2034
a895a2b8
KV
2035 if (POINTER_TYPE_P (TREE_TYPE (node))
2036 && SSA_NAME_PTR_INFO (node))
f0107145 2037 {
644ffefd 2038 unsigned int align, misalign;
a895a2b8 2039 struct ptr_info_def *pi = SSA_NAME_PTR_INFO (node);
d09c0e9b 2040 pp_string (buffer, "# PT = ");
1be38ccb
RG
2041 pp_points_to_solution (buffer, &pi->pt);
2042 newline_and_indent (buffer, spc);
644ffefd 2043 if (get_ptr_info_alignment (pi, &align, &misalign))
b1edf2bc 2044 {
644ffefd 2045 pp_printf (buffer, "# ALIGN = %u, MISALIGN = %u", align, misalign);
b1edf2bc
RG
2046 newline_and_indent (buffer, spc);
2047 }
f0107145 2048 }
726a989a 2049
a895a2b8
KV
2050 if (!POINTER_TYPE_P (TREE_TYPE (node))
2051 && SSA_NAME_RANGE_INFO (node))
2052 {
807e902e 2053 wide_int min, max, nonzero_bits;
a895a2b8
KV
2054 value_range_type range_type = get_range_info (node, &min, &max);
2055
2056 if (range_type == VR_VARYING)
d09c0e9b 2057 pp_printf (buffer, "# RANGE VR_VARYING");
a895a2b8 2058 else if (range_type == VR_RANGE || range_type == VR_ANTI_RANGE)
0498471b
CL
2059 {
2060 pp_printf (buffer, "# RANGE ");
2061 pp_printf (buffer, "%s[", range_type == VR_RANGE ? "" : "~");
807e902e 2062 pp_wide_int (buffer, min, TYPE_SIGN (TREE_TYPE (node)));
0498471b 2063 pp_printf (buffer, ", ");
807e902e 2064 pp_wide_int (buffer, max, TYPE_SIGN (TREE_TYPE (node)));
0498471b 2065 pp_printf (buffer, "]");
0498471b 2066 }
c853f62a 2067 nonzero_bits = get_nonzero_bits (node);
807e902e 2068 if (nonzero_bits != -1)
c853f62a
JJ
2069 {
2070 pp_string (buffer, " NONZERO ");
807e902e 2071 pp_wide_int (buffer, nonzero_bits, UNSIGNED);
c853f62a
JJ
2072 }
2073 newline_and_indent (buffer, spc);
a895a2b8
KV
2074 }
2075}
2076
0482b001
TV
2077/* As dump_ssaname_info, but dump to FILE. */
2078
2079void
2080dump_ssaname_info_to_file (FILE *file, tree node, int spc)
2081{
2082 pretty_printer buffer;
2083 pp_needs_newline (&buffer) = true;
2084 buffer.buffer->stream = file;
2085 dump_ssaname_info (&buffer, node, spc);
2086 pp_flush (&buffer);
2087}
a895a2b8
KV
2088
2089/* Dump a PHI node PHI. BUFFER, SPC and FLAGS are as in pp_gimple_stmt_1.
2090 The caller is responsible for calling pp_flush on BUFFER to finalize
d09c0e9b 2091 pretty printer. If COMMENT is true, print this after #. */
a895a2b8
KV
2092
2093static void
538dd0b7 2094dump_gimple_phi (pretty_printer *buffer, gphi *phi, int spc, bool comment,
d09c0e9b 2095 int flags)
a895a2b8
KV
2096{
2097 size_t i;
2098 tree lhs = gimple_phi_result (phi);
2099
2100 if (flags & TDF_ALIAS)
2101 dump_ssaname_info (buffer, lhs, spc);
2102
d09c0e9b
JJ
2103 if (comment)
2104 pp_string (buffer, "# ");
2105
726a989a 2106 if (flags & TDF_RAW)
0498471b
CL
2107 dump_gimple_fmt (buffer, spc, flags, "%G <%T, ", phi,
2108 gimple_phi_result (phi));
726a989a
RB
2109 else
2110 {
f0107145 2111 dump_generic_node (buffer, lhs, spc, flags, false);
1ee62b92
PG
2112 if (flags & TDF_GIMPLE)
2113 pp_string (buffer, " = __PHI (");
2114 else
2115 pp_string (buffer, " = PHI <");
726a989a
RB
2116 }
2117 for (i = 0; i < gimple_phi_num_args (phi); i++)
2118 {
f5045c96 2119 if ((flags & TDF_LINENO) && gimple_phi_arg_has_location (phi, i))
bb42836b 2120 dump_location (buffer, gimple_phi_arg_location (phi, i));
1ee62b92
PG
2121 if (flags & TDF_GIMPLE)
2122 {
2123 basic_block src = gimple_phi_arg_edge (phi, i)->src;
2124 gimple *stmt = first_stmt (src);
2125 if (!stmt || gimple_code (stmt) != GIMPLE_LABEL)
2126 {
2127 pp_string (buffer, "bb_");
2128 pp_decimal_int (buffer, src->index);
2129 }
2130 else
2131 dump_generic_node (buffer, gimple_label_label (as_a <glabel *> (stmt)), 0, flags,
2132 false);
2133 pp_string (buffer, ": ");
2134 }
726a989a
RB
2135 dump_generic_node (buffer, gimple_phi_arg_def (phi, i), spc, flags,
2136 false);
1ee62b92
PG
2137 if (! (flags & TDF_GIMPLE))
2138 {
2139 pp_left_paren (buffer);
2140 pp_decimal_int (buffer, gimple_phi_arg_edge (phi, i)->src->index);
2141 pp_right_paren (buffer);
2142 }
726a989a
RB
2143 if (i < gimple_phi_num_args (phi) - 1)
2144 pp_string (buffer, ", ");
2145 }
1ee62b92
PG
2146 if (flags & TDF_GIMPLE)
2147 pp_string (buffer, ");");
2148 else
2149 pp_greater (buffer);
726a989a
RB
2150}
2151
2152
2153/* Dump a GIMPLE_OMP_PARALLEL tuple on the pretty_printer BUFFER, SPC spaces
2154 of indent. FLAGS specifies details to show in the dump (see TDF_* in
7ee2468b 2155 dumpfile.h). */
726a989a
RB
2156
2157static void
538dd0b7
DM
2158dump_gimple_omp_parallel (pretty_printer *buffer, gomp_parallel *gs,
2159 int spc, int flags)
726a989a
RB
2160{
2161 if (flags & TDF_RAW)
2162 {
2163 dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S>%nCLAUSES <", gs,
2164 gimple_omp_body (gs));
2165 dump_omp_clauses (buffer, gimple_omp_parallel_clauses (gs), spc, flags);
2166 dump_gimple_fmt (buffer, spc, flags, " >, %T, %T%n>",
2167 gimple_omp_parallel_child_fn (gs),
2168 gimple_omp_parallel_data_arg (gs));
2169 }
2170 else
2171 {
2172 gimple_seq body;
2173 pp_string (buffer, "#pragma omp parallel");
2174 dump_omp_clauses (buffer, gimple_omp_parallel_clauses (gs), spc, flags);
2175 if (gimple_omp_parallel_child_fn (gs))
2176 {
2177 pp_string (buffer, " [child fn: ");
2178 dump_generic_node (buffer, gimple_omp_parallel_child_fn (gs),
2179 spc, flags, false);
2180 pp_string (buffer, " (");
2181 if (gimple_omp_parallel_data_arg (gs))
2182 dump_generic_node (buffer, gimple_omp_parallel_data_arg (gs),
2183 spc, flags, false);
2184 else
2185 pp_string (buffer, "???");
2186 pp_string (buffer, ")]");
2187 }
2188 body = gimple_omp_body (gs);
2189 if (body && gimple_code (gimple_seq_first_stmt (body)) != GIMPLE_BIND)
2190 {
2191 newline_and_indent (buffer, spc + 2);
07838b13 2192 pp_left_brace (buffer);
726a989a
RB
2193 pp_newline (buffer);
2194 dump_gimple_seq (buffer, body, spc + 4, flags);
2195 newline_and_indent (buffer, spc + 2);
07838b13 2196 pp_right_brace (buffer);
726a989a
RB
2197 }
2198 else if (body)
2199 {
2200 pp_newline (buffer);
2201 dump_gimple_seq (buffer, body, spc + 2, flags);
2202 }
2203 }
2204}
2205
2206
2207/* Dump a GIMPLE_OMP_TASK tuple on the pretty_printer BUFFER, SPC spaces
2208 of indent. FLAGS specifies details to show in the dump (see TDF_* in
7ee2468b 2209 dumpfile.h). */
726a989a
RB
2210
2211static void
538dd0b7 2212dump_gimple_omp_task (pretty_printer *buffer, gomp_task *gs, int spc,
726a989a
RB
2213 int flags)
2214{
2215 if (flags & TDF_RAW)
2216 {
2217 dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S>%nCLAUSES <", gs,
2218 gimple_omp_body (gs));
2219 dump_omp_clauses (buffer, gimple_omp_task_clauses (gs), spc, flags);
2220 dump_gimple_fmt (buffer, spc, flags, " >, %T, %T, %T, %T, %T%n>",
2221 gimple_omp_task_child_fn (gs),
2222 gimple_omp_task_data_arg (gs),
2223 gimple_omp_task_copy_fn (gs),
2224 gimple_omp_task_arg_size (gs),
2225 gimple_omp_task_arg_size (gs));
2226 }
2227 else
2228 {
2229 gimple_seq body;
d9a6bd32
JJ
2230 if (gimple_omp_task_taskloop_p (gs))
2231 pp_string (buffer, "#pragma omp taskloop");
2232 else
2233 pp_string (buffer, "#pragma omp task");
726a989a
RB
2234 dump_omp_clauses (buffer, gimple_omp_task_clauses (gs), spc, flags);
2235 if (gimple_omp_task_child_fn (gs))
2236 {
2237 pp_string (buffer, " [child fn: ");
2238 dump_generic_node (buffer, gimple_omp_task_child_fn (gs),
2239 spc, flags, false);
2240 pp_string (buffer, " (");
2241 if (gimple_omp_task_data_arg (gs))
2242 dump_generic_node (buffer, gimple_omp_task_data_arg (gs),
2243 spc, flags, false);
2244 else
2245 pp_string (buffer, "???");
2246 pp_string (buffer, ")]");
2247 }
2248 body = gimple_omp_body (gs);
2249 if (body && gimple_code (gimple_seq_first_stmt (body)) != GIMPLE_BIND)
2250 {
2251 newline_and_indent (buffer, spc + 2);
07838b13 2252 pp_left_brace (buffer);
726a989a
RB
2253 pp_newline (buffer);
2254 dump_gimple_seq (buffer, body, spc + 4, flags);
2255 newline_and_indent (buffer, spc + 2);
07838b13 2256 pp_right_brace (buffer);
726a989a
RB
2257 }
2258 else if (body)
2259 {
2260 pp_newline (buffer);
2261 dump_gimple_seq (buffer, body, spc + 2, flags);
2262 }
2263 }
2264}
2265
2266
2267/* Dump a GIMPLE_OMP_ATOMIC_LOAD tuple on the pretty_printer BUFFER, SPC
2268 spaces of indent. FLAGS specifies details to show in the dump (see TDF_*
7ee2468b 2269 in dumpfile.h). */
726a989a
RB
2270
2271static void
538dd0b7
DM
2272dump_gimple_omp_atomic_load (pretty_printer *buffer, gomp_atomic_load *gs,
2273 int spc, int flags)
726a989a
RB
2274{
2275 if (flags & TDF_RAW)
2276 {
2277 dump_gimple_fmt (buffer, spc, flags, "%G <%T, %T>", gs,
2278 gimple_omp_atomic_load_lhs (gs),
2279 gimple_omp_atomic_load_rhs (gs));
2280 }
2281 else
2282 {
2283 pp_string (buffer, "#pragma omp atomic_load");
acf0174b
JJ
2284 if (gimple_omp_atomic_seq_cst_p (gs))
2285 pp_string (buffer, " seq_cst");
05409788
RH
2286 if (gimple_omp_atomic_need_value_p (gs))
2287 pp_string (buffer, " [needed]");
726a989a
RB
2288 newline_and_indent (buffer, spc + 2);
2289 dump_generic_node (buffer, gimple_omp_atomic_load_lhs (gs),
2290 spc, flags, false);
2291 pp_space (buffer);
07838b13 2292 pp_equal (buffer);
726a989a 2293 pp_space (buffer);
07838b13 2294 pp_star (buffer);
726a989a
RB
2295 dump_generic_node (buffer, gimple_omp_atomic_load_rhs (gs),
2296 spc, flags, false);
2297 }
2298}
2299
2300/* Dump a GIMPLE_OMP_ATOMIC_STORE tuple on the pretty_printer BUFFER, SPC
2301 spaces of indent. FLAGS specifies details to show in the dump (see TDF_*
7ee2468b 2302 in dumpfile.h). */
726a989a
RB
2303
2304static void
538dd0b7
DM
2305dump_gimple_omp_atomic_store (pretty_printer *buffer,
2306 gomp_atomic_store *gs, int spc, int flags)
726a989a
RB
2307{
2308 if (flags & TDF_RAW)
2309 {
2310 dump_gimple_fmt (buffer, spc, flags, "%G <%T>", gs,
2311 gimple_omp_atomic_store_val (gs));
2312 }
2313 else
2314 {
05409788 2315 pp_string (buffer, "#pragma omp atomic_store ");
acf0174b
JJ
2316 if (gimple_omp_atomic_seq_cst_p (gs))
2317 pp_string (buffer, "seq_cst ");
05409788
RH
2318 if (gimple_omp_atomic_need_value_p (gs))
2319 pp_string (buffer, "[needed] ");
07838b13 2320 pp_left_paren (buffer);
726a989a
RB
2321 dump_generic_node (buffer, gimple_omp_atomic_store_val (gs),
2322 spc, flags, false);
07838b13 2323 pp_right_paren (buffer);
726a989a
RB
2324 }
2325}
2326
726a989a
RB
2327
2328/* Dump all the memory operands for statement GS. BUFFER, SPC and
b5f47924 2329 FLAGS are as in pp_gimple_stmt_1. */
726a989a
RB
2330
2331static void
355fe088 2332dump_gimple_mem_ops (pretty_printer *buffer, gimple *gs, int spc, int flags)
726a989a 2333{
5006671f
RG
2334 tree vdef = gimple_vdef (gs);
2335 tree vuse = gimple_vuse (gs);
726a989a 2336
5006671f 2337 if (vdef != NULL_TREE)
726a989a 2338 {
5006671f
RG
2339 pp_string (buffer, "# ");
2340 dump_generic_node (buffer, vdef, spc + 2, flags, false);
2341 pp_string (buffer, " = VDEF <");
2342 dump_generic_node (buffer, vuse, spc + 2, flags, false);
07838b13 2343 pp_greater (buffer);
726a989a 2344 newline_and_indent (buffer, spc);
726a989a 2345 }
5006671f 2346 else if (vuse != NULL_TREE)
726a989a 2347 {
5006671f
RG
2348 pp_string (buffer, "# VUSE <");
2349 dump_generic_node (buffer, vuse, spc + 2, flags, false);
07838b13 2350 pp_greater (buffer);
726a989a 2351 newline_and_indent (buffer, spc);
726a989a
RB
2352 }
2353}
2354
2355
b5f47924 2356/* Print the gimple statement GS on the pretty printer BUFFER, SPC
726a989a 2357 spaces of indent. FLAGS specifies details to show in the dump (see
c4669594
SB
2358 TDF_* in dumpfile.h). The caller is responsible for calling
2359 pp_flush on BUFFER to finalize the pretty printer. */
726a989a
RB
2360
2361void
355fe088 2362pp_gimple_stmt_1 (pretty_printer *buffer, gimple *gs, int spc, int flags)
726a989a
RB
2363{
2364 if (!gs)
2365 return;
2366
2367 if (flags & TDF_STMTADDR)
2368 pp_printf (buffer, "<&%p> ", (void *) gs);
2369
2370 if ((flags & TDF_LINENO) && gimple_has_location (gs))
bb42836b 2371 dump_location (buffer, gimple_location (gs));
726a989a 2372
cae63f88
DN
2373 if (flags & TDF_EH)
2374 {
1d65f45c
RH
2375 int lp_nr = lookup_stmt_eh_lp (gs);
2376 if (lp_nr > 0)
2377 pp_printf (buffer, "[LP %d] ", lp_nr);
2378 else if (lp_nr < 0)
2379 pp_printf (buffer, "[MNT %d] ", -lp_nr);
cae63f88
DN
2380 }
2381
726a989a
RB
2382 if ((flags & (TDF_VOPS|TDF_MEMSYMS))
2383 && gimple_has_mem_ops (gs))
2384 dump_gimple_mem_ops (buffer, gs, spc, flags);
2385
a895a2b8
KV
2386 if (gimple_has_lhs (gs)
2387 && (flags & TDF_ALIAS))
2388 dump_ssaname_info (buffer, gimple_get_lhs (gs), spc);
f0107145 2389
726a989a
RB
2390 switch (gimple_code (gs))
2391 {
2392 case GIMPLE_ASM:
538dd0b7 2393 dump_gimple_asm (buffer, as_a <gasm *> (gs), spc, flags);
726a989a
RB
2394 break;
2395
2396 case GIMPLE_ASSIGN:
538dd0b7 2397 dump_gimple_assign (buffer, as_a <gassign *> (gs), spc, flags);
726a989a
RB
2398 break;
2399
2400 case GIMPLE_BIND:
538dd0b7 2401 dump_gimple_bind (buffer, as_a <gbind *> (gs), spc, flags);
726a989a
RB
2402 break;
2403
2404 case GIMPLE_CALL:
538dd0b7 2405 dump_gimple_call (buffer, as_a <gcall *> (gs), spc, flags);
726a989a
RB
2406 break;
2407
2408 case GIMPLE_COND:
538dd0b7 2409 dump_gimple_cond (buffer, as_a <gcond *> (gs), spc, flags);
726a989a
RB
2410 break;
2411
2412 case GIMPLE_LABEL:
538dd0b7 2413 dump_gimple_label (buffer, as_a <glabel *> (gs), spc, flags);
726a989a
RB
2414 break;
2415
2416 case GIMPLE_GOTO:
538dd0b7 2417 dump_gimple_goto (buffer, as_a <ggoto *> (gs), spc, flags);
726a989a
RB
2418 break;
2419
2420 case GIMPLE_NOP:
2421 pp_string (buffer, "GIMPLE_NOP");
2422 break;
2423
2424 case GIMPLE_RETURN:
538dd0b7 2425 dump_gimple_return (buffer, as_a <greturn *> (gs), spc, flags);
726a989a
RB
2426 break;
2427
2428 case GIMPLE_SWITCH:
538dd0b7 2429 dump_gimple_switch (buffer, as_a <gswitch *> (gs), spc, flags);
726a989a
RB
2430 break;
2431
2432 case GIMPLE_TRY:
538dd0b7 2433 dump_gimple_try (buffer, as_a <gtry *> (gs), spc, flags);
726a989a
RB
2434 break;
2435
2436 case GIMPLE_PHI:
538dd0b7 2437 dump_gimple_phi (buffer, as_a <gphi *> (gs), spc, false, flags);
726a989a
RB
2438 break;
2439
2440 case GIMPLE_OMP_PARALLEL:
538dd0b7
DM
2441 dump_gimple_omp_parallel (buffer, as_a <gomp_parallel *> (gs), spc,
2442 flags);
726a989a
RB
2443 break;
2444
2445 case GIMPLE_OMP_TASK:
538dd0b7 2446 dump_gimple_omp_task (buffer, as_a <gomp_task *> (gs), spc, flags);
726a989a
RB
2447 break;
2448
2449 case GIMPLE_OMP_ATOMIC_LOAD:
538dd0b7
DM
2450 dump_gimple_omp_atomic_load (buffer, as_a <gomp_atomic_load *> (gs),
2451 spc, flags);
726a989a
RB
2452 break;
2453
2454 case GIMPLE_OMP_ATOMIC_STORE:
538dd0b7
DM
2455 dump_gimple_omp_atomic_store (buffer,
2456 as_a <gomp_atomic_store *> (gs),
2457 spc, flags);
726a989a
RB
2458 break;
2459
2460 case GIMPLE_OMP_FOR:
538dd0b7 2461 dump_gimple_omp_for (buffer, as_a <gomp_for *> (gs), spc, flags);
726a989a
RB
2462 break;
2463
2464 case GIMPLE_OMP_CONTINUE:
538dd0b7
DM
2465 dump_gimple_omp_continue (buffer, as_a <gomp_continue *> (gs), spc,
2466 flags);
726a989a
RB
2467 break;
2468
2469 case GIMPLE_OMP_SINGLE:
538dd0b7
DM
2470 dump_gimple_omp_single (buffer, as_a <gomp_single *> (gs), spc,
2471 flags);
726a989a
RB
2472 break;
2473
acf0174b 2474 case GIMPLE_OMP_TARGET:
538dd0b7
DM
2475 dump_gimple_omp_target (buffer, as_a <gomp_target *> (gs), spc,
2476 flags);
acf0174b
JJ
2477 break;
2478
2479 case GIMPLE_OMP_TEAMS:
538dd0b7
DM
2480 dump_gimple_omp_teams (buffer, as_a <gomp_teams *> (gs), spc,
2481 flags);
acf0174b
JJ
2482 break;
2483
726a989a
RB
2484 case GIMPLE_OMP_RETURN:
2485 dump_gimple_omp_return (buffer, gs, spc, flags);
2486 break;
2487
2488 case GIMPLE_OMP_SECTIONS:
538dd0b7
DM
2489 dump_gimple_omp_sections (buffer, as_a <gomp_sections *> (gs),
2490 spc, flags);
726a989a
RB
2491 break;
2492
2493 case GIMPLE_OMP_SECTIONS_SWITCH:
2494 pp_string (buffer, "GIMPLE_SECTIONS_SWITCH");
2495 break;
2496
2497 case GIMPLE_OMP_MASTER:
acf0174b 2498 case GIMPLE_OMP_TASKGROUP:
726a989a 2499 case GIMPLE_OMP_SECTION:
b2b40051 2500 case GIMPLE_OMP_GRID_BODY:
726a989a
RB
2501 dump_gimple_omp_block (buffer, gs, spc, flags);
2502 break;
2503
d9a6bd32
JJ
2504 case GIMPLE_OMP_ORDERED:
2505 dump_gimple_omp_ordered (buffer, as_a <gomp_ordered *> (gs), spc,
2506 flags);
2507 break;
2508
726a989a 2509 case GIMPLE_OMP_CRITICAL:
538dd0b7
DM
2510 dump_gimple_omp_critical (buffer, as_a <gomp_critical *> (gs), spc,
2511 flags);
726a989a
RB
2512 break;
2513
726a989a 2514 case GIMPLE_CATCH:
538dd0b7 2515 dump_gimple_catch (buffer, as_a <gcatch *> (gs), spc, flags);
726a989a
RB
2516 break;
2517
2518 case GIMPLE_EH_FILTER:
538dd0b7 2519 dump_gimple_eh_filter (buffer, as_a <geh_filter *> (gs), spc, flags);
726a989a
RB
2520 break;
2521
1d65f45c 2522 case GIMPLE_EH_MUST_NOT_THROW:
538dd0b7
DM
2523 dump_gimple_eh_must_not_throw (buffer,
2524 as_a <geh_mnt *> (gs),
2525 spc, flags);
1d65f45c
RH
2526 break;
2527
0a35513e 2528 case GIMPLE_EH_ELSE:
538dd0b7 2529 dump_gimple_eh_else (buffer, as_a <geh_else *> (gs), spc, flags);
0a35513e
AH
2530 break;
2531
726a989a 2532 case GIMPLE_RESX:
538dd0b7 2533 dump_gimple_resx (buffer, as_a <gresx *> (gs), spc, flags);
726a989a
RB
2534 break;
2535
1d65f45c 2536 case GIMPLE_EH_DISPATCH:
538dd0b7
DM
2537 dump_gimple_eh_dispatch (buffer, as_a <geh_dispatch *> (gs), spc,
2538 flags);
1d65f45c
RH
2539 break;
2540
b5b8b0ac 2541 case GIMPLE_DEBUG:
538dd0b7 2542 dump_gimple_debug (buffer, as_a <gdebug *> (gs), spc, flags);
b5b8b0ac
AO
2543 break;
2544
726a989a
RB
2545 case GIMPLE_PREDICT:
2546 pp_string (buffer, "// predicted ");
2547 if (gimple_predict_outcome (gs))
2548 pp_string (buffer, "likely by ");
2549 else
2550 pp_string (buffer, "unlikely by ");
2551 pp_string (buffer, predictor_name (gimple_predict_predictor (gs)));
2552 pp_string (buffer, " predictor.");
2553 break;
2554
0a35513e 2555 case GIMPLE_TRANSACTION:
538dd0b7
DM
2556 dump_gimple_transaction (buffer, as_a <gtransaction *> (gs), spc,
2557 flags);
0a35513e
AH
2558 break;
2559
726a989a
RB
2560 default:
2561 GIMPLE_NIY;
2562 }
726a989a
RB
2563}
2564
2565
a315c44c 2566/* Dumps header of basic block BB to OUTF indented by INDENT
726a989a
RB
2567 spaces and details described by flags. */
2568
2569static void
a315c44c 2570dump_gimple_bb_header (FILE *outf, basic_block bb, int indent, int flags)
726a989a 2571{
726a989a
RB
2572 if (flags & TDF_BLOCKS)
2573 {
726a989a
RB
2574 if (flags & TDF_LINENO)
2575 {
2576 gimple_stmt_iterator gsi;
a315c44c
SB
2577
2578 if (flags & TDF_COMMENT)
2579 fputs (";; ", outf);
726a989a
RB
2580
2581 for (gsi = gsi_start_bb (bb); !gsi_end_p (gsi); gsi_next (&gsi))
b5b8b0ac
AO
2582 if (!is_gimple_debug (gsi_stmt (gsi))
2583 && get_lineno (gsi_stmt (gsi)) != UNKNOWN_LOCATION)
726a989a 2584 {
3a8ebb92
L
2585 fprintf (outf, "%*sstarting at line %d",
2586 indent, "", get_lineno (gsi_stmt (gsi)));
726a989a
RB
2587 break;
2588 }
a315c44c
SB
2589 if (bb->discriminator)
2590 fprintf (outf, ", discriminator %i", bb->discriminator);
2591 fputc ('\n', outf);
726a989a 2592 }
726a989a
RB
2593 }
2594 else
2595 {
355fe088 2596 gimple *stmt = first_stmt (bb);
726a989a 2597 if (!stmt || gimple_code (stmt) != GIMPLE_LABEL)
1ee62b92
PG
2598 {
2599 if (flags & TDF_GIMPLE)
2600 fprintf (outf, "%*sbb_%d:\n", indent, "", bb->index);
2601 else
0d56d3c1
ML
2602 fprintf (outf, "%*s<bb %d> [%.1f%%]:\n", indent, "", bb->index,
2603 bb->frequency * 100.0 / REG_BR_PROB_BASE);
1ee62b92 2604 }
726a989a 2605 }
726a989a
RB
2606}
2607
2608
2609/* Dumps end of basic block BB to buffer BUFFER indented by INDENT
2610 spaces. */
2611
2612static void
c4669594
SB
2613dump_gimple_bb_footer (FILE *outf ATTRIBUTE_UNUSED,
2614 basic_block bb ATTRIBUTE_UNUSED,
2615 int indent ATTRIBUTE_UNUSED,
2616 int flags ATTRIBUTE_UNUSED)
726a989a 2617{
c4669594
SB
2618 /* There is currently no GIMPLE-specific basic block info to dump. */
2619 return;
726a989a
RB
2620}
2621
2622
2623/* Dump PHI nodes of basic block BB to BUFFER with details described
2624 by FLAGS and indented by INDENT spaces. */
2625
2626static void
2627dump_phi_nodes (pretty_printer *buffer, basic_block bb, int indent, int flags)
2628{
538dd0b7 2629 gphi_iterator i;
726a989a
RB
2630
2631 for (i = gsi_start_phis (bb); !gsi_end_p (i); gsi_next (&i))
2632 {
538dd0b7 2633 gphi *phi = i.phi ();
ea057359 2634 if (!virtual_operand_p (gimple_phi_result (phi)) || (flags & TDF_VOPS))
726a989a
RB
2635 {
2636 INDENT (indent);
1ee62b92
PG
2637 dump_gimple_phi (buffer, phi, indent,
2638 (flags & TDF_GIMPLE) ? false : true, flags);
726a989a
RB
2639 pp_newline (buffer);
2640 }
2641 }
2642}
2643
2644
2645/* Dump jump to basic block BB that is represented implicitly in the cfg
2646 to BUFFER. */
2647
2648static void
0d56d3c1 2649pp_cfg_jump (pretty_printer *buffer, edge e, int flags)
726a989a 2650{
1ee62b92 2651 if (flags & TDF_GIMPLE)
726a989a 2652 {
1ee62b92 2653 pp_string (buffer, "goto bb_");
0d56d3c1 2654 pp_decimal_int (buffer, e->dest->index);
726a989a
RB
2655 pp_semicolon (buffer);
2656 }
2657 else
1ee62b92 2658 {
0d56d3c1
ML
2659 gimple *stmt = first_stmt (e->dest);
2660
1ee62b92 2661 pp_string (buffer, "goto <bb ");
0d56d3c1 2662 pp_decimal_int (buffer, e->dest->index);
1ee62b92
PG
2663 pp_greater (buffer);
2664 if (stmt && gimple_code (stmt) == GIMPLE_LABEL)
2665 {
2666 pp_string (buffer, " (");
2667 dump_generic_node (buffer,
2668 gimple_label_label (as_a <glabel *> (stmt)),
2669 0, 0, false);
2670 pp_right_paren (buffer);
2671 pp_semicolon (buffer);
2672 }
2673 else
2674 pp_semicolon (buffer);
0d56d3c1
ML
2675
2676 dump_edge_probability (buffer, e);
1ee62b92 2677 }
726a989a
RB
2678}
2679
2680
2681/* Dump edges represented implicitly in basic block BB to BUFFER, indented
2682 by INDENT spaces, with details given by FLAGS. */
2683
2684static void
2685dump_implicit_edges (pretty_printer *buffer, basic_block bb, int indent,
2686 int flags)
2687{
2688 edge e;
355fe088 2689 gimple *stmt;
726a989a
RB
2690
2691 stmt = last_stmt (bb);
2692
2693 if (stmt && gimple_code (stmt) == GIMPLE_COND)
2694 {
2695 edge true_edge, false_edge;
2696
2697 /* When we are emitting the code or changing CFG, it is possible that
2698 the edges are not yet created. When we are using debug_bb in such
2699 a situation, we do not want it to crash. */
2700 if (EDGE_COUNT (bb->succs) != 2)
2701 return;
2702 extract_true_false_edges_from_block (bb, &true_edge, &false_edge);
2703
2704 INDENT (indent + 2);
0d56d3c1 2705 pp_cfg_jump (buffer, true_edge, flags);
726a989a
RB
2706 newline_and_indent (buffer, indent);
2707 pp_string (buffer, "else");
2708 newline_and_indent (buffer, indent + 2);
0d56d3c1 2709 pp_cfg_jump (buffer, false_edge, flags);
726a989a
RB
2710 pp_newline (buffer);
2711 return;
2712 }
2713
2714 /* If there is a fallthru edge, we may need to add an artificial
2715 goto to the dump. */
0fd4b31d 2716 e = find_fallthru_edge (bb->succs);
726a989a
RB
2717
2718 if (e && e->dest != bb->next_bb)
2719 {
2720 INDENT (indent);
2721
2722 if ((flags & TDF_LINENO)
bb42836b
MLI
2723 && e->goto_locus != UNKNOWN_LOCATION)
2724 dump_location (buffer, e->goto_locus);
726a989a 2725
0d56d3c1 2726 pp_cfg_jump (buffer, e, flags);
726a989a
RB
2727 pp_newline (buffer);
2728 }
2729}
2730
2731
2732/* Dumps basic block BB to buffer BUFFER with details described by FLAGS and
2733 indented by INDENT spaces. */
2734
2735static void
2736gimple_dump_bb_buff (pretty_printer *buffer, basic_block bb, int indent,
2737 int flags)
2738{
2739 gimple_stmt_iterator gsi;
355fe088 2740 gimple *stmt;
726a989a
RB
2741 int label_indent = indent - 2;
2742
2743 if (label_indent < 0)
2744 label_indent = 0;
2745
726a989a
RB
2746 dump_phi_nodes (buffer, bb, indent, flags);
2747
2748 for (gsi = gsi_start_bb (bb); !gsi_end_p (gsi); gsi_next (&gsi))
2749 {
2750 int curr_indent;
2751
2752 stmt = gsi_stmt (gsi);
2753
2754 curr_indent = gimple_code (stmt) == GIMPLE_LABEL ? label_indent : indent;
2755
2756 INDENT (curr_indent);
b5f47924 2757 pp_gimple_stmt_1 (buffer, stmt, curr_indent, flags);
f8923f7e 2758 pp_newline_and_flush (buffer);
2eb712b4
MJ
2759 gcc_checking_assert (DECL_STRUCT_FUNCTION (current_function_decl));
2760 dump_histograms_for_stmt (DECL_STRUCT_FUNCTION (current_function_decl),
c3284718 2761 pp_buffer (buffer)->stream, stmt);
726a989a
RB
2762 }
2763
2764 dump_implicit_edges (buffer, bb, indent, flags);
3e31cf28 2765 pp_flush (buffer);
726a989a
RB
2766}
2767
2768
2769/* Dumps basic block BB to FILE with details described by FLAGS and
2770 indented by INDENT spaces. */
2771
2772void
a315c44c 2773gimple_dump_bb (FILE *file, basic_block bb, int indent, int flags)
726a989a 2774{
a315c44c 2775 dump_gimple_bb_header (file, bb, indent, flags);
c4669594
SB
2776 if (bb->index >= NUM_FIXED_BLOCKS)
2777 {
b3f80694 2778 pretty_printer buffer;
b3f80694
GDR
2779 pp_needs_newline (&buffer) = true;
2780 buffer.buffer->stream = file;
c4669594
SB
2781 gimple_dump_bb_buff (&buffer, bb, indent, flags);
2782 }
a315c44c 2783 dump_gimple_bb_footer (file, bb, indent, flags);
726a989a 2784}
41222ddf
SB
2785
2786/* Dumps basic block BB to pretty-printer PP with default dump flags and
2787 no indentation, for use as a label of a DOT graph record-node.
2788 ??? Should just use gimple_dump_bb_buff here, except that value profiling
2789 histogram dumping doesn't know about pretty-printers. */
2790
2791void
2792gimple_dump_bb_for_graph (pretty_printer *pp, basic_block bb)
2793{
41222ddf
SB
2794 pp_printf (pp, "<bb %d>:\n", bb->index);
2795 pp_write_text_as_dot_label_to_stream (pp, /*for_record=*/true);
2796
538dd0b7
DM
2797 for (gphi_iterator gsi = gsi_start_phis (bb); !gsi_end_p (gsi);
2798 gsi_next (&gsi))
41222ddf 2799 {
538dd0b7 2800 gphi *phi = gsi.phi ();
41222ddf
SB
2801 if (!virtual_operand_p (gimple_phi_result (phi))
2802 || (dump_flags & TDF_VOPS))
2803 {
07838b13 2804 pp_bar (pp);
41222ddf
SB
2805 pp_write_text_to_stream (pp);
2806 pp_string (pp, "# ");
2807 pp_gimple_stmt_1 (pp, phi, 0, dump_flags);
2808 pp_newline (pp);
2809 pp_write_text_as_dot_label_to_stream (pp, /*for_record=*/true);
2810 }
2811 }
2812
538dd0b7
DM
2813 for (gimple_stmt_iterator gsi = gsi_start_bb (bb); !gsi_end_p (gsi);
2814 gsi_next (&gsi))
41222ddf 2815 {
355fe088 2816 gimple *stmt = gsi_stmt (gsi);
07838b13 2817 pp_bar (pp);
41222ddf
SB
2818 pp_write_text_to_stream (pp);
2819 pp_gimple_stmt_1 (pp, stmt, 0, dump_flags);
2820 pp_newline (pp);
2821 pp_write_text_as_dot_label_to_stream (pp, /*for_record=*/true);
2822 }
2823 dump_implicit_edges (pp, bb, 0, dump_flags);
2824 pp_write_text_as_dot_label_to_stream (pp, /*for_record=*/true);
2825}
2826