gcc/gimple-pretty-print.c

   1 /* Pretty formatting of GIMPLE statements and expressions.
   2    Copyright (C) 2001, 2002, 2003, 2004, 2005, 2006, 2007, 2008, 2009, 2010,
   3    2011  Free Software Foundation, Inc.
   4    Contributed by Aldy Hernandez <aldyh@redhat.com> and
   5    Diego Novillo <dnovillo@google.com>
   6
   7 This file is part of GCC.
   8
   9 GCC is free software; you can redistribute it and/or modify it under
  10 the terms of the GNU General Public License as published by the Free
  11 Software Foundation; either version 3, or (at your option) any later
  12 version.
  13
  14 GCC is distributed in the hope that it will be useful, but WITHOUT ANY
  15 WARRANTY; without even the implied warranty of MERCHANTABILITY or
  16 FITNESS FOR A PARTICULAR PURPOSE.  See the GNU General Public License
  17 for more details.
  18
  19 You should have received a copy of the GNU General Public License
  20 along with GCC; see the file COPYING3.  If not see
  21 <http://www.gnu.org/licenses/>.  */
  22
  23 #include "config.h"
  24 #include "system.h"
  25 #include "coretypes.h"
  26 #include "tm.h"
  27 #include "tree.h"
  28 #include "diagnostic.h"
  29 #include "tree-pretty-print.h"
  30 #include "gimple-pretty-print.h"
  31 #include "hashtab.h"
  32 #include "tree-flow.h"
  33 #include "tree-pass.h"
  34 #include "gimple.h"
  35 #include "value-prof.h"
  36 #include "trans-mem.h"
  37
  38 #define INDENT(SPACE)                                                   \
  39   do { int i; for (i = 0; i < SPACE; i++) pp_space (buffer); } while (0)
  40
  41 static pretty_printer buffer;
  42 static bool initialized = false;
  43
  44 #define GIMPLE_NIY do_niy (buffer,gs)
  45
  46 /* Try to print on BUFFER a default message for the unrecognized
  47    gimple statement GS.  */
  48
  49 static void
  50 do_niy (pretty_printer *buffer, gimple gs)
  51 {
  52   pp_printf (buffer, "<<< Unknown GIMPLE statement: %s >>>\n",
  53              gimple_code_name[(int) gimple_code (gs)]);
  54 }
  55
  56
  57 /* Initialize the pretty printer on FILE if needed.  */
  58
  59 static void
  60 maybe_init_pretty_print (FILE *file)
  61 {
  62   if (!initialized)
  63     {
  64       pp_construct (&buffer, NULL, 0);
  65       pp_needs_newline (&buffer) = true;
  66       initialized = true;
  67     }
  68
  69   buffer.buffer->stream = file;
  70 }
  71
  72
  73 /* Emit a newline and SPC indentantion spaces to BUFFER.  */
  74
  75 static void
  76 newline_and_indent (pretty_printer *buffer, int spc)
  77 {
  78   pp_newline (buffer);
  79   INDENT (spc);
  80 }
  81
  82
  83 /* Print the GIMPLE statement GS on stderr.  */
  84
  85 DEBUG_FUNCTION void
  86 debug_gimple_stmt (gimple gs)
  87 {
  88   print_gimple_stmt (stderr, gs, 0, TDF_VOPS|TDF_MEMSYMS);
  89   fprintf (stderr, "\n");
  90 }
  91
  92
  93 /* Dump GIMPLE statement G to FILE using SPC indentantion spaces and
  94    FLAGS as in dump_gimple_stmt.  */
  95
  96 void
  97 print_gimple_stmt (FILE *file, gimple g, int spc, int flags)
  98 {
  99   maybe_init_pretty_print (file);
 100   dump_gimple_stmt (&buffer, g, spc, flags);
 101   pp_flush (&buffer);
 102 }
 103
 104
 105 /* Dump GIMPLE statement G to FILE using SPC indentantion spaces and
 106    FLAGS as in dump_gimple_stmt.  Print only the right-hand side
 107    of the statement.  */
 108
 109 void
 110 print_gimple_expr (FILE *file, gimple g, int spc, int flags)
 111 {
 112   flags |= TDF_RHS_ONLY;
 113   maybe_init_pretty_print (file);
 114   dump_gimple_stmt (&buffer, g, spc, flags);
 115 }
 116
 117
 118 /* Print the GIMPLE sequence SEQ on BUFFER using SPC indentantion
 119    spaces and FLAGS as in dump_gimple_stmt.  */
 120
 121 static void
 122 dump_gimple_seq (pretty_printer *buffer, gimple_seq seq, int spc, int flags)
 123 {
 124   gimple_stmt_iterator i;
 125
 126   for (i = gsi_start (seq); !gsi_end_p (i); gsi_next (&i))
 127     {
 128       gimple gs = gsi_stmt (i);
 129       INDENT (spc);
 130       dump_gimple_stmt (buffer, gs, spc, flags);
 131       if (!gsi_one_before_end_p (i))
 132         pp_newline (buffer);
 133     }
 134 }
 135
 136
 137 /* Dump GIMPLE sequence SEQ to FILE using SPC indentantion spaces and
 138    FLAGS as in dump_gimple_stmt.  */
 139
 140 void
 141 print_gimple_seq (FILE *file, gimple_seq seq, int spc, int flags)
 142 {
 143   maybe_init_pretty_print (file);
 144   dump_gimple_seq (&buffer, seq, spc, flags);
 145   pp_flush (&buffer);
 146 }
 147
 148
 149 /* Print the GIMPLE sequence SEQ on stderr.  */
 150
 151 DEBUG_FUNCTION void
 152 debug_gimple_seq (gimple_seq seq)
 153 {
 154   print_gimple_seq (stderr, seq, 0, TDF_VOPS|TDF_MEMSYMS);
 155 }
 156
 157
 158 /* A simple helper to pretty-print some of the gimple tuples in the printf
 159    style. The format modifiers are preceded by '%' and are:
 160      'G' - outputs a string corresponding to the code of the given gimple,
 161      'S' - outputs a gimple_seq with indent of spc + 2,
 162      'T' - outputs the tree t,
 163      'd' - outputs an int as a decimal,
 164      's' - outputs a string,
 165      'n' - outputs a newline,
 166      'x' - outputs an int as hexadecimal,
 167      '+' - increases indent by 2 then outputs a newline,
 168      '-' - decreases indent by 2 then outputs a newline.   */
 169
 170 static void
 171 dump_gimple_fmt (pretty_printer *buffer, int spc, int flags,
 172                  const char *fmt, ...)
 173 {
 174   va_list args;
 175   const char *c;
 176   const char *tmp;
 177
 178   va_start (args, fmt);
 179   for (c = fmt; *c; c++)
 180     {
 181       if (*c == '%')
 182         {
 183           gimple_seq seq;
 184           tree t;
 185           gimple g;
 186           switch (*++c)
 187             {
 188               case 'G':
 189                 g = va_arg (args, gimple);
 190                 tmp = gimple_code_name[gimple_code (g)];
 191                 pp_string (buffer, tmp);
 192                 break;
 193
 194               case 'S':
 195                 seq = va_arg (args, gimple_seq);
 196                 pp_newline (buffer);
 197                 dump_gimple_seq (buffer, seq, spc + 2, flags);
 198                 newline_and_indent (buffer, spc);
 199                 break;
 200
 201               case 'T':
 202                 t = va_arg (args, tree);
 203                 if (t == NULL_TREE)
 204                   pp_string (buffer, "NULL");
 205                 else
 206                   dump_generic_node (buffer, t, spc, flags, false);
 207                 break;
 208
 209               case 'd':
 210                 pp_decimal_int (buffer, va_arg (args, int));
 211                 break;
 212
 213               case 's':
 214                 pp_string (buffer, va_arg (args, char *));
 215                 break;
 216
 217               case 'n':
 218                 newline_and_indent (buffer, spc);
 219                 break;
 220
 221               case 'x':
 222                 pp_scalar (buffer, "%x", va_arg (args, int));
 223                 break;
 224
 225               case '+':
 226                 spc += 2;
 227                 newline_and_indent (buffer, spc);
 228                 break;
 229
 230               case '-':
 231                 spc -= 2;
 232                 newline_and_indent (buffer, spc);
 233                 break;
 234
 235               default:
 236                 gcc_unreachable ();
 237             }
 238         }
 239       else
 240         pp_character (buffer, *c);
 241     }
 242   va_end (args);
 243 }
 244
 245
 246 /* Helper for dump_gimple_assign.  Print the unary RHS of the
 247    assignment GS.  BUFFER, SPC and FLAGS are as in dump_gimple_stmt.  */
 248
 249 static void
 250 dump_unary_rhs (pretty_printer *buffer, gimple gs, int spc, int flags)
 251 {
 252   enum tree_code rhs_code = gimple_assign_rhs_code (gs);
 253   tree lhs = gimple_assign_lhs (gs);
 254   tree rhs = gimple_assign_rhs1 (gs);
 255
 256   switch (rhs_code)
 257     {
 258     case VIEW_CONVERT_EXPR:
 259     case ASSERT_EXPR:
 260       dump_generic_node (buffer, rhs, spc, flags, false);
 261       break;
 262
 263     case FIXED_CONVERT_EXPR:
 264     case ADDR_SPACE_CONVERT_EXPR:
 265     case FIX_TRUNC_EXPR:
 266     case FLOAT_EXPR:
 267     CASE_CONVERT:
 268       pp_character (buffer, '(');
 269       dump_generic_node (buffer, TREE_TYPE (lhs), spc, flags, false);
 270       pp_string (buffer, ") ");
 271       if (op_prio (rhs) < op_code_prio (rhs_code))
 272         {
 273           pp_character (buffer, '(');
 274           dump_generic_node (buffer, rhs, spc, flags, false);
 275           pp_character (buffer, ')');
 276         }
 277       else
 278         dump_generic_node (buffer, rhs, spc, flags, false);
 279       break;
 280
 281     case PAREN_EXPR:
 282       pp_string (buffer, "((");
 283       dump_generic_node (buffer, rhs, spc, flags, false);
 284       pp_string (buffer, "))");
 285       break;
 286
 287     case ABS_EXPR:
 288       pp_string (buffer, "ABS_EXPR <");
 289       dump_generic_node (buffer, rhs, spc, flags, false);
 290       pp_character (buffer, '>');
 291       break;
 292
 293     default:
 294       if (TREE_CODE_CLASS (rhs_code) == tcc_declaration
 295           || TREE_CODE_CLASS (rhs_code) == tcc_constant
 296           || TREE_CODE_CLASS (rhs_code) == tcc_reference
 297           || rhs_code == SSA_NAME
 298           || rhs_code == ADDR_EXPR
 299           || rhs_code == CONSTRUCTOR)
 300         {
 301           dump_generic_node (buffer, rhs, spc, flags, false);
 302           break;
 303         }
 304       else if (rhs_code == BIT_NOT_EXPR)
 305         pp_character (buffer, '~');
 306       else if (rhs_code == TRUTH_NOT_EXPR)
 307         pp_character (buffer, '!');
 308       else if (rhs_code == NEGATE_EXPR)
 309         pp_character (buffer, '-');
 310       else
 311         {
 312           pp_character (buffer, '[');
 313           pp_string (buffer, tree_code_name [rhs_code]);
 314           pp_string (buffer, "] ");
 315         }
 316
 317       if (op_prio (rhs) < op_code_prio (rhs_code))
 318         {
 319           pp_character (buffer, '(');
 320           dump_generic_node (buffer, rhs, spc, flags, false);
 321           pp_character (buffer, ')');
 322         }
 323       else
 324         dump_generic_node (buffer, rhs, spc, flags, false);
 325       break;
 326     }
 327 }
 328
 329
 330 /* Helper for dump_gimple_assign.  Print the binary RHS of the
 331    assignment GS.  BUFFER, SPC and FLAGS are as in dump_gimple_stmt.  */
 332
 333 static void
 334 dump_binary_rhs (pretty_printer *buffer, gimple gs, int spc, int flags)
 335 {
 336   const char *p;
 337   enum tree_code code = gimple_assign_rhs_code (gs);
 338   switch (code)
 339     {
 340     case COMPLEX_EXPR:
 341     case MIN_EXPR:
 342     case MAX_EXPR:
 343     case VEC_WIDEN_MULT_HI_EXPR:
 344     case VEC_WIDEN_MULT_LO_EXPR:
 345     case VEC_WIDEN_MULT_EVEN_EXPR:
 346     case VEC_WIDEN_MULT_ODD_EXPR:
 347     case VEC_PACK_TRUNC_EXPR:
 348     case VEC_PACK_SAT_EXPR:
 349     case VEC_PACK_FIX_TRUNC_EXPR:
 350     case VEC_WIDEN_LSHIFT_HI_EXPR:
 351     case VEC_WIDEN_LSHIFT_LO_EXPR:
 352       for (p = tree_code_name [(int) code]; *p; p++)
 353         pp_character (buffer, TOUPPER (*p));
 354       pp_string (buffer, " <");
 355       dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
 356       pp_string (buffer, ", ");
 357       dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
 358       pp_character (buffer, '>');
 359       break;
 360
 361     default:
 362       if (op_prio (gimple_assign_rhs1 (gs)) <= op_code_prio (code))
 363         {
 364           pp_character (buffer, '(');
 365           dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags,
 366                              false);
 367           pp_character (buffer, ')');
 368         }
 369       else
 370         dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
 371       pp_space (buffer);
 372       pp_string (buffer, op_symbol_code (gimple_assign_rhs_code (gs)));
 373       pp_space (buffer);
 374       if (op_prio (gimple_assign_rhs2 (gs)) <= op_code_prio (code))
 375         {
 376           pp_character (buffer, '(');
 377           dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags,
 378                              false);
 379           pp_character (buffer, ')');
 380         }
 381       else
 382         dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
 383     }
 384 }
 385
 386 /* Helper for dump_gimple_assign.  Print the ternary RHS of the
 387    assignment GS.  BUFFER, SPC and FLAGS are as in dump_gimple_stmt.  */
 388
 389 static void
 390 dump_ternary_rhs (pretty_printer *buffer, gimple gs, int spc, int flags)
 391 {
 392   const char *p;
 393   enum tree_code code = gimple_assign_rhs_code (gs);
 394   switch (code)
 395     {
 396     case WIDEN_MULT_PLUS_EXPR:
 397     case WIDEN_MULT_MINUS_EXPR:
 398       for (p = tree_code_name [(int) code]; *p; p++)
 399         pp_character (buffer, TOUPPER (*p));
 400       pp_string (buffer, " <");
 401       dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
 402       pp_string (buffer, ", ");
 403       dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
 404       pp_string (buffer, ", ");
 405       dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
 406       pp_character (buffer, '>');
 407       break;
 408
 409     case FMA_EXPR:
 410       dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
 411       pp_string (buffer, " * ");
 412       dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
 413       pp_string (buffer, " + ");
 414       dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
 415       break;
 416
 417     case DOT_PROD_EXPR:
 418       pp_string (buffer, "DOT_PROD_EXPR <");
 419       dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
 420       pp_string (buffer, ", ");
 421       dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
 422       pp_string (buffer, ", ");
 423       dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
 424       pp_string (buffer, ">");
 425       break;
 426
 427     case VEC_PERM_EXPR:
 428       pp_string (buffer, "VEC_PERM_EXPR <");
 429       dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
 430       pp_string (buffer, ", ");
 431       dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
 432       pp_string (buffer, ", ");
 433       dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
 434       pp_string (buffer, ">");
 435       break;
 436
 437     case REALIGN_LOAD_EXPR:
 438       pp_string (buffer, "REALIGN_LOAD <");
 439       dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
 440       pp_string (buffer, ", ");
 441       dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
 442       pp_string (buffer, ", ");
 443       dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
 444       pp_string (buffer, ">");
 445       break;
 446
 447     case COND_EXPR:
 448       dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
 449       pp_string (buffer, " ? ");
 450       dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
 451       pp_string (buffer, " : ");
 452       dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
 453       break;
 454
 455     case VEC_COND_EXPR:
 456       pp_string (buffer, "VEC_COND_EXPR <");
 457       dump_generic_node (buffer, gimple_assign_rhs1 (gs), spc, flags, false);
 458       pp_string (buffer, ", ");
 459       dump_generic_node (buffer, gimple_assign_rhs2 (gs), spc, flags, false);
 460       pp_string (buffer, ", ");
 461       dump_generic_node (buffer, gimple_assign_rhs3 (gs), spc, flags, false);
 462       pp_string (buffer, ">");
 463       break;
 464
 465     default:
 466       gcc_unreachable ();
 467     }
 468 }
 469
 470
 471 /* Dump the gimple assignment GS.  BUFFER, SPC and FLAGS are as in
 472    dump_gimple_stmt.  */
 473
 474 static void
 475 dump_gimple_assign (pretty_printer *buffer, gimple gs, int spc, int flags)
 476 {
 477   if (flags & TDF_RAW)
 478     {
 479       tree last;
 480       if (gimple_num_ops (gs) == 2)
 481         last = NULL_TREE;
 482       else if (gimple_num_ops (gs) == 3)
 483         last = gimple_assign_rhs2 (gs);
 484       else
 485         gcc_unreachable ();
 486
 487       dump_gimple_fmt (buffer, spc, flags, "%G <%s, %T, %T, %T>", gs,
 488                        tree_code_name[gimple_assign_rhs_code (gs)],
 489                        gimple_assign_lhs (gs), gimple_assign_rhs1 (gs), last);
 490     }
 491   else
 492     {
 493       if (!(flags & TDF_RHS_ONLY))
 494         {
 495           dump_generic_node (buffer, gimple_assign_lhs (gs), spc, flags, false);
 496           pp_space (buffer);
 497           pp_character (buffer, '=');
 498
 499           if (gimple_assign_nontemporal_move_p (gs))
 500             pp_string (buffer, "{nt}");
 501
 502           if (gimple_has_volatile_ops (gs))
 503             pp_string (buffer, "{v}");
 504
 505           pp_space (buffer);
 506         }
 507
 508       if (gimple_num_ops (gs) == 2)
 509         dump_unary_rhs (buffer, gs, spc, flags);
 510       else if (gimple_num_ops (gs) == 3)
 511         dump_binary_rhs (buffer, gs, spc, flags);
 512       else if (gimple_num_ops (gs) == 4)
 513         dump_ternary_rhs (buffer, gs, spc, flags);
 514       else
 515         gcc_unreachable ();
 516       if (!(flags & TDF_RHS_ONLY))
 517         pp_semicolon(buffer);
 518     }
 519 }
 520
 521
 522 /* Dump the return statement GS.  BUFFER, SPC and FLAGS are as in
 523    dump_gimple_stmt.  */
 524
 525 static void
 526 dump_gimple_return (pretty_printer *buffer, gimple gs, int spc, int flags)
 527 {
 528   tree t;
 529
 530   t = gimple_return_retval (gs);
 531   if (flags & TDF_RAW)
 532     dump_gimple_fmt (buffer, spc, flags, "%G <%T>", gs, t);
 533   else
 534     {
 535       pp_string (buffer, "return");
 536       if (t)
 537         {
 538           pp_space (buffer);
 539           dump_generic_node (buffer, t, spc, flags, false);
 540         }
 541       pp_semicolon (buffer);
 542     }
 543 }
 544
 545
 546 /* Dump the call arguments for a gimple call. BUFFER, FLAGS are as in
 547    dump_gimple_call.  */
 548
 549 static void
 550 dump_gimple_call_args (pretty_printer *buffer, gimple gs, int flags)
 551 {
 552   size_t i;
 553
 554   for (i = 0; i < gimple_call_num_args (gs); i++)
 555     {
 556       dump_generic_node (buffer, gimple_call_arg (gs, i), 0, flags, false);
 557       if (i < gimple_call_num_args (gs) - 1)
 558         pp_string (buffer, ", ");
 559     }
 560
 561   if (gimple_call_va_arg_pack_p (gs))
 562     {
 563       if (gimple_call_num_args (gs) > 0)
 564         {
 565           pp_character (buffer, ',');
 566           pp_space (buffer);
 567         }
 568
 569       pp_string (buffer, "__builtin_va_arg_pack ()");
 570     }
 571 }
 572
 573 /* Dump the points-to solution *PT to BUFFER.  */
 574
 575 static void
 576 pp_points_to_solution (pretty_printer *buffer, struct pt_solution *pt)
 577 {
 578   if (pt->anything)
 579     {
 580       pp_string (buffer, "anything ");
 581       return;
 582     }
 583   if (pt->nonlocal)
 584     pp_string (buffer, "nonlocal ");
 585   if (pt->escaped)
 586     pp_string (buffer, "escaped ");
 587   if (pt->ipa_escaped)
 588     pp_string (buffer, "unit-escaped ");
 589   if (pt->null)
 590     pp_string (buffer, "null ");
 591   if (pt->vars
 592       && !bitmap_empty_p (pt->vars))
 593     {
 594       bitmap_iterator bi;
 595       unsigned i;
 596       pp_string (buffer, "{ ");
 597       EXECUTE_IF_SET_IN_BITMAP (pt->vars, 0, i, bi)
 598         {
 599           tree var = referenced_var_lookup (cfun, i);
 600           if (var)
 601             {
 602               dump_generic_node (buffer, var, 0, dump_flags, false);
 603               if (DECL_PT_UID (var) != DECL_UID (var))
 604                 {
 605                   pp_string (buffer, "ptD.");
 606                   pp_decimal_int (buffer, DECL_PT_UID (var));
 607                 }
 608             }
 609           else
 610             {
 611               pp_string (buffer, "D.");
 612               pp_decimal_int (buffer, i);
 613             }
 614           pp_character (buffer, ' ');
 615         }
 616       pp_character (buffer, '}');
 617       if (pt->vars_contains_global)
 618         pp_string (buffer, " (glob)");
 619     }
 620 }
 621
 622 /* Dump the call statement GS.  BUFFER, SPC and FLAGS are as in
 623    dump_gimple_stmt.  */
 624
 625 static void
 626 dump_gimple_call (pretty_printer *buffer, gimple gs, int spc, int flags)
 627 {
 628   tree lhs = gimple_call_lhs (gs);
 629   tree fn = gimple_call_fn (gs);
 630
 631   if (flags & TDF_ALIAS)
 632     {
 633       struct pt_solution *pt;
 634       pt = gimple_call_use_set (gs);
 635       if (!pt_solution_empty_p (pt))
 636         {
 637           pp_string (buffer, "# USE = ");
 638           pp_points_to_solution (buffer, pt);
 639           newline_and_indent (buffer, spc);
 640         }
 641       pt = gimple_call_clobber_set (gs);
 642       if (!pt_solution_empty_p (pt))
 643         {
 644           pp_string (buffer, "# CLB = ");
 645           pp_points_to_solution (buffer, pt);
 646           newline_and_indent (buffer, spc);
 647         }
 648     }
 649
 650   if (flags & TDF_RAW)
 651     {
 652       if (gimple_call_internal_p (gs))
 653         dump_gimple_fmt (buffer, spc, flags, "%G <%s, %T", gs,
 654                          internal_fn_name (gimple_call_internal_fn (gs)), lhs);
 655       else
 656         dump_gimple_fmt (buffer, spc, flags, "%G <%T, %T", gs, fn, lhs);
 657       if (gimple_call_num_args (gs) > 0)
 658         {
 659           pp_string (buffer, ", ");
 660           dump_gimple_call_args (buffer, gs, flags);
 661         }
 662       pp_character (buffer, '>');
 663     }
 664   else
 665     {
 666       if (lhs && !(flags & TDF_RHS_ONLY))
 667         {
 668           dump_generic_node (buffer, lhs, spc, flags, false);
 669           pp_string (buffer, " =");
 670
 671           if (gimple_has_volatile_ops (gs))
 672             pp_string (buffer, "{v}");
 673
 674           pp_space (buffer);
 675         }
 676       if (gimple_call_internal_p (gs))
 677         pp_string (buffer, internal_fn_name (gimple_call_internal_fn (gs)));
 678       else
 679         print_call_name (buffer, fn, flags);
 680       pp_string (buffer, " (");
 681       dump_gimple_call_args (buffer, gs, flags);
 682       pp_character (buffer, ')');
 683       if (!(flags & TDF_RHS_ONLY))
 684         pp_semicolon (buffer);
 685     }
 686
 687   if (gimple_call_chain (gs))
 688     {
 689       pp_string (buffer, " [static-chain: ");
 690       dump_generic_node (buffer, gimple_call_chain (gs), spc, flags, false);
 691       pp_character (buffer, ']');
 692     }
 693
 694   if (gimple_call_return_slot_opt_p (gs))
 695     pp_string (buffer, " [return slot optimization]");
 696   if (gimple_call_tail_p (gs))
 697     pp_string (buffer, " [tail call]");
 698
 699   if (fn == NULL)
 700     return;
 701
 702   /* Dump the arguments of _ITM_beginTransaction sanely.  */
 703   if (TREE_CODE (fn) == ADDR_EXPR)
 704     fn = TREE_OPERAND (fn, 0);
 705   if (TREE_CODE (fn) == FUNCTION_DECL && decl_is_tm_clone (fn))
 706     pp_string (buffer, " [tm-clone]");
 707   if (TREE_CODE (fn) == FUNCTION_DECL
 708       && DECL_BUILT_IN_CLASS (fn) == BUILT_IN_NORMAL
 709       && DECL_FUNCTION_CODE (fn) == BUILT_IN_TM_START
 710       && gimple_call_num_args (gs) > 0)
 711     {
 712       tree t = gimple_call_arg (gs, 0);
 713       unsigned HOST_WIDE_INT props;
 714       gcc_assert (TREE_CODE (t) == INTEGER_CST);
 715
 716       pp_string (buffer, " [ ");
 717
 718       /* Get the transaction code properties.  */
 719       props = TREE_INT_CST_LOW (t);
 720
 721       if (props & PR_INSTRUMENTEDCODE)
 722         pp_string (buffer, "instrumentedCode ");
 723       if (props & PR_UNINSTRUMENTEDCODE)
 724         pp_string (buffer, "uninstrumentedCode ");
 725       if (props & PR_HASNOXMMUPDATE)
 726         pp_string (buffer, "hasNoXMMUpdate ");
 727       if (props & PR_HASNOABORT)
 728         pp_string (buffer, "hasNoAbort ");
 729       if (props & PR_HASNOIRREVOCABLE)
 730         pp_string (buffer, "hasNoIrrevocable ");
 731       if (props & PR_DOESGOIRREVOCABLE)
 732         pp_string (buffer, "doesGoIrrevocable ");
 733       if (props & PR_HASNOSIMPLEREADS)
 734         pp_string (buffer, "hasNoSimpleReads ");
 735       if (props & PR_AWBARRIERSOMITTED)
 736         pp_string (buffer, "awBarriersOmitted ");
 737       if (props & PR_RARBARRIERSOMITTED)
 738         pp_string (buffer, "RaRBarriersOmitted ");
 739       if (props & PR_UNDOLOGCODE)
 740         pp_string (buffer, "undoLogCode ");
 741       if (props & PR_PREFERUNINSTRUMENTED)
 742         pp_string (buffer, "preferUninstrumented ");
 743       if (props & PR_EXCEPTIONBLOCK)
 744         pp_string (buffer, "exceptionBlock ");
 745       if (props & PR_HASELSE)
 746         pp_string (buffer, "hasElse ");
 747       if (props & PR_READONLY)
 748         pp_string (buffer, "readOnly ");
 749
 750       pp_string (buffer, "]");
 751     }
 752 }
 753
 754
 755 /* Dump the switch statement GS.  BUFFER, SPC and FLAGS are as in
 756    dump_gimple_stmt.  */
 757
 758 static void
 759 dump_gimple_switch (pretty_printer *buffer, gimple gs, int spc, int flags)
 760 {
 761   unsigned int i;
 762
 763   GIMPLE_CHECK (gs, GIMPLE_SWITCH);
 764   if (flags & TDF_RAW)
 765     dump_gimple_fmt (buffer, spc, flags, "%G <%T, ", gs,
 766                    gimple_switch_index (gs));
 767   else
 768     {
 769       pp_string (buffer, "switch (");
 770       dump_generic_node (buffer, gimple_switch_index (gs), spc, flags, true);
 771       pp_string (buffer, ") <");
 772     }
 773
 774   for (i = 0; i < gimple_switch_num_labels (gs); i++)
 775     {
 776       tree case_label = gimple_switch_label (gs, i);
 777       if (case_label == NULL_TREE)
 778         continue;
 779
 780       dump_generic_node (buffer, case_label, spc, flags, false);
 781       pp_character (buffer, ' ');
 782       dump_generic_node (buffer, CASE_LABEL (case_label), spc, flags, false);
 783       if (i < gimple_switch_num_labels (gs) - 1)
 784         pp_string (buffer, ", ");
 785     }
 786   pp_character (buffer, '>');
 787 }
 788
 789
 790 /* Dump the gimple conditional GS.  BUFFER, SPC and FLAGS are as in
 791    dump_gimple_stmt.  */
 792
 793 static void
 794 dump_gimple_cond (pretty_printer *buffer, gimple gs, int spc, int flags)
 795 {
 796   if (flags & TDF_RAW)
 797     dump_gimple_fmt (buffer, spc, flags, "%G <%s, %T, %T, %T, %T>", gs,
 798                    tree_code_name [gimple_cond_code (gs)],
 799                    gimple_cond_lhs (gs), gimple_cond_rhs (gs),
 800                    gimple_cond_true_label (gs), gimple_cond_false_label (gs));
 801   else
 802     {
 803       if (!(flags & TDF_RHS_ONLY))
 804         pp_string (buffer, "if (");
 805       dump_generic_node (buffer, gimple_cond_lhs (gs), spc, flags, false);
 806       pp_space (buffer);
 807       pp_string (buffer, op_symbol_code (gimple_cond_code (gs)));
 808       pp_space (buffer);
 809       dump_generic_node (buffer, gimple_cond_rhs (gs), spc, flags, false);
 810       if (!(flags & TDF_RHS_ONLY))
 811         {
 812           pp_character (buffer, ')');
 813
 814           if (gimple_cond_true_label (gs))
 815             {
 816               pp_string (buffer, " goto ");
 817               dump_generic_node (buffer, gimple_cond_true_label (gs),
 818                                  spc, flags, false);
 819               pp_semicolon (buffer);
 820             }
 821           if (gimple_cond_false_label (gs))
 822             {
 823               pp_string (buffer, " else goto ");
 824               dump_generic_node (buffer, gimple_cond_false_label (gs),
 825                                  spc, flags, false);
 826               pp_semicolon (buffer);
 827             }
 828         }
 829     }
 830 }
 831
 832
 833 /* Dump a GIMPLE_LABEL tuple on the pretty_printer BUFFER, SPC
 834    spaces of indent.  FLAGS specifies details to show in the dump (see
 835    TDF_* in tree-pass.h).  */
 836
 837 static void
 838 dump_gimple_label (pretty_printer *buffer, gimple gs, int spc, int flags)
 839 {
 840   tree label = gimple_label_label (gs);
 841   if (flags & TDF_RAW)
 842       dump_gimple_fmt (buffer, spc, flags, "%G <%T>", gs, label);
 843   else
 844     {
 845       dump_generic_node (buffer, label, spc, flags, false);
 846       pp_character (buffer, ':');
 847     }
 848   if (DECL_NONLOCAL (label))
 849     pp_string (buffer, " [non-local]");
 850   if ((flags & TDF_EH) && EH_LANDING_PAD_NR (label))
 851     pp_printf (buffer, " [LP %d]", EH_LANDING_PAD_NR (label));
 852 }
 853
 854 /* Dump a GIMPLE_GOTO tuple on the pretty_printer BUFFER, SPC
 855    spaces of indent.  FLAGS specifies details to show in the dump (see
 856    TDF_* in tree-pass.h).  */
 857
 858 static void
 859 dump_gimple_goto (pretty_printer *buffer, gimple gs, int spc, int flags)
 860 {
 861   tree label = gimple_goto_dest (gs);
 862   if (flags & TDF_RAW)
 863     dump_gimple_fmt (buffer, spc, flags, "%G <%T>", gs, label);
 864   else
 865     dump_gimple_fmt (buffer, spc, flags, "goto %T;", label);
 866 }
 867
 868
 869 /* Dump a GIMPLE_BIND tuple on the pretty_printer BUFFER, SPC
 870    spaces of indent.  FLAGS specifies details to show in the dump (see
 871    TDF_* in tree-pass.h).  */
 872
 873 static void
 874 dump_gimple_bind (pretty_printer *buffer, gimple gs, int spc, int flags)
 875 {
 876   if (flags & TDF_RAW)
 877     dump_gimple_fmt (buffer, spc, flags, "%G <", gs);
 878   else
 879     pp_character (buffer, '{');
 880   if (!(flags & TDF_SLIM))
 881     {
 882       tree var;
 883
 884       for (var = gimple_bind_vars (gs); var; var = DECL_CHAIN (var))
 885         {
 886           newline_and_indent (buffer, 2);
 887           print_declaration (buffer, var, spc, flags);
 888         }
 889       if (gimple_bind_vars (gs))
 890         pp_newline (buffer);
 891     }
 892   pp_newline (buffer);
 893   dump_gimple_seq (buffer, gimple_bind_body (gs), spc + 2, flags);
 894   newline_and_indent (buffer, spc);
 895   if (flags & TDF_RAW)
 896     pp_character (buffer, '>');
 897   else
 898     pp_character (buffer, '}');
 899 }
 900
 901
 902 /* Dump a GIMPLE_TRY tuple on the pretty_printer BUFFER, SPC spaces of
 903    indent.  FLAGS specifies details to show in the dump (see TDF_* in
 904    tree-pass.h).  */
 905
 906 static void
 907 dump_gimple_try (pretty_printer *buffer, gimple gs, int spc, int flags)
 908 {
 909   if (flags & TDF_RAW)
 910     {
 911       const char *type;
 912       if (gimple_try_kind (gs) == GIMPLE_TRY_CATCH)
 913         type = "GIMPLE_TRY_CATCH";
 914       else if (gimple_try_kind (gs) == GIMPLE_TRY_FINALLY)
 915         type = "GIMPLE_TRY_FINALLY";
 916       else
 917         type = "UNKNOWN GIMPLE_TRY";
 918       dump_gimple_fmt (buffer, spc, flags,
 919                        "%G <%s,%+EVAL <%S>%nCLEANUP <%S>%->", gs, type,
 920                        gimple_try_eval (gs), gimple_try_cleanup (gs));
 921     }
 922   else
 923     {
 924       pp_string (buffer, "try");
 925       newline_and_indent (buffer, spc + 2);
 926       pp_character (buffer, '{');
 927       pp_newline (buffer);
 928
 929       dump_gimple_seq (buffer, gimple_try_eval (gs), spc + 4, flags);
 930       newline_and_indent (buffer, spc + 2);
 931       pp_character (buffer, '}');
 932
 933       if (gimple_try_kind (gs) == GIMPLE_TRY_CATCH)
 934         {
 935           newline_and_indent (buffer, spc);
 936           pp_string (buffer, "catch");
 937           newline_and_indent (buffer, spc + 2);
 938           pp_character (buffer, '{');
 939         }
 940       else if (gimple_try_kind (gs) == GIMPLE_TRY_FINALLY)
 941         {
 942           newline_and_indent (buffer, spc);
 943           pp_string (buffer, "finally");
 944           newline_and_indent (buffer, spc + 2);
 945           pp_character (buffer, '{');
 946         }
 947       else
 948         pp_string (buffer, " <UNKNOWN GIMPLE_TRY> {");
 949
 950       pp_newline (buffer);
 951       dump_gimple_seq (buffer, gimple_try_cleanup (gs), spc + 4, flags);
 952       newline_and_indent (buffer, spc + 2);
 953       pp_character (buffer, '}');
 954     }
 955 }
 956
 957
 958 /* Dump a GIMPLE_CATCH tuple on the pretty_printer BUFFER, SPC spaces of
 959    indent.  FLAGS specifies details to show in the dump (see TDF_* in
 960    tree-pass.h).  */
 961
 962 static void
 963 dump_gimple_catch (pretty_printer *buffer, gimple gs, int spc, int flags)
 964 {
 965   if (flags & TDF_RAW)
 966       dump_gimple_fmt (buffer, spc, flags, "%G <%T, %+CATCH <%S>%->", gs,
 967                        gimple_catch_types (gs), gimple_catch_handler (gs));
 968   else
 969       dump_gimple_fmt (buffer, spc, flags, "catch (%T)%+{%S}",
 970                        gimple_catch_types (gs), gimple_catch_handler (gs));
 971 }
 972
 973
 974 /* Dump a GIMPLE_EH_FILTER tuple on the pretty_printer BUFFER, SPC spaces of
 975    indent.  FLAGS specifies details to show in the dump (see TDF_* in
 976    tree-pass.h).  */
 977
 978 static void
 979 dump_gimple_eh_filter (pretty_printer *buffer, gimple gs, int spc, int flags)
 980 {
 981   if (flags & TDF_RAW)
 982     dump_gimple_fmt (buffer, spc, flags, "%G <%T, %+FAILURE <%S>%->", gs,
 983                      gimple_eh_filter_types (gs),
 984                      gimple_eh_filter_failure (gs));
 985   else
 986     dump_gimple_fmt (buffer, spc, flags, "<<<eh_filter (%T)>>>%+{%+%S%-}",
 987                      gimple_eh_filter_types (gs),
 988                      gimple_eh_filter_failure (gs));
 989 }
 990
 991
 992 /* Dump a GIMPLE_EH_MUST_NOT_THROW tuple.  */
 993
 994 static void
 995 dump_gimple_eh_must_not_throw (pretty_printer *buffer, gimple gs,
 996                                int spc, int flags)
 997 {
 998   if (flags & TDF_RAW)
 999     dump_gimple_fmt (buffer, spc, flags, "%G <%T>", gs,
1000                      gimple_eh_must_not_throw_fndecl (gs));
1001   else
1002     dump_gimple_fmt (buffer, spc, flags, "<<<eh_must_not_throw (%T)>>>",
1003                      gimple_eh_must_not_throw_fndecl (gs));
1004 }
1005
1006
1007 /* Dump a GIMPLE_EH_ELSE tuple on the pretty_printer BUFFER, SPC spaces of
1008    indent.  FLAGS specifies details to show in the dump (see TDF_* in
1009    tree-pass.h).  */
1010
1011 static void
1012 dump_gimple_eh_else (pretty_printer *buffer, gimple gs, int spc, int flags)
1013 {
1014   if (flags & TDF_RAW)
1015     dump_gimple_fmt (buffer, spc, flags,
1016                      "%G <%+N_BODY <%S>%nE_BODY <%S>%->", gs,
1017                      gimple_eh_else_n_body (gs), gimple_eh_else_e_body (gs));
1018   else
1019     dump_gimple_fmt (buffer, spc, flags,
1020                     "<<<if_normal_exit>>>%+{%S}%-<<<else_eh_exit>>>%+{%S}",
1021                      gimple_eh_else_n_body (gs), gimple_eh_else_e_body (gs));
1022 }
1023
1024
1025 /* Dump a GIMPLE_RESX tuple on the pretty_printer BUFFER, SPC spaces of
1026    indent.  FLAGS specifies details to show in the dump (see TDF_* in
1027    tree-pass.h).  */
1028
1029 static void
1030 dump_gimple_resx (pretty_printer *buffer, gimple gs, int spc, int flags)
1031 {
1032   if (flags & TDF_RAW)
1033     dump_gimple_fmt (buffer, spc, flags, "%G <%d>", gs,
1034                      gimple_resx_region (gs));
1035   else
1036     dump_gimple_fmt (buffer, spc, flags, "resx %d", gimple_resx_region (gs));
1037 }
1038
1039 /* Dump a GIMPLE_EH_DISPATCH tuple on the pretty_printer BUFFER.  */
1040
1041 static void
1042 dump_gimple_eh_dispatch (pretty_printer *buffer, gimple gs, int spc, int flags)
1043 {
1044   if (flags & TDF_RAW)
1045     dump_gimple_fmt (buffer, spc, flags, "%G <%d>", gs,
1046                      gimple_eh_dispatch_region (gs));
1047   else
1048     dump_gimple_fmt (buffer, spc, flags, "eh_dispatch %d",
1049                      gimple_eh_dispatch_region (gs));
1050 }
1051
1052 /* Dump a GIMPLE_DEBUG tuple on the pretty_printer BUFFER, SPC spaces
1053    of indent.  FLAGS specifies details to show in the dump (see TDF_*
1054    in tree-pass.h).  */
1055
1056 static void
1057 dump_gimple_debug (pretty_printer *buffer, gimple gs, int spc, int flags)
1058 {
1059   switch (gs->gsbase.subcode)
1060     {
1061     case GIMPLE_DEBUG_BIND:
1062       if (flags & TDF_RAW)
1063         dump_gimple_fmt (buffer, spc, flags, "%G BIND <%T, %T>", gs,
1064                          gimple_debug_bind_get_var (gs),
1065                          gimple_debug_bind_get_value (gs));
1066       else
1067         dump_gimple_fmt (buffer, spc, flags, "# DEBUG %T => %T",
1068                          gimple_debug_bind_get_var (gs),
1069                          gimple_debug_bind_get_value (gs));
1070       break;
1071
1072     case GIMPLE_DEBUG_SOURCE_BIND:
1073       if (flags & TDF_RAW)
1074         dump_gimple_fmt (buffer, spc, flags, "%G SRCBIND <%T, %T>", gs,
1075                          gimple_debug_source_bind_get_var (gs),
1076                          gimple_debug_source_bind_get_value (gs));
1077       else
1078         dump_gimple_fmt (buffer, spc, flags, "# DEBUG %T s=> %T",
1079                          gimple_debug_source_bind_get_var (gs),
1080                          gimple_debug_source_bind_get_value (gs));
1081       break;
1082
1083     default:
1084       gcc_unreachable ();
1085     }
1086 }
1087
1088 /* Dump a GIMPLE_OMP_FOR tuple on the pretty_printer BUFFER.  */
1089 static void
1090 dump_gimple_omp_for (pretty_printer *buffer, gimple gs, int spc, int flags)
1091 {
1092   size_t i;
1093
1094   if (flags & TDF_RAW)
1095     {
1096       dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S>%nCLAUSES <", gs,
1097                        gimple_omp_body (gs));
1098       dump_omp_clauses (buffer, gimple_omp_for_clauses (gs), spc, flags);
1099       dump_gimple_fmt (buffer, spc, flags, " >,");
1100       for (i = 0; i < gimple_omp_for_collapse (gs); i++)
1101         dump_gimple_fmt (buffer, spc, flags,
1102                          "%+%T, %T, %T, %s, %T,%n",
1103                          gimple_omp_for_index (gs, i),
1104                          gimple_omp_for_initial (gs, i),
1105                          gimple_omp_for_final (gs, i),
1106                          tree_code_name[gimple_omp_for_cond (gs, i)],
1107                          gimple_omp_for_incr (gs, i));
1108       dump_gimple_fmt (buffer, spc, flags, "PRE_BODY <%S>%->",
1109                        gimple_omp_for_pre_body (gs));
1110     }
1111   else
1112     {
1113       pp_string (buffer, "#pragma omp for");
1114       dump_omp_clauses (buffer, gimple_omp_for_clauses (gs), spc, flags);
1115       for (i = 0; i < gimple_omp_for_collapse (gs); i++)
1116         {
1117           if (i)
1118             spc += 2;
1119           newline_and_indent (buffer, spc);
1120           pp_string (buffer, "for (");
1121           dump_generic_node (buffer, gimple_omp_for_index (gs, i), spc,
1122                              flags, false);
1123           pp_string (buffer, " = ");
1124           dump_generic_node (buffer, gimple_omp_for_initial (gs, i), spc,
1125                              flags, false);
1126           pp_string (buffer, "; ");
1127
1128           dump_generic_node (buffer, gimple_omp_for_index (gs, i), spc,
1129                              flags, false);
1130           pp_space (buffer);
1131           switch (gimple_omp_for_cond (gs, i))
1132             {
1133             case LT_EXPR:
1134               pp_character (buffer, '<');
1135               break;
1136             case GT_EXPR:
1137               pp_character (buffer, '>');
1138               break;
1139             case LE_EXPR:
1140               pp_string (buffer, "<=");
1141               break;
1142             case GE_EXPR:
1143               pp_string (buffer, ">=");
1144               break;
1145             default:
1146               gcc_unreachable ();
1147             }
1148           pp_space (buffer);
1149           dump_generic_node (buffer, gimple_omp_for_final (gs, i), spc,
1150                              flags, false);
1151           pp_string (buffer, "; ");
1152
1153           dump_generic_node (buffer, gimple_omp_for_index (gs, i), spc,
1154                              flags, false);
1155           pp_string (buffer, " = ");
1156           dump_generic_node (buffer, gimple_omp_for_incr (gs, i), spc,
1157                              flags, false);
1158           pp_character (buffer, ')');
1159         }
1160
1161       if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1162         {
1163           newline_and_indent (buffer, spc + 2);
1164           pp_character (buffer, '{');
1165           pp_newline (buffer);
1166           dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1167           newline_and_indent (buffer, spc + 2);
1168           pp_character (buffer, '}');
1169         }
1170     }
1171 }
1172
1173 /* Dump a GIMPLE_OMP_CONTINUE tuple on the pretty_printer BUFFER.  */
1174
1175 static void
1176 dump_gimple_omp_continue (pretty_printer *buffer, gimple gs, int spc, int flags)
1177 {
1178   if (flags & TDF_RAW)
1179     {
1180       dump_gimple_fmt (buffer, spc, flags, "%G <%T, %T>", gs,
1181                        gimple_omp_continue_control_def (gs),
1182                        gimple_omp_continue_control_use (gs));
1183     }
1184   else
1185     {
1186       pp_string (buffer, "#pragma omp continue (");
1187       dump_generic_node (buffer, gimple_omp_continue_control_def (gs),
1188                          spc, flags, false);
1189       pp_character (buffer, ',');
1190       pp_space (buffer);
1191       dump_generic_node (buffer, gimple_omp_continue_control_use (gs),
1192                          spc, flags, false);
1193       pp_character (buffer, ')');
1194     }
1195 }
1196
1197 /* Dump a GIMPLE_OMP_SINGLE tuple on the pretty_printer BUFFER.  */
1198
1199 static void
1200 dump_gimple_omp_single (pretty_printer *buffer, gimple gs, int spc, int flags)
1201 {
1202   if (flags & TDF_RAW)
1203     {
1204       dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S>%nCLAUSES <", gs,
1205                        gimple_omp_body (gs));
1206       dump_omp_clauses (buffer, gimple_omp_single_clauses (gs), spc, flags);
1207       dump_gimple_fmt (buffer, spc, flags, " >");
1208     }
1209   else
1210     {
1211       pp_string (buffer, "#pragma omp single");
1212       dump_omp_clauses (buffer, gimple_omp_single_clauses (gs), spc, flags);
1213       if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1214         {
1215           newline_and_indent (buffer, spc + 2);
1216           pp_character (buffer, '{');
1217           pp_newline (buffer);
1218           dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1219           newline_and_indent (buffer, spc + 2);
1220           pp_character (buffer, '}');
1221         }
1222     }
1223 }
1224
1225 /* Dump a GIMPLE_OMP_SECTIONS tuple on the pretty_printer BUFFER.  */
1226
1227 static void
1228 dump_gimple_omp_sections (pretty_printer *buffer, gimple gs, int spc,
1229                           int flags)
1230 {
1231   if (flags & TDF_RAW)
1232     {
1233       dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S>%nCLAUSES <", gs,
1234                        gimple_omp_body (gs));
1235       dump_omp_clauses (buffer, gimple_omp_sections_clauses (gs), spc, flags);
1236       dump_gimple_fmt (buffer, spc, flags, " >");
1237     }
1238   else
1239     {
1240       pp_string (buffer, "#pragma omp sections");
1241       if (gimple_omp_sections_control (gs))
1242         {
1243           pp_string (buffer, " <");
1244           dump_generic_node (buffer, gimple_omp_sections_control (gs), spc,
1245                              flags, false);
1246           pp_character (buffer, '>');
1247         }
1248       dump_omp_clauses (buffer, gimple_omp_sections_clauses (gs), spc, flags);
1249       if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1250         {
1251           newline_and_indent (buffer, spc + 2);
1252           pp_character (buffer, '{');
1253           pp_newline (buffer);
1254           dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1255           newline_and_indent (buffer, spc + 2);
1256           pp_character (buffer, '}');
1257         }
1258     }
1259 }
1260
1261 /* Dump a GIMPLE_OMP_{MASTER,ORDERED,SECTION} tuple on the pretty_printer
1262    BUFFER.  */
1263
1264 static void
1265 dump_gimple_omp_block (pretty_printer *buffer, gimple gs, int spc, int flags)
1266 {
1267   if (flags & TDF_RAW)
1268     dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S> >", gs,
1269                      gimple_omp_body (gs));
1270   else
1271     {
1272       switch (gimple_code (gs))
1273         {
1274         case GIMPLE_OMP_MASTER:
1275           pp_string (buffer, "#pragma omp master");
1276           break;
1277         case GIMPLE_OMP_ORDERED:
1278           pp_string (buffer, "#pragma omp ordered");
1279           break;
1280         case GIMPLE_OMP_SECTION:
1281           pp_string (buffer, "#pragma omp section");
1282           break;
1283         default:
1284           gcc_unreachable ();
1285         }
1286       if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1287         {
1288           newline_and_indent (buffer, spc + 2);
1289           pp_character (buffer, '{');
1290           pp_newline (buffer);
1291           dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1292           newline_and_indent (buffer, spc + 2);
1293           pp_character (buffer, '}');
1294         }
1295     }
1296 }
1297
1298 /* Dump a GIMPLE_OMP_CRITICAL tuple on the pretty_printer BUFFER.  */
1299
1300 static void
1301 dump_gimple_omp_critical (pretty_printer *buffer, gimple gs, int spc,
1302                           int flags)
1303 {
1304   if (flags & TDF_RAW)
1305     dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S> >", gs,
1306                      gimple_omp_body (gs));
1307   else
1308     {
1309       pp_string (buffer, "#pragma omp critical");
1310       if (gimple_omp_critical_name (gs))
1311         {
1312           pp_string (buffer, " (");
1313           dump_generic_node (buffer, gimple_omp_critical_name (gs), spc,
1314                              flags, false);
1315           pp_character (buffer, ')');
1316         }
1317       if (!gimple_seq_empty_p (gimple_omp_body (gs)))
1318         {
1319           newline_and_indent (buffer, spc + 2);
1320           pp_character (buffer, '{');
1321           pp_newline (buffer);
1322           dump_gimple_seq (buffer, gimple_omp_body (gs), spc + 4, flags);
1323           newline_and_indent (buffer, spc + 2);
1324           pp_character (buffer, '}');
1325         }
1326     }
1327 }
1328
1329 /* Dump a GIMPLE_OMP_RETURN tuple on the pretty_printer BUFFER.  */
1330
1331 static void
1332 dump_gimple_omp_return (pretty_printer *buffer, gimple gs, int spc, int flags)
1333 {
1334   if (flags & TDF_RAW)
1335     {
1336       dump_gimple_fmt (buffer, spc, flags, "%G <nowait=%d>", gs,
1337                        (int) gimple_omp_return_nowait_p (gs));
1338     }
1339   else
1340     {
1341       pp_string (buffer, "#pragma omp return");
1342       if (gimple_omp_return_nowait_p (gs))
1343         pp_string (buffer, "(nowait)");
1344     }
1345 }
1346
1347 /* Dump a GIMPLE_TRANSACTION tuple on the pretty_printer BUFFER.  */
1348
1349 static void
1350 dump_gimple_transaction (pretty_printer *buffer, gimple gs, int spc, int flags)
1351 {
1352   unsigned subcode = gimple_transaction_subcode (gs);
1353
1354   if (flags & TDF_RAW)
1355     {
1356       dump_gimple_fmt (buffer, spc, flags,
1357                        "%G [SUBCODE=%x,LABEL=%T] <%+BODY <%S> >",
1358                        gs, subcode, gimple_transaction_label (gs),
1359                        gimple_transaction_body (gs));
1360     }
1361   else
1362     {
1363       if (subcode & GTMA_IS_OUTER)
1364         pp_string (buffer, "__transaction_atomic [[outer]]");
1365       else if (subcode & GTMA_IS_RELAXED)
1366         pp_string (buffer, "__transaction_relaxed");
1367       else
1368         pp_string (buffer, "__transaction_atomic");
1369       subcode &= ~GTMA_DECLARATION_MASK;
1370
1371       if (subcode || gimple_transaction_label (gs))
1372         {
1373           pp_string (buffer, "  //");
1374           if (gimple_transaction_label (gs))
1375             {
1376               pp_string (buffer, " LABEL=");
1377               dump_generic_node (buffer, gimple_transaction_label (gs),
1378                                  spc, flags, false);
1379             }
1380           if (subcode)
1381             {
1382               pp_string (buffer, " SUBCODE=[ ");
1383               if (subcode & GTMA_HAVE_ABORT)
1384                 {
1385                   pp_string (buffer, "GTMA_HAVE_ABORT ");
1386                   subcode &= ~GTMA_HAVE_ABORT;
1387                 }
1388               if (subcode & GTMA_HAVE_LOAD)
1389                 {
1390                   pp_string (buffer, "GTMA_HAVE_LOAD ");
1391                   subcode &= ~GTMA_HAVE_LOAD;
1392                 }
1393               if (subcode & GTMA_HAVE_STORE)
1394                 {
1395                   pp_string (buffer, "GTMA_HAVE_STORE ");
1396                   subcode &= ~GTMA_HAVE_STORE;
1397                 }
1398               if (subcode & GTMA_MAY_ENTER_IRREVOCABLE)
1399                 {
1400                   pp_string (buffer, "GTMA_MAY_ENTER_IRREVOCABLE ");
1401                   subcode &= ~GTMA_MAY_ENTER_IRREVOCABLE;
1402                 }
1403               if (subcode & GTMA_DOES_GO_IRREVOCABLE)
1404                 {
1405                   pp_string (buffer, "GTMA_DOES_GO_IRREVOCABLE ");
1406                   subcode &= ~GTMA_DOES_GO_IRREVOCABLE;
1407                 }
1408               if (subcode)
1409                 pp_printf (buffer, "0x%x ", subcode);
1410               pp_string (buffer, "]");
1411             }
1412         }
1413
1414       if (!gimple_seq_empty_p (gimple_transaction_body (gs)))
1415         {
1416           newline_and_indent (buffer, spc + 2);
1417           pp_character (buffer, '{');
1418           pp_newline (buffer);
1419           dump_gimple_seq (buffer, gimple_transaction_body (gs),
1420                            spc + 4, flags);
1421           newline_and_indent (buffer, spc + 2);
1422           pp_character (buffer, '}');
1423         }
1424     }
1425 }
1426
1427 /* Dump a GIMPLE_ASM tuple on the pretty_printer BUFFER, SPC spaces of
1428    indent.  FLAGS specifies details to show in the dump (see TDF_* in
1429    tree-pass.h).  */
1430
1431 static void
1432 dump_gimple_asm (pretty_printer *buffer, gimple gs, int spc, int flags)
1433 {
1434   unsigned int i, n, f, fields;
1435
1436   if (flags & TDF_RAW)
1437     {
1438       dump_gimple_fmt (buffer, spc, flags, "%G <%+STRING <%n%s%n>", gs,
1439                        gimple_asm_string (gs));
1440
1441       n = gimple_asm_noutputs (gs);
1442       if (n)
1443         {
1444           newline_and_indent (buffer, spc + 2);
1445           pp_string (buffer, "OUTPUT: ");
1446           for (i = 0; i < n; i++)
1447             {
1448               dump_generic_node (buffer, gimple_asm_output_op (gs, i),
1449                                  spc, flags, false);
1450               if (i < n - 1)
1451                 pp_string (buffer, ", ");
1452             }
1453         }
1454
1455       n = gimple_asm_ninputs (gs);
1456       if (n)
1457         {
1458           newline_and_indent (buffer, spc + 2);
1459           pp_string (buffer, "INPUT: ");
1460           for (i = 0; i < n; i++)
1461             {
1462               dump_generic_node (buffer, gimple_asm_input_op (gs, i),
1463                                  spc, flags, false);
1464               if (i < n - 1)
1465                 pp_string (buffer, ", ");
1466             }
1467         }
1468
1469       n = gimple_asm_nclobbers (gs);
1470       if (n)
1471         {
1472           newline_and_indent (buffer, spc + 2);
1473           pp_string (buffer, "CLOBBER: ");
1474           for (i = 0; i < n; i++)
1475             {
1476               dump_generic_node (buffer, gimple_asm_clobber_op (gs, i),
1477                                  spc, flags, false);
1478               if (i < n - 1)
1479                 pp_string (buffer, ", ");
1480             }
1481         }
1482
1483       n = gimple_asm_nlabels (gs);
1484       if (n)
1485         {
1486           newline_and_indent (buffer, spc + 2);
1487           pp_string (buffer, "LABEL: ");
1488           for (i = 0; i < n; i++)
1489             {
1490               dump_generic_node (buffer, gimple_asm_label_op (gs, i),
1491                                  spc, flags, false);
1492               if (i < n - 1)
1493                 pp_string (buffer, ", ");
1494             }
1495         }
1496
1497       newline_and_indent (buffer, spc);
1498       pp_character (buffer, '>');
1499     }
1500   else
1501     {
1502       pp_string (buffer, "__asm__");
1503       if (gimple_asm_volatile_p (gs))
1504         pp_string (buffer, " __volatile__");
1505       if (gimple_asm_nlabels (gs))
1506         pp_string (buffer, " goto");
1507       pp_string (buffer, "(\"");
1508       pp_string (buffer, gimple_asm_string (gs));
1509       pp_string (buffer, "\"");
1510
1511       if (gimple_asm_nlabels (gs))
1512         fields = 4;
1513       else if (gimple_asm_nclobbers (gs))
1514         fields = 3;
1515       else if (gimple_asm_ninputs (gs))
1516         fields = 2;
1517       else if (gimple_asm_noutputs (gs))
1518         fields = 1;
1519       else
1520         fields = 0;
1521
1522       for (f = 0; f < fields; ++f)
1523         {
1524           pp_string (buffer, " : ");
1525
1526           switch (f)
1527             {
1528             case 0:
1529               n = gimple_asm_noutputs (gs);
1530               for (i = 0; i < n; i++)
1531                 {
1532                   dump_generic_node (buffer, gimple_asm_output_op (gs, i),
1533                                      spc, flags, false);
1534                   if (i < n - 1)
1535                     pp_string (buffer, ", ");
1536                 }
1537               break;
1538
1539             case 1:
1540               n = gimple_asm_ninputs (gs);
1541               for (i = 0; i < n; i++)
1542                 {
1543                   dump_generic_node (buffer, gimple_asm_input_op (gs, i),
1544                                      spc, flags, false);
1545                   if (i < n - 1)
1546                     pp_string (buffer, ", ");
1547                 }
1548               break;
1549
1550             case 2:
1551               n = gimple_asm_nclobbers (gs);
1552               for (i = 0; i < n; i++)
1553                 {
1554                   dump_generic_node (buffer, gimple_asm_clobber_op (gs, i),
1555                                      spc, flags, false);
1556                   if (i < n - 1)
1557                     pp_string (buffer, ", ");
1558                 }
1559               break;
1560
1561             case 3:
1562               n = gimple_asm_nlabels (gs);
1563               for (i = 0; i < n; i++)
1564                 {
1565                   dump_generic_node (buffer, gimple_asm_label_op (gs, i),
1566                                      spc, flags, false);
1567                   if (i < n - 1)
1568                     pp_string (buffer, ", ");
1569                 }
1570               break;
1571
1572             default:
1573               gcc_unreachable ();
1574             }
1575         }
1576
1577       pp_string (buffer, ");");
1578     }
1579 }
1580
1581
1582 /* Dump a PHI node PHI.  BUFFER, SPC and FLAGS are as in
1583    dump_gimple_stmt.  */
1584
1585 static void
1586 dump_gimple_phi (pretty_printer *buffer, gimple phi, int spc, int flags)
1587 {
1588   size_t i;
1589   tree lhs = gimple_phi_result (phi);
1590
1591   if (flags & TDF_ALIAS
1592       && POINTER_TYPE_P (TREE_TYPE (lhs))
1593       && SSA_NAME_PTR_INFO (lhs))
1594     {
1595       unsigned int align, misalign;
1596       struct ptr_info_def *pi = SSA_NAME_PTR_INFO (lhs);
1597       pp_string (buffer, "PT = ");
1598       pp_points_to_solution (buffer, &pi->pt);
1599       newline_and_indent (buffer, spc);
1600       if (get_ptr_info_alignment (pi, &align, &misalign))
1601         {
1602           pp_printf (buffer, "# ALIGN = %u, MISALIGN = %u", align, misalign);
1603           newline_and_indent (buffer, spc);
1604         }
1605       pp_string (buffer, "# ");
1606     }
1607
1608   if (flags & TDF_RAW)
1609       dump_gimple_fmt (buffer, spc, flags, "%G <%T, ", phi,
1610                        gimple_phi_result (phi));
1611   else
1612     {
1613       dump_generic_node (buffer, lhs, spc, flags, false);
1614       pp_string (buffer, " = PHI <");
1615     }
1616   for (i = 0; i < gimple_phi_num_args (phi); i++)
1617     {
1618       if ((flags & TDF_LINENO) && gimple_phi_arg_has_location (phi, i))
1619         {
1620           expanded_location xloc;
1621
1622           xloc = expand_location (gimple_phi_arg_location (phi, i));
1623           pp_character (buffer, '[');
1624           if (xloc.file)
1625             {
1626               pp_string (buffer, xloc.file);
1627               pp_string (buffer, " : ");
1628             }
1629           pp_decimal_int (buffer, xloc.line);
1630           pp_string (buffer, ":");
1631           pp_decimal_int (buffer, xloc.column);
1632           pp_string (buffer, "] ");
1633         }
1634       dump_generic_node (buffer, gimple_phi_arg_def (phi, i), spc, flags,
1635                          false);
1636       pp_character (buffer, '(');
1637       pp_decimal_int (buffer, gimple_phi_arg_edge (phi, i)->src->index);
1638       pp_character (buffer, ')');
1639       if (i < gimple_phi_num_args (phi) - 1)
1640         pp_string (buffer, ", ");
1641     }
1642   pp_character (buffer, '>');
1643 }
1644
1645
1646 /* Dump a GIMPLE_OMP_PARALLEL tuple on the pretty_printer BUFFER, SPC spaces
1647    of indent.  FLAGS specifies details to show in the dump (see TDF_* in
1648    tree-pass.h).  */
1649
1650 static void
1651 dump_gimple_omp_parallel (pretty_printer *buffer, gimple gs, int spc,
1652                           int flags)
1653 {
1654   if (flags & TDF_RAW)
1655     {
1656       dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S>%nCLAUSES <", gs,
1657                        gimple_omp_body (gs));
1658       dump_omp_clauses (buffer, gimple_omp_parallel_clauses (gs), spc, flags);
1659       dump_gimple_fmt (buffer, spc, flags, " >, %T, %T%n>",
1660                        gimple_omp_parallel_child_fn (gs),
1661                        gimple_omp_parallel_data_arg (gs));
1662     }
1663   else
1664     {
1665       gimple_seq body;
1666       pp_string (buffer, "#pragma omp parallel");
1667       dump_omp_clauses (buffer, gimple_omp_parallel_clauses (gs), spc, flags);
1668       if (gimple_omp_parallel_child_fn (gs))
1669         {
1670           pp_string (buffer, " [child fn: ");
1671           dump_generic_node (buffer, gimple_omp_parallel_child_fn (gs),
1672                              spc, flags, false);
1673           pp_string (buffer, " (");
1674           if (gimple_omp_parallel_data_arg (gs))
1675             dump_generic_node (buffer, gimple_omp_parallel_data_arg (gs),
1676                                spc, flags, false);
1677           else
1678             pp_string (buffer, "???");
1679           pp_string (buffer, ")]");
1680         }
1681       body = gimple_omp_body (gs);
1682       if (body && gimple_code (gimple_seq_first_stmt (body)) != GIMPLE_BIND)
1683         {
1684           newline_and_indent (buffer, spc + 2);
1685           pp_character (buffer, '{');
1686           pp_newline (buffer);
1687           dump_gimple_seq (buffer, body, spc + 4, flags);
1688           newline_and_indent (buffer, spc + 2);
1689           pp_character (buffer, '}');
1690         }
1691       else if (body)
1692         {
1693           pp_newline (buffer);
1694           dump_gimple_seq (buffer, body, spc + 2, flags);
1695         }
1696     }
1697 }
1698
1699
1700 /* Dump a GIMPLE_OMP_TASK tuple on the pretty_printer BUFFER, SPC spaces
1701    of indent.  FLAGS specifies details to show in the dump (see TDF_* in
1702    tree-pass.h).  */
1703
1704 static void
1705 dump_gimple_omp_task (pretty_printer *buffer, gimple gs, int spc,
1706                       int flags)
1707 {
1708   if (flags & TDF_RAW)
1709     {
1710       dump_gimple_fmt (buffer, spc, flags, "%G <%+BODY <%S>%nCLAUSES <", gs,
1711                        gimple_omp_body (gs));
1712       dump_omp_clauses (buffer, gimple_omp_task_clauses (gs), spc, flags);
1713       dump_gimple_fmt (buffer, spc, flags, " >, %T, %T, %T, %T, %T%n>",
1714                        gimple_omp_task_child_fn (gs),
1715                        gimple_omp_task_data_arg (gs),
1716                        gimple_omp_task_copy_fn (gs),
1717                        gimple_omp_task_arg_size (gs),
1718                        gimple_omp_task_arg_size (gs));
1719     }
1720   else
1721     {
1722       gimple_seq body;
1723       pp_string (buffer, "#pragma omp task");
1724       dump_omp_clauses (buffer, gimple_omp_task_clauses (gs), spc, flags);
1725       if (gimple_omp_task_child_fn (gs))
1726         {
1727           pp_string (buffer, " [child fn: ");
1728           dump_generic_node (buffer, gimple_omp_task_child_fn (gs),
1729                              spc, flags, false);
1730           pp_string (buffer, " (");
1731           if (gimple_omp_task_data_arg (gs))
1732             dump_generic_node (buffer, gimple_omp_task_data_arg (gs),
1733                                spc, flags, false);
1734           else
1735             pp_string (buffer, "???");
1736           pp_string (buffer, ")]");
1737         }
1738       body = gimple_omp_body (gs);
1739       if (body && gimple_code (gimple_seq_first_stmt (body)) != GIMPLE_BIND)
1740         {
1741           newline_and_indent (buffer, spc + 2);
1742           pp_character (buffer, '{');
1743           pp_newline (buffer);
1744           dump_gimple_seq (buffer, body, spc + 4, flags);
1745           newline_and_indent (buffer, spc + 2);
1746           pp_character (buffer, '}');
1747         }
1748       else if (body)
1749         {
1750           pp_newline (buffer);
1751           dump_gimple_seq (buffer, body, spc + 2, flags);
1752         }
1753     }
1754 }
1755
1756
1757 /* Dump a GIMPLE_OMP_ATOMIC_LOAD tuple on the pretty_printer BUFFER, SPC
1758    spaces of indent.  FLAGS specifies details to show in the dump (see TDF_*
1759    in tree-pass.h).  */
1760
1761 static void
1762 dump_gimple_omp_atomic_load (pretty_printer *buffer, gimple gs, int spc,
1763                              int flags)
1764 {
1765   if (flags & TDF_RAW)
1766     {
1767       dump_gimple_fmt (buffer, spc, flags, "%G <%T, %T>", gs,
1768                        gimple_omp_atomic_load_lhs (gs),
1769                        gimple_omp_atomic_load_rhs (gs));
1770     }
1771   else
1772     {
1773       pp_string (buffer, "#pragma omp atomic_load");
1774       if (gimple_omp_atomic_need_value_p (gs))
1775         pp_string (buffer, " [needed]");
1776       newline_and_indent (buffer, spc + 2);
1777       dump_generic_node (buffer, gimple_omp_atomic_load_lhs (gs),
1778                          spc, flags, false);
1779       pp_space (buffer);
1780       pp_character (buffer, '=');
1781       pp_space (buffer);
1782       pp_character (buffer, '*');
1783       dump_generic_node (buffer, gimple_omp_atomic_load_rhs (gs),
1784                          spc, flags, false);
1785     }
1786 }
1787
1788 /* Dump a GIMPLE_OMP_ATOMIC_STORE tuple on the pretty_printer BUFFER, SPC
1789    spaces of indent.  FLAGS specifies details to show in the dump (see TDF_*
1790    in tree-pass.h).  */
1791
1792 static void
1793 dump_gimple_omp_atomic_store (pretty_printer *buffer, gimple gs, int spc,
1794                              int flags)
1795 {
1796   if (flags & TDF_RAW)
1797     {
1798       dump_gimple_fmt (buffer, spc, flags, "%G <%T>", gs,
1799                        gimple_omp_atomic_store_val (gs));
1800     }
1801   else
1802     {
1803       pp_string (buffer, "#pragma omp atomic_store ");
1804       if (gimple_omp_atomic_need_value_p (gs))
1805         pp_string (buffer, "[needed] ");
1806       pp_character (buffer, '(');
1807       dump_generic_node (buffer, gimple_omp_atomic_store_val (gs),
1808                          spc, flags, false);
1809       pp_character (buffer, ')');
1810     }
1811 }
1812
1813
1814 /* Dump all the memory operands for statement GS.  BUFFER, SPC and
1815    FLAGS are as in dump_gimple_stmt.  */
1816
1817 static void
1818 dump_gimple_mem_ops (pretty_printer *buffer, gimple gs, int spc, int flags)
1819 {
1820   tree vdef = gimple_vdef (gs);
1821   tree vuse = gimple_vuse (gs);
1822
1823   if (!ssa_operands_active () || !gimple_references_memory_p (gs))
1824     return;
1825
1826   if (vdef != NULL_TREE)
1827     {
1828       pp_string (buffer, "# ");
1829       dump_generic_node (buffer, vdef, spc + 2, flags, false);
1830       pp_string (buffer, " = VDEF <");
1831       dump_generic_node (buffer, vuse, spc + 2, flags, false);
1832       pp_character (buffer, '>');
1833       newline_and_indent (buffer, spc);
1834     }
1835   else if (vuse != NULL_TREE)
1836     {
1837       pp_string (buffer, "# VUSE <");
1838       dump_generic_node (buffer, vuse, spc + 2, flags, false);
1839       pp_character (buffer, '>');
1840       newline_and_indent (buffer, spc);
1841     }
1842 }
1843
1844
1845 /* Dump the gimple statement GS on the pretty printer BUFFER, SPC
1846    spaces of indent.  FLAGS specifies details to show in the dump (see
1847    TDF_* in tree-pass.h).  */
1848
1849 void
1850 dump_gimple_stmt (pretty_printer *buffer, gimple gs, int spc, int flags)
1851 {
1852   if (!gs)
1853     return;
1854
1855   if (flags & TDF_STMTADDR)
1856     pp_printf (buffer, "<&%p> ", (void *) gs);
1857
1858   if ((flags & TDF_LINENO) && gimple_has_location (gs))
1859     {
1860       expanded_location xloc = expand_location (gimple_location (gs));
1861       pp_character (buffer, '[');
1862       if (xloc.file)
1863         {
1864           pp_string (buffer, xloc.file);
1865           pp_string (buffer, " : ");
1866         }
1867       pp_decimal_int (buffer, xloc.line);
1868       pp_string (buffer, ":");
1869       pp_decimal_int (buffer, xloc.column);
1870       pp_string (buffer, "] ");
1871     }
1872
1873   if (flags & TDF_EH)
1874     {
1875       int lp_nr = lookup_stmt_eh_lp (gs);
1876       if (lp_nr > 0)
1877         pp_printf (buffer, "[LP %d] ", lp_nr);
1878       else if (lp_nr < 0)
1879         pp_printf (buffer, "[MNT %d] ", -lp_nr);
1880     }
1881
1882   if ((flags & (TDF_VOPS|TDF_MEMSYMS))
1883       && gimple_has_mem_ops (gs))
1884     dump_gimple_mem_ops (buffer, gs, spc, flags);
1885
1886   if ((flags & TDF_ALIAS)
1887       && gimple_has_lhs (gs))
1888     {
1889       tree lhs = gimple_get_lhs (gs);
1890       if (TREE_CODE (lhs) == SSA_NAME
1891           && POINTER_TYPE_P (TREE_TYPE (lhs))
1892           && SSA_NAME_PTR_INFO (lhs))
1893         {
1894           unsigned int align, misalign;
1895           struct ptr_info_def *pi = SSA_NAME_PTR_INFO (lhs);
1896           pp_string (buffer, "# PT = ");
1897           pp_points_to_solution (buffer, &pi->pt);
1898           newline_and_indent (buffer, spc);
1899           if (get_ptr_info_alignment (pi, &align, &misalign))
1900             {
1901               pp_printf (buffer, "# ALIGN = %u, MISALIGN = %u",
1902                          align, misalign);
1903               newline_and_indent (buffer, spc);
1904             }
1905         }
1906     }
1907
1908   switch (gimple_code (gs))
1909     {
1910     case GIMPLE_ASM:
1911       dump_gimple_asm (buffer, gs, spc, flags);
1912       break;
1913
1914     case GIMPLE_ASSIGN:
1915       dump_gimple_assign (buffer, gs, spc, flags);
1916       break;
1917
1918     case GIMPLE_BIND:
1919       dump_gimple_bind (buffer, gs, spc, flags);
1920       break;
1921
1922     case GIMPLE_CALL:
1923       dump_gimple_call (buffer, gs, spc, flags);
1924       break;
1925
1926     case GIMPLE_COND:
1927       dump_gimple_cond (buffer, gs, spc, flags);
1928       break;
1929
1930     case GIMPLE_LABEL:
1931       dump_gimple_label (buffer, gs, spc, flags);
1932       break;
1933
1934     case GIMPLE_GOTO:
1935       dump_gimple_goto (buffer, gs, spc, flags);
1936       break;
1937
1938     case GIMPLE_NOP:
1939       pp_string (buffer, "GIMPLE_NOP");
1940       break;
1941
1942     case GIMPLE_RETURN:
1943       dump_gimple_return (buffer, gs, spc, flags);
1944       break;
1945
1946     case GIMPLE_SWITCH:
1947       dump_gimple_switch (buffer, gs, spc, flags);
1948       break;
1949
1950     case GIMPLE_TRY:
1951       dump_gimple_try (buffer, gs, spc, flags);
1952       break;
1953
1954     case GIMPLE_PHI:
1955       dump_gimple_phi (buffer, gs, spc, flags);
1956       break;
1957
1958     case GIMPLE_OMP_PARALLEL:
1959       dump_gimple_omp_parallel (buffer, gs, spc, flags);
1960       break;
1961
1962     case GIMPLE_OMP_TASK:
1963       dump_gimple_omp_task (buffer, gs, spc, flags);
1964       break;
1965
1966     case GIMPLE_OMP_ATOMIC_LOAD:
1967       dump_gimple_omp_atomic_load (buffer, gs, spc, flags);
1968
1969       break;
1970
1971     case GIMPLE_OMP_ATOMIC_STORE:
1972       dump_gimple_omp_atomic_store (buffer, gs, spc, flags);
1973       break;
1974
1975     case GIMPLE_OMP_FOR:
1976       dump_gimple_omp_for (buffer, gs, spc, flags);
1977       break;
1978
1979     case GIMPLE_OMP_CONTINUE:
1980       dump_gimple_omp_continue (buffer, gs, spc, flags);
1981       break;
1982
1983     case GIMPLE_OMP_SINGLE:
1984       dump_gimple_omp_single (buffer, gs, spc, flags);
1985       break;
1986
1987     case GIMPLE_OMP_RETURN:
1988       dump_gimple_omp_return (buffer, gs, spc, flags);
1989       break;
1990
1991     case GIMPLE_OMP_SECTIONS:
1992       dump_gimple_omp_sections (buffer, gs, spc, flags);
1993       break;
1994
1995     case GIMPLE_OMP_SECTIONS_SWITCH:
1996       pp_string (buffer, "GIMPLE_SECTIONS_SWITCH");
1997       break;
1998
1999     case GIMPLE_OMP_MASTER:
2000     case GIMPLE_OMP_ORDERED:
2001     case GIMPLE_OMP_SECTION:
2002       dump_gimple_omp_block (buffer, gs, spc, flags);
2003       break;
2004
2005     case GIMPLE_OMP_CRITICAL:
2006       dump_gimple_omp_critical (buffer, gs, spc, flags);
2007       break;
2008
2009     case GIMPLE_CATCH:
2010       dump_gimple_catch (buffer, gs, spc, flags);
2011       break;
2012
2013     case GIMPLE_EH_FILTER:
2014       dump_gimple_eh_filter (buffer, gs, spc, flags);
2015       break;
2016
2017     case GIMPLE_EH_MUST_NOT_THROW:
2018       dump_gimple_eh_must_not_throw (buffer, gs, spc, flags);
2019       break;
2020
2021     case GIMPLE_EH_ELSE:
2022       dump_gimple_eh_else (buffer, gs, spc, flags);
2023       break;
2024
2025     case GIMPLE_RESX:
2026       dump_gimple_resx (buffer, gs, spc, flags);
2027       break;
2028
2029     case GIMPLE_EH_DISPATCH:
2030       dump_gimple_eh_dispatch (buffer, gs, spc, flags);
2031       break;
2032
2033     case GIMPLE_DEBUG:
2034       dump_gimple_debug (buffer, gs, spc, flags);
2035       break;
2036
2037     case GIMPLE_PREDICT:
2038       pp_string (buffer, "// predicted ");
2039       if (gimple_predict_outcome (gs))
2040         pp_string (buffer, "likely by ");
2041       else
2042         pp_string (buffer, "unlikely by ");
2043       pp_string (buffer, predictor_name (gimple_predict_predictor (gs)));
2044       pp_string (buffer, " predictor.");
2045       break;
2046
2047     case GIMPLE_TRANSACTION:
2048       dump_gimple_transaction (buffer, gs, spc, flags);
2049       break;
2050
2051     default:
2052       GIMPLE_NIY;
2053     }
2054
2055   /* If we're building a diagnostic, the formatted text will be
2056      written into BUFFER's stream by the caller; otherwise, write it
2057      now.  */
2058   if (!(flags & TDF_DIAGNOSTIC))
2059     pp_write_text_to_stream (buffer);
2060 }
2061
2062
2063 /* Dumps header of basic block BB to buffer BUFFER indented by INDENT
2064    spaces and details described by flags.  */
2065
2066 static void
2067 dump_bb_header (pretty_printer *buffer, basic_block bb, int indent, int flags)
2068 {
2069   edge e;
2070   gimple stmt;
2071   edge_iterator ei;
2072
2073   if (flags & TDF_BLOCKS)
2074     {
2075       INDENT (indent);
2076       pp_string (buffer, "# BLOCK ");
2077       pp_decimal_int (buffer, bb->index);
2078       if (bb->frequency)
2079         {
2080           pp_string (buffer, " freq:");
2081           pp_decimal_int (buffer, bb->frequency);
2082         }
2083       if (bb->count)
2084         {
2085           pp_string (buffer, " count:");
2086           pp_widest_integer (buffer, bb->count);
2087         }
2088
2089       if (flags & TDF_LINENO)
2090         {
2091           gimple_stmt_iterator gsi;
2092
2093           for (gsi = gsi_start_bb (bb); !gsi_end_p (gsi); gsi_next (&gsi))
2094             if (!is_gimple_debug (gsi_stmt (gsi))
2095                 && get_lineno (gsi_stmt (gsi)) != UNKNOWN_LOCATION)
2096               {
2097                 pp_string (buffer, ", starting at line ");
2098                 pp_decimal_int (buffer, get_lineno (gsi_stmt (gsi)));
2099                 break;
2100               }
2101
2102           if (bb->discriminator)
2103             {
2104               pp_string (buffer, ", discriminator ");
2105               pp_decimal_int (buffer, bb->discriminator);
2106             }
2107         }
2108       newline_and_indent (buffer, indent);
2109
2110       pp_string (buffer, "# PRED:");
2111       pp_write_text_to_stream (buffer);
2112       FOR_EACH_EDGE (e, ei, bb->preds)
2113         if (flags & TDF_SLIM)
2114           {
2115             pp_character (buffer, ' ');
2116             if (e->src == ENTRY_BLOCK_PTR)
2117               pp_string (buffer, "ENTRY");
2118             else
2119               pp_decimal_int (buffer, e->src->index);
2120           }
2121         else
2122           dump_edge_info (buffer->buffer->stream, e, 0);
2123       pp_newline (buffer);
2124     }
2125   else
2126     {
2127       stmt = first_stmt (bb);
2128       if (!stmt || gimple_code (stmt) != GIMPLE_LABEL)
2129         {
2130           INDENT (indent - 2);
2131           pp_string (buffer, "<bb ");
2132           pp_decimal_int (buffer, bb->index);
2133           pp_string (buffer, ">:");
2134           pp_newline (buffer);
2135         }
2136     }
2137   pp_write_text_to_stream (buffer);
2138   if (cfun)
2139     check_bb_profile (bb, buffer->buffer->stream);
2140 }
2141
2142
2143 /* Dumps end of basic block BB to buffer BUFFER indented by INDENT
2144    spaces.  */
2145
2146 static void
2147 dump_bb_end (pretty_printer *buffer, basic_block bb, int indent, int flags)
2148 {
2149   edge e;
2150   edge_iterator ei;
2151
2152   INDENT (indent);
2153   pp_string (buffer, "# SUCC:");
2154   pp_write_text_to_stream (buffer);
2155   FOR_EACH_EDGE (e, ei, bb->succs)
2156     if (flags & TDF_SLIM)
2157       {
2158         pp_character (buffer, ' ');
2159         if (e->dest == EXIT_BLOCK_PTR)
2160           pp_string (buffer, "EXIT");
2161         else
2162           pp_decimal_int (buffer, e->dest->index);
2163       }
2164     else
2165       dump_edge_info (buffer->buffer->stream, e, 1);
2166   pp_newline (buffer);
2167 }
2168
2169
2170 /* Dump PHI nodes of basic block BB to BUFFER with details described
2171    by FLAGS and indented by INDENT spaces.  */
2172
2173 static void
2174 dump_phi_nodes (pretty_printer *buffer, basic_block bb, int indent, int flags)
2175 {
2176   gimple_stmt_iterator i;
2177
2178   for (i = gsi_start_phis (bb); !gsi_end_p (i); gsi_next (&i))
2179     {
2180       gimple phi = gsi_stmt (i);
2181       if (is_gimple_reg (gimple_phi_result (phi)) || (flags & TDF_VOPS))
2182         {
2183           INDENT (indent);
2184           pp_string (buffer, "# ");
2185           dump_gimple_phi (buffer, phi, indent, flags);
2186           pp_newline (buffer);
2187         }
2188     }
2189 }
2190
2191
2192 /* Dump jump to basic block BB that is represented implicitly in the cfg
2193    to BUFFER.  */
2194
2195 static void
2196 pp_cfg_jump (pretty_printer *buffer, basic_block bb)
2197 {
2198   gimple stmt;
2199
2200   stmt = first_stmt (bb);
2201
2202   pp_string (buffer, "goto <bb ");
2203   pp_decimal_int (buffer, bb->index);
2204   pp_character (buffer, '>');
2205   if (stmt && gimple_code (stmt) == GIMPLE_LABEL)
2206     {
2207       pp_string (buffer, " (");
2208       dump_generic_node (buffer, gimple_label_label (stmt), 0, 0, false);
2209       pp_character (buffer, ')');
2210       pp_semicolon (buffer);
2211     }
2212   else
2213     pp_semicolon (buffer);
2214 }
2215
2216
2217 /* Dump edges represented implicitly in basic block BB to BUFFER, indented
2218    by INDENT spaces, with details given by FLAGS.  */
2219
2220 static void
2221 dump_implicit_edges (pretty_printer *buffer, basic_block bb, int indent,
2222                      int flags)
2223 {
2224   edge e;
2225   gimple stmt;
2226
2227   stmt = last_stmt (bb);
2228
2229   if (stmt && gimple_code (stmt) == GIMPLE_COND)
2230     {
2231       edge true_edge, false_edge;
2232
2233       /* When we are emitting the code or changing CFG, it is possible that
2234          the edges are not yet created.  When we are using debug_bb in such
2235          a situation, we do not want it to crash.  */
2236       if (EDGE_COUNT (bb->succs) != 2)
2237         return;
2238       extract_true_false_edges_from_block (bb, &true_edge, &false_edge);
2239
2240       INDENT (indent + 2);
2241       pp_cfg_jump (buffer, true_edge->dest);
2242       newline_and_indent (buffer, indent);
2243       pp_string (buffer, "else");
2244       newline_and_indent (buffer, indent + 2);
2245       pp_cfg_jump (buffer, false_edge->dest);
2246       pp_newline (buffer);
2247       return;
2248     }
2249
2250   /* If there is a fallthru edge, we may need to add an artificial
2251      goto to the dump.  */
2252   e = find_fallthru_edge (bb->succs);
2253
2254   if (e && e->dest != bb->next_bb)
2255     {
2256       INDENT (indent);
2257
2258       if ((flags & TDF_LINENO)
2259           && e->goto_locus != UNKNOWN_LOCATION
2260           )
2261         {
2262           expanded_location goto_xloc;
2263           goto_xloc = expand_location (e->goto_locus);
2264           pp_character (buffer, '[');
2265           if (goto_xloc.file)
2266             {
2267               pp_string (buffer, goto_xloc.file);
2268               pp_string (buffer, " : ");
2269             }
2270           pp_decimal_int (buffer, goto_xloc.line);
2271           pp_string (buffer, " : ");
2272           pp_decimal_int (buffer, goto_xloc.column);
2273           pp_string (buffer, "] ");
2274         }
2275
2276       pp_cfg_jump (buffer, e->dest);
2277       pp_newline (buffer);
2278     }
2279 }
2280
2281
2282 /* Dumps basic block BB to buffer BUFFER with details described by FLAGS and
2283    indented by INDENT spaces.  */
2284
2285 static void
2286 gimple_dump_bb_buff (pretty_printer *buffer, basic_block bb, int indent,
2287                      int flags)
2288 {
2289   gimple_stmt_iterator gsi;
2290   gimple stmt;
2291   int label_indent = indent - 2;
2292
2293   if (label_indent < 0)
2294     label_indent = 0;
2295
2296   dump_bb_header (buffer, bb, indent, flags);
2297   dump_phi_nodes (buffer, bb, indent, flags);
2298
2299   for (gsi = gsi_start_bb (bb); !gsi_end_p (gsi); gsi_next (&gsi))
2300     {
2301       int curr_indent;
2302
2303       stmt = gsi_stmt (gsi);
2304
2305       curr_indent = gimple_code (stmt) == GIMPLE_LABEL ? label_indent : indent;
2306
2307       INDENT (curr_indent);
2308       dump_gimple_stmt (buffer, stmt, curr_indent, flags);
2309       pp_newline (buffer);
2310       dump_histograms_for_stmt (cfun, buffer->buffer->stream, stmt);
2311     }
2312
2313   dump_implicit_edges (buffer, bb, indent, flags);
2314
2315   if (flags & TDF_BLOCKS)
2316     dump_bb_end (buffer, bb, indent, flags);
2317 }
2318
2319
2320 /* Dumps basic block BB to FILE with details described by FLAGS and
2321    indented by INDENT spaces.  */
2322
2323 void
2324 gimple_dump_bb (basic_block bb, FILE *file, int indent, int flags)
2325 {
2326   maybe_init_pretty_print (file);
2327   gimple_dump_bb_buff (&buffer, bb, indent, flags);
2328   pp_flush (&buffer);
2329 }