gcc/gimple-pretty-print.c

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