1 2011-12-12 Richard Sandiford <richard.sandiford@linaro.org>
4 * optabs.c (maybe_legitimize_operand_same_code): Use copy_to_mode_reg
5 instead of force_reg. Do nothing if the address is already a
6 non-virtual pseudo register.
8 2011-12-12 Torvald Riegel <triegel@redhat.com>
10 * gimplify.c (voidify_wrapper_expr): Add default handling for
13 2011-12-12 Torvald Riegel <triegel@redhat.com>
15 * tree-ssa-tail-merge.c (gimple_equal_p): Don't treat transaction
18 2011-12-12 Iain Sandoe <iains@gcc.gnu.org>
20 * config/darwin-sections.def (zobj_const_data_section): Fix over-
23 2011-12-11 Richard Henderson <rth@redhat.com>
25 * config/rs6000/rs6000.c (rs6000_expand_interleave): Use
26 BYTES_BIG_ENDIAN, not TARGET_BIG_ENDIAN.
28 2011-12-11 Jakub Jelinek <jakub@redhat.com>
30 PR tree-optimization/51485
31 * tree-vect-data-refs.c (vect_analyze_data_refs): Give up on
34 2011-12-11 Patrick Marlier <patrick.marlier@gmail.com>
36 * trans-mem.c (ipa_tm_transform_calls_redirect): Do not remove
39 2011-12-10 Richard Henderson <rth@redhat.com>
41 * config/rs6000/altivec.md (altivec_vmrghb): Rewrite pattern as
42 vec_select + vec_concat.
43 (altivec_vmrghh, altivec_vmrghw, altivec_vmrghsf, altivec_vmrglb,
44 altivec_vmrglh, altivec_vmrglw, altivec_vmrglsf): Likewise.
45 (vec_perm_constv16qi): New.
46 (vec_extract_evenv4si, vec_extract_evenv4sf, vpkuhum_nomode,
47 vpkuwum_nomode, vec_extract_oddv8hi, vec_extract_oddv16qi,
48 vec_interleave_high<VI>, vec_interleave_low<VI>): Remove.
49 * config/rs6000/paired.md (paired_merge00): Rewrite pattern as
50 vec_select + vec_concat.
51 (paired_merge10, paired_merge01, paired_merge11): Likewise.
52 (vec_perm_constv2sf): New.
53 (vec_interleave_highv2sf, vec_interleave_lowv2sf,
54 vec_extract_evenv2sf, vec_extract_oddv2sf): Remove.
55 * config/rs6000/spe.md (spe_evmergehi): Rewrite pattern as
56 vec_select + vec_concat.
57 (spe_evmergehilo, spe_evmergelo, spe_evmergelohi): New.
58 (vec_perm_constv2si): New.
59 * config/rs6000/vector.md (vec_interleave_highv4sf,
60 vec_interleave_lowv4sf, vec_interleave_high<VEC_64>,
61 vec_interleave_low<VEC_64>): Remove.
62 * config/rs6000/vsx.md (VS_double): New mode attribute.
63 (UNSPEC_VSX_XXPERMDI): Remove.
64 (vsx_xxpermdi_<VSX_L>_1): Rewrite pattern as vec_select + vec_concat.
65 (vsx_xxmrghw_<VSX_W>, vsx_xxmrglw_<VSX_W>): Likewise.
66 (vsx_xxpermdi_<VSX_L>): Change to expander.
67 (vec_perm_const<VSX_D>): New.
68 (vsx_mergel_<VSX_D>, vsx_mergeh_<VSX_D>): New.
69 * config/rs6000/predicates.md (const_0_to_1_operand): New.
70 (const_2_to_3_operand): New.
71 * config/rs6000/rs6000.c (TARGET_VECTORIZE_VEC_PERM_CONST_OK): New.
72 (altivec_expand_vec_perm_const): New.
73 (rs6000_expand_vec_perm_const_1, rs6000_expand_vec_perm_const): New.
74 (rs6000_vectorize_vec_perm_const_ok): New.
75 (rs6000_do_expand_vec_perm): New.
76 (rs6000_expand_extract_even, rs6000_expand_interleave): New.
77 * config/rs6000/rs6000-builtin.def (VEC_MERGE*): Update rtx codes.
78 * config/rs6000/rs6000-modes.def: Add double-wide vector modes.
79 * config/rs6000/rs6000-protos.h: Update.
81 2011-12-10 Richard Henderson <rth@redhat.com>
83 * expr.c (expand_expr_real_2) [VEC_PERM_EXPR]: Avoid passing a
84 CONST_INT to expand_vec_perm as the selector.
85 * optabs.c (expand_vec_perm): Assert the selector is of a proper mode.
87 2011-12-10 Richard Henderson <rth@redhat.com>
89 * genmodes.c (struct mode_data): Remove wider_2x member.
90 (blank_mode): Adjust initializer.
91 (calc_wider_mode): Use XALLOCAVEC.
92 (emit_move_wider): Select double-width same-element vectors for
94 * machmode.h (GET_MODE_2XWIDER_MODE): Update documentation.
95 * config/i386/i386.c (doublesize_vector_mode): Remove.
96 (expand_vselect_vconcat): Use GET_MODE_2XWIDER_MODE instead.
98 2011-12-10 Joern Rennecke <joern.rennecke@embecosm.com>
100 * config/epiphany/epiphany.h (USE_LOAD_POST_INCREMENT): Define.
101 (USE_LOAD_POST_DECREMENT, USE_STORE_POST_INCREMENT): Likewise.
102 (USE_STORE_POST_DECREMENT): Likewise.
104 * config/epiphany/epiphany.h (EPIPHANY_RETURN_REGNO): New macro,
106 (INCOMING_RETURN_ADDR_RTX) .. this. Use EPIPHANY_RETURN_REGNO.
107 (DWARF_FRAME_RETURN_COLUMN): New macro.
109 * config/epiphany/epiphany-protos.h (epiphany_start_function): Declare.
110 * config/epiphany/epiphany.c (epiphany_handle_interrupt_attribute):
111 Split "timer" value into "timer0" and "timer1".
112 Handle page_miss, message and wand. Don't handle static_flag.
114 (epiphany_start_function): New function.
115 (epiphany_compute_function_type): Split "timer" value into "timer0"
116 and "timer1". Handle page_miss, message and wand.
117 Don't handle static_flag.
118 (epiphany_expand_epilogue): Don't use frame_insn for status / iret
120 * config/epiphany/epiphany.h: ASM_DECLARE_FUNCTION_NAME: Define.
121 (enum epiphany_function_type):
122 Split EPIPHANY_FUNCTION_TIMER value into EPIPHANY_FUNCTION_TIMER0
123 and EPIPHANY_FUNCTION_TIMER1.
124 Remove EPIPHANY_FUNCTION_ILINK1 and EPIPHANY_FUNCTION_ILINK2 values.
125 Add EPIPHANY_FUNCTION_PAGE_MISS and EPIPHANY_FUNCTION_MESSAGE values.
126 Rename EPIPHANY_FUNCTION_STATIC_FLAG to EPIPHANY_FUNCTION_WAND.
128 2011-12-10 Nathan Sidwell <nathan@acm.org>
130 PR gcov-profile/51449
131 * coverage.c (coverage_end_function): Always process the coverage
134 2011-12-09 Aldy Hernandez <aldyh@redhat.com>
137 * tree.c (build_common_builtin_nodes): Do not use TM_PURE
138 attribute unless language has support for TM.
139 * config/i386/i386.c (ix86_init_tm_builtins): Exit gracefully in
140 the absence of TM builtins.
142 2011-12-09 Eric Botcazou <ebotcazou@adacore.com>
144 * gimple-fold.c (gimple_fold_stmt_to_constant_1) <GIMPLE_UNARY_RHS>:
145 Also check the TYPE_MODE to recognize useless pointer conversions.
147 2011-12-09 Jakub Jelinek <jakub@redhat.com>
149 PR tree-optimization/51117
150 * tree-eh.c (optimize_clobbers): Don't remove just one
151 clobber, but all consecutive clobbers before RESX.
152 Use gimple_clobber_p predicate.
154 2011-12-09 Michael Meissner <meissner@the-meissners.org>
156 * config/rs6000/rs6000.c (altivec_expand_builtin): Call
157 expand_call to return a valid funciton instead of return
158 cosnt0_rtx/NULL_RTX if there was an error with the builtin.
159 (altivec_expand_ld_builtin): Ditto.
160 (rs6000_inner_target_options): If VSX is selected as a target
161 attribute or pragma, enable ALTIVEC also.
162 (rs6000_pragma_target_parse): Call rs6000_option_override_internal
163 to do all of the standard processing when switching options,
164 including redefining appropriate macros.
166 PR rtl-optimization/51469
167 * varasm.c (default_binds_local_p_1): If the symbol is a gnu
168 indirect function, mark the symbol as non-local.
170 2011-12-09 H.J. Lu <hongjiu.lu@intel.com>
173 * Makefile.in (errors.o): Restored.
175 2011-12-09 Richard Guenther <rguenther@suse.de>
178 * tree.c (free_lang_data_in_decl): Remove freeing conditional
181 2011-12-09 Joern Rennecke <joern.rennecke@embecosm.com>
184 * emit-rtl.c (set_dst_reg_note): New function.
185 * rtl.h (set_dst_reg_note): Declare.
186 * optabs.c (expand_binop, expand_absneg_bit): Use set_dst_reg_note.
187 (emit_libcall_block, expand_fix): Likewise.
188 * function.c (assign_parm_setup_reg, expand_function_start): Likewise.
189 * expmed.c (expand_mult_const, expand_divmod): Likewise.
190 * reload1.c (gen_reload): Likewise.
192 * dse.c (get_stored_val, get_call_args): Use gen_int_mode.
193 * expmed.c (expand_divmod): Likewise.
194 * combine.c (simplify_if_then_else): Likewise.
196 2011-12-09 Kai Tietz <ktietz@redhat.com>
198 * ira-color.c (print_hard_regs_subforest): Use
199 HOST_WIDEST_INT_PRINT_DEC instead of %lld.
200 (allocno_hard_regs): Change type of cost member
202 (add_allocno_hard_regs): Change type of argument cost
204 * ira-conflict.c (build_conflict_bit_table): Replace use
205 of long-long by HOST_WIDEST_INT.
207 2011-12-09 Georg-Johann Lay <avr@gjlay.de>
210 * config/avr/avr.md (config/avr/avr.md, *sbix_branch_tmp): Use
211 zero_extract:QIHI instead of zero_extract:HI.
213 2011-12-09 Jakub Jelinek <jakub@redhat.com>
214 Andrew Pinski <apinski@cavium.com>
216 PR tree-optimization/51117
217 * tree-eh.c (optimize_clobbers): New function.
218 (execute_lower_eh_dispatch): Call it.
220 2011-12-09 Richard Guenther <rguenther@suse.de>
222 PR tree-optimization/51482
223 * tree-vect-stmts.c (get_vectype_for_scalar_type_and_size):
224 Make sure to only create REAL_TYPE and INTEGER_TYPE component
227 2011-12-09 Kai Tietz <ktietz@redhat.com>
229 * implicit-zee.c (num_realized): Change type to long.
230 (num_ze_opportunities): Likewise.
232 2011-12-08 Andrew Pinski <apinski@cavium.com>
234 * config/mips/mips-cpus.def (octeon+): New CPU.
235 * config/mips/mips-tables.opt: Regenerate.
236 * config/mips/mips.h (MIPS_CPP_SET_PROCESSOR): Emit '+' as 'P'.
238 2011-12-08 Bill Schmidt <wschmidt@linux.vnet.ibm.com>
241 * tree-ssa-dom.c (enum expr_kind): Add EXPR_PHI.
242 (struct hashable_expr): Add struct phi field.
243 (initialize_hash_element): Handle phis; change to use XCNEWVEC.
244 (hashable_expr_equal_p): Handle phis.
245 (iterative_hash_hashable_expr): Likewise.
246 (print_expr_hash_elt): Likewise.
247 (free_expr_hash_elt): Likewise.
248 (dom_opt_enter_block): Create equivalences from redundant phis.
249 (eliminate_redundant_computations): Handle redundant phis.
250 (lookup_avail_expr): Handle phis.
252 2011-12-08 Jakub Jelinek <jakub@redhat.com>
254 PR tree-optimization/51466
255 * tree-ssa-forwprop.c (forward_propagate_addr_expr_1): Also copy
258 2011-12-08 Richard Guenther <rguenther@suse.de>
260 * tree-ssa-operands.c (add_stmt_operand): Do not mark stmts
261 volatile when processing operands of an ADDR_EXPR.
262 (get_indirect_ref_operands): Likewise.
263 (get_tmr_operands): Likewise.
264 (get_expr_operands): Likewise.
266 2011-12-08 Andreas Krebbel <Andreas.Krebbel@de.ibm.com>
269 * config/s390/s390.c (s390_mainpool_finish): Emit the jump over
270 the literal pool as jump insn.
272 2011-12-08 Richard Guenther <rguenther@suse.de>
274 PR tree-optimization/49772
275 * tree-inline.c (optimize_inline_calls): Remove bail out
278 2011-12-08 Richard Guenther <rguenther@suse.de>
281 * lto-streamer-out.c (produce_symtab): Remove asserts.
283 2011-12-08 Richard Guenther <rguenther@suse.de>
286 * lto-streamer-out.c (tree_is_indexable): Localize variably
287 modified types and their FIELD_DECLs.
289 2011-12-08 Eric Botcazou <ebotcazou@adacore.com>
291 PR tree-optimization/51315
292 * tree.h (get_object_or_type_alignment): Declare.
293 * expr.c (get_object_or_type_alignment): Move to...
294 * builtins.c (get_object_or_type_alignment): ...here. Add assertion.
295 * tree-sra.c (tree_non_mode_aligned_mem_p): Rename to...
296 (tree_non_aligned_mem_p): ...this. Add ALIGN parameter. Look into
297 MEM_REFs and use get_object_or_type_alignment for them.
298 (build_accesses_from_assign): Adjust for above change.
299 (access_precludes_ipa_sra_p): Likewise.
301 2011-12-08 Richard Guenther <rguenther@suse.de>
304 * lto-streamer-out.c (tree_is_indexable): Exclude block-local
307 2011-12-07 Andrew Pinski <apinski@cavium.com>
310 * expr.c (do_store_flag): Rewrite code that looks for BIT_AND_EXPR for
313 2011-12-07 Richard Guenther <rguenther@suse.de>
315 PR tree-optimization/50823
316 * ipa-inline.c (edge_badness): Do not account for the number of
319 2011-12-07 Martin Jambor <mjambor@suse.cz>
321 PR tree-optimization/50744
322 * ipa-cp.c (good_cloning_opportunity_p): Assert size_cost is positive,
323 compute evaluation in HOST_WIDEST_INT.
324 (safe_add): New function
325 (propagate_effects): Use safe_add to accumulate effects.
327 2011-12-06 Joel Sherrill <joel.sherrill@oarcorp.com>
329 * config/rs6000/rtems.h: Switch to using global_options_set
330 in SUBSUBTARGET_OVERRIDE_OPTIONS.
332 2011-12-06 David S. Miller <davem@davemloft.net>
334 * config/sparc/visintrin.h: Add appropriate __VIS__ cpp protection.
336 2011-12-06 Georg-Johann Lay <avr@gjlay.de>
338 * config/avr/avr.c (avr_file_start): Fix missing ,
340 2011-12-06 Jakub Jelinek <jakub@redhat.com>
343 * config/i386/i386.c (ix86_emit_leave): Call ix86_add_cfa_restore_note
346 2011-12-06 Georg-Johann Lay <avr@gjlay.de>
348 Forward-port from gcc-4_6-branch r181936 2011-12-02.
349 * config/avr/avr-mcus.def (avr_mcu_types): ATtiny4313 and
350 AT86RF401 have a 16-bit SP (their manual is bogus).
352 2011-12-06 Georg-Johann Lay <avr@gjlay.de>
354 Forward-port from gcc-4_6-branch r181936 2011-12-02.
357 * config/avr/avr.md (movhi_sp_r): Set insn condition to
359 * config/avr/avr.c (output_movhi): Use "clr%B0" instead of "in
360 %B0,__SP_H__" if AVR_HAVE_8BIT_SP.
361 (avr_file_start): Only print "__SP_H__ = 0x3e" if !AVR_HAVE_8BIT_SP.
363 2011-12-06 Georg-Johann Lay <avr@gjlay.de>
367 * config/avr/avr.h (ADDR_SPACE_PGM, ADDR_SPACE_PGM1,
368 ADDR_SPACE_PGM2, ADDR_SPACE_PGM3, ADDR_SPACE_PGM4,
369 ADDR_SPACE_PGM5, ADDR_SPACE_PGMX): Write as enum.
370 (avr_addrspace_t): New typedef.
371 (avr_addrspace): New declaration.
372 * config/avr/avr-c.c (avr_toupper): New static function.
373 (avr_register_target_pragmas, avr_cpu_cpp_builtins): Use
374 avr_addrspace to get address space information.
375 * config/avr/avr.c (avr_addrspace): New variable.
376 (avr_out_lpm, avr_pgm_check_var_decl, avr_insert_attributes,
377 avr_asm_named_section, avr_section_type_flags,
378 avr_asm_select_section, avr_addr_space_address_mode,
379 avr_addr_space_convert, avr_emit_movmemhi): Use it.
380 (avr_addr_space_pointer_mode): Forward to avr_addr_space_address_mode.
381 (avr_pgm_segment): Remove.
383 2011-12-06 Richard Guenther <rguenther@suse.de>
386 * varasm.c (assemble_alias): Move DECL_EXTERNAL implementation
387 quirk adjustjment ...
388 * passes.c (rest_of_decl_compilation): ... here.
390 2011-12-06 Richard Guenther <rguenther@suse.de>
393 * gimple-fold.c (gimplify_and_update_call_from_tree): Guard
394 vdef check for the fact we do not have virtual operands when
397 2011-12-06 Richard Guenther <rguenther@suse.de>
399 PR tree-optimization/51245
400 * tree-ssa-sccvn.c (vn_reference_lookup_or_insert_constant_for_pieces):
402 (vn_reference_lookup_3): Use it. Properly valueize all refs
405 2011-12-06 Iain Sandoe <iains@gcc.gnu.org>
407 * config/rs6000/rs6000.c (darwin_rs6000_override_options): Initialize
410 2011-12-06 Richard Guenther <rguenther@suse.de>
412 PR tree-optimization/51363
413 * gimple.c (gimple_rhs_has_side_effects): Remove.
414 * gimple.h (gimple_rhs_has_side_effects): Likewise.
415 * tree-ssa-dom.c (optimize_stmt): Simplify conditional.
417 2011-12-06 Alan Modra <amodra@gmail.com>
420 * config/rs6000/rs6000.c (rs6000_emit_prologue <TARGET_SPE_ABI>):
421 Do not mark r11 setup as frame-related. Pass correct offset to
422 rs6000_emit_savres_rtx. Correct out-of-line rs6000_frame_related
423 arguments. Correct sp_offset. Remove "offset" fudge from
424 in-line rs6000_frame_related call. Rename misleading variable.
425 Fix comments and whitespace. Tidy some expressions.
426 (rs6000_emit_epilogue <TARGET_SPE_ABI>): Always set frame_reg_rtx
427 to r11 in out-of-line case. Correct sp_offset. Pass correct
428 offset to rs6000_emit_savres_rtx. Rename misleading variable.
429 Fix comments and whitespace. Tidy some expressions.
430 (rs6000_emit_epilogue <non-TARGET_SPE_ABI>): Add sp_offset
431 adjustment when !saving_GPRs_inline. Correct register mode
432 used in address calcs.
433 (rs6000_emit_epilogue <non-TARGET_SPE_ABI>): Similarly when
434 !restoring_GPRs_inline.
436 2011-12-06 Ramana Radhakrishnan <ramana.radhakrishnan@linaro.org>
438 * config/arm/vfp.md (*combine_vcvt_f64_<FCVTI32typename>): Fix
439 formatting character for vmov.f64 case.
441 2011-12-05 Jakub Jelinek <jakub@redhat.com>
443 PR tree-optimization/51396
444 * tree-ssa-math-opts.c (convert_mult_to_fma): Don't optimize
445 if MUL_RESULT has zero uses.
448 * c-decl.c (pop_scope): Don't add DECL_EXTERNAL decls
449 for debug info if scope is file_scope.
452 * c-decl.c (c_finish_incomplete_decl, finish_decl): Call
453 relayout_decl instead of layout_decl.
455 2011-12-05 Richard Sandiford <rdsandiford@googlemail.com>
457 * resource.c (init_resource_info): Only consider EXIT_IGNORE_STACK
458 if there is in epilogue.
460 2011-12-05 Richard Sandiford <rdsandiford@googlemail.com>
462 * optabs.c (maybe_emit_sync_lock_test_and_set): Pass a null target
463 to emit_library_call_value.
464 (expand_atomic_compare_and_swap): Likewise.
466 2011-12-05 Vladimir Makarov <vmakarov@redhat.com>
469 * ira-int.h (struct ira_object): Remove add_data.
470 (OBJECT_ADD_DATA): Remove.
472 * ira-build.c (ira_create_object): Remove OBJECT_ADD_DATA
475 * ira-color.c (object_hard_regs_t, object_hard_regs): Rename to
476 allocno_hard_regs_t, allocno_hard_regs.
477 (object_hard_regs_node_t, object_hard_regs_node): Rename to
478 allocno_hard_regs_node_t and allocno_hard_regs_node.
479 (struct allocno_color_data): Add new member last_process. Move
480 profitable_hard_regs, hard_regs_node, and hard_regs_subnodes_start
481 from object_color_data.
482 (object_color_data_t, object_color_data, OBJECT_COLOR_DATA):
484 (curr_allocno_process): New static variable.
485 (object_hard_regs_eq, object_hard_regs_htab): Rename to
486 allocno_hard_regs_eq and allocno_hard_regs_htab.
487 (init_object_hard_regs, finish_object_hard_regs): Rename to
488 init_allocno_hard_regs and finish_allocno_hard_regs.
489 (object_hard_regs_compare, object_hard_regs_node_t): Rename to
490 allocno_hard_regs_compare and allocno_hard_regs_node_t.
491 (create_new_object_hard_regs_node): Rename to
492 create_new_allocno_hard_regs_node.
493 (add_new_object_hard_regs_node_to_forest): Rename to
494 add_new_allocno_hard_regs_node_to_forest.
495 (add_object_hard_regs_to_forest, collect_object_hard_regs_cover):
496 Rename to add_allocno_hard_regs_to_forest and collect_allocno_hard_regs_cover.
497 (setup_object_hard_regs_nodes_parent): Rename to setup_allocno_hard_regs_nodes_parent.
498 (remove_unused_object_hard_regs_nodes): Rename to remove_unused_allocno_hard_regs_nodes.
499 (enumerate_object_hard_regs_nodes, object_hard_regs_nodes_num):
500 Rename to enumerate_allocno_hard_regs_nodes and allocno_hard_regs_nodes_num.
501 (object_hard_regs_nodes, object_hard_regs_subnode_t): Rename to
502 allocno_hard_regs_nodes and allocno_hard_regs_subnode_t.
503 (object_hard_regs_subnode, object_hard_regs_subnodes): Rename to
504 allocno_hard_regs_subnode and allocno_hard_regs_subnodes.
505 (object_hard_regs_subnode_index): Rename to allocno_hard_regs_subnode_index.
506 (setup_object_hard_regs_subnode_index): Rename to
507 setup_allocno_hard_regs_subnode_index.
508 (get_object_hard_regs_subnodes_num): Rename to get_allocno_hard_regs_subnodes_num.
509 (form_object_hard_regs_nodes_forest): Rename to form_allocno_hard_regs_nodes_forest.
510 (finish_object_hard_regs_nodes_tree): Rename to form_allocno_hard_regs_nodes_forest
511 (finish_object_hard_regs_nodes_forest): Rename to
512 finish_allocno_hard_regs_nodes_forest.
513 (setup_left_conflict_sizes_p): Use allocno data instead of object
514 ones. Process conflict allocnos once.
515 (update_left_conflict_sizes_p): Use allocno data instead of object
516 ones. Change prototype signature.
517 (empty_profitable_hard_regs): Use allocno data instead of object
519 (setup_profitable_hard_regs): Ditto.
520 (get_conflict_profitable_regs): Rename to
521 get_conflict_and_start_profitable_regs. Use allocno data for
522 profitable regs calculation.
523 (check_hard_reg_p): Change prototype signature. Check profitable
524 regs for allocno not the objects.
525 (assign_hard_reg): Process conflict allocnos only once for
526 updating conflict costs.
527 (setup_allocno_available_regs_num): Use allocno data instead of
528 object ones. Modify debug output.
529 (color_pass): Remove initialization and finalization of object
532 2011-12-05 Kazu Hirata <kazu@codesourcery.com>
535 * config/arm/arm.md (*minmax_arithsi): Always require the else
536 clause in the MINUS case.
538 2011-12-05 Richard Guenther <rguenther@suse.de>
540 PR tree-optimization/50904
541 * tree-ssa-loop-im.c (struct mem_ref): Remove vops member.
542 (MEM_ANALYZABLE): New.
543 (memory_references): Remove clobbered_vops and vop_ref_map
544 members, add all_refs_stored_in_loop member.
545 (memref_free): Adjust.
546 (mem_ref_alloc): Likewise.
547 (gather_mem_refs_stmt): Do not record clobbers, instead
548 record refs for unanalyzable stmts.
549 (gather_mem_refs_in_loops): Do not propagate clobbers.
550 (struct vop_to_refs_elt, vtoe_hash, vtoe_eq, vtoe_free,
551 record_vop_access, get_vop_accesses, get_vop_stores,
552 add_vop_ref_mapping): Remove.
553 (create_vop_ref_mapping_loop): Adjust to simply record all
555 (analyze_memory_references): Adjust.
556 (refs_independent_p): Check for not analyzable refs.
557 (can_sm_ref_p): Likewise.
558 (ref_indep_loop_p_1): Simplify.
559 (tree_ssa_lim_finalize): Adjust.
561 * tree-ssa-loop-im.c (stmt_cost): Simplify, use LIM_EXPENSIVE
562 rather than magic constants. Assign zero cost to PAREN_EXPR
563 and SSA_NAME copies. Assign cost proportional to the vector
564 size for vector constructors.
566 2011-12-05 Richard Guenther <rguenther@suse.de>
568 * tree-ssa-alias.h (struct ao_ref_s): Add volatile_p field.
569 * tree-ssa-alias.c (ao_ref_init): Initialize it.
570 (ao_ref_init_from_ptr_and_size): Likewise.
571 (refs_may_alias_p_1): Two volatile accesses conflict.
572 (ref_maybe_used_by_call_p_1): Likewise.
573 (call_may_clobber_ref_p_1): Likewise.
574 * tree-ssa-sccvn.c (ao_ref_init_from_vn_reference): Initialize
577 2011-12-05 Richard Guenther <rguenther@suse.de>
579 * tree-ssa.c (verify_ssa): Verify SSA names in the loop
580 over all SSA names. Remove SSA operand checking, call
582 * tree-ssa-operands.h (verify_ssa_operands): Declare.
583 * tree-ssa-operands.c (verify_ssa_operands): New function.
585 2011-12-05 Ramana Radhakrishnan <ramana.radhakrishnan@linaro.org>
587 * config/arm/arm.c (vfp3_const_double_for_fract_bits): Define.
588 * config/arm/arm-protos.h (vfp3_const_double_for_fract_bits): Declare.
589 * config/arm/constraints.md ("Dt"): New constraint.
590 * config/arm/predicates.md
591 (const_double_vcvt_power_of_two_reciprocal): New.
592 * config/arm/vfp.md (FCVTI32typename): New.
593 (FCVT): New iterator.
594 (*combine_vcvt_f32_<FCVTI32typename>): New.
595 (*combine_vcvt_f64_<FCVTI32typename>): New.
597 2011-12-05 Richard Guenther <rguenther@suse.de>
599 * cgraph.c (cgraph_create_edge_1): Initialize
600 call_stmt_cannot_inline_p from the stmt if possible.
601 (cgraph_make_edge_direct): Likewise.
602 * gimple-streamer-in.c (input_gimple_stmt): Do not
603 call gimple_call_set_cannot_inline.
604 * gimple.h (enum gf_mask): Remove GF_CALL_CANNOT_INLINE, shift
606 (gimple_call_set_cannot_inline): Remove.
607 (gimple_call_cannot_inline_p): Likewise.
608 * ipa-inline-analysis.c (initialize_inline_failed): Look
609 at the edge call_stmt_cannot_inline_p flag.
610 * ipa-inline.c (can_inline_edge_p): Likewise.
611 (early_inliner): Only update the edge flag.
612 * ipa-prop.c (update_indirect_edges_after_inlining): Likewise.
613 (ipa_modify_call_arguments): Do not call gimple_call_set_cannot_inline.
614 * cgraphunit.c (assemble_thunk): Likewise.
615 * gimple-fold.c (gimple_fold_call): Likewise.
617 * tree.h (CALL_CANNOT_INLINE_P): Remove.
618 * tree-mudflap.c (mf_xform_statements): Do not modify alloca calls.
619 * builtins.c (expand_builtin_alloca): With -fmudflap do not expand
621 * cfgexpand.c (expand_call_stmt): Do not set CALL_CANNOT_INLINE_P.
622 * gimple.c (gimple_build_call_from_tree): Do not read
623 CALL_CANNOT_INLINE_P.
624 * gimplify.c (gimplify_call_expr): Do not copy CALL_CANNOT_INLINE_P.
626 2011-12-05 Jakub Jelinek <jakub@redhat.com>
627 Eric Botcazou <ebotcazou@adacore.com>
631 * calls.c (internal_arg_pointer_exp_state): New variable.
632 (internal_arg_pointer_based_exp_1,
633 internal_arg_pointer_exp_scan): New functions.
634 (internal_arg_pointer_based_exp): New function.
635 (mem_overlaps_already_clobbered_arg_p): Use it.
636 (expand_call): Free internal_arg_pointer_exp_state.cache vector
637 and clear internal_arg_pointer_exp_state.scan_start.
639 2011-12-04 Kaz Kojima <kkojima@gcc.gnu.org>
641 * config/sh/linux.h (TARGET_DEFAULT): Add MASK_SOFT_ATOMIC.
642 * config/sh/sync.md: New file.
643 * config/sh/sh.md: Include sync.md.
644 * config/sh/sh.opt (msoft-atomic): New option.
645 * doc/invoke.texi (SH Options): Document it.
647 2011-12-04 Nathan Sidwell <nathan@acm.org>
649 * gcov-io.h (struct gcov_info): Replace trailing array with
651 * profile.c (branch_prob): Only call renamed
652 coverage_begin_function once.
653 * coverage.h (coverage_begin_output): Rename to ...
654 (coverage_begin_function): ... here.
655 * coverage.c (struct function_list): Rename to ...
656 (struct coverage_data): ... this. Update all uses.
657 (gcov_info_var, gcov_fn_info_type, gcov_fn_info_ptr_type): New
659 (bbg_file_opened, bbg_function_announced): Remove.
660 (get_coverage_counts): Adjust message.
661 (coverage_begin_ouput): Rename to ...
662 (coverage_begin_function): ... here. Move file opening to
663 coverage_init. Adjust for being called only once.
664 (coverage_end_function): Remove bbg file and inhibit further
665 output here on error.
666 (build_info_type): Adjust for change to pointer to array.
667 (build_info): Receive array of function pointers and adjust.
668 (create_coverage): Break into ...
669 (coverage_obj_init, coverage_obj_fn, coverage_obj_finish):
670 ... these, and adjust.
671 (coverage_init): Open the notes file here. Tidy.
672 (coverage_finish): Call coverage_obj_init etc.
674 2011-12-04 Ira Rosen <ira.rosen@linaro.org>
677 * tree-vect-loop.c (vect_create_epilog_for_reduction): Create exit
678 phi nodes for outer loop in case of double reduction.
680 2011-12-04 Jérémie Detrey <Jeremie.Detrey@loria.fr>
683 * config/i386/avxintrin.h (_mm256_insert_epi64): Declare second
684 parameter as long long.
686 2011-12-04 Richard Sandiford <rdsandiford@googlemail.com>
689 * optabs.c (init_sync_libfuncs): Use "or" rather than "ior"
690 in the external names.
692 2011-12-03 Jack Howarth <howarth@bromo.med.uc.edu>
694 * config/darwin10.h (LINK_GCC_C_SEQUENCE_SPEC): Pass -no_pie for
695 non-PIC code when targeting 10.7 or later.
697 2011-12-03 Iain Sandoe <iains@gcc.gnu.org>
699 * config/darwin.h (STARTFILE_SPEC): Do not use -lbundle1.o when
701 (DARWIN_DYLIB1_SPEC): Do not use -ldylib1.10.5.o when Darwin >= 10.
702 (DARWIN_CRT1_SPEC): Use -lcrt1.10.6.o when Darwin >= 10.
704 2011-12-03 Jakub Jelinek <jakub@redhat.com>
706 * fold-const.c (fold_unary_loc): Fold VEC_UNPACK_LO_EXPR,
707 VEC_UNPACK_HI_EXPR, VEC_UNPACK_FLOAT_LO_EXPR and
708 VEC_UNPACK_FLOAT_HI_EXPR with VECTOR_CST argument.
709 (fold_binary_loc): Fold VEC_PACK_TRUNC_EXPR,
710 VEC_PACK_FIX_TRUNC_EXPR, VEC_WIDEN_MULT_LO_EXPR
711 and VEC_WIDEN_MULT_HI_EXPR with VECTOR_CST arguments.
714 * tree-ssa.c (target_for_debug_bind): Also allow is_gimple_reg_type
715 vars that aren't referenced.
716 (tree-ssa-live.c (remove_unused_locals): Don't clear TREE_ADDRESSABLE
717 of unreferenced local vars.
718 * cfgexpand.c (expand_debug_expr): For DEBUG_IMPLICIT_PTR allow also
719 TREE_ADDRESSABLE vars that satisfy target_for_debug_bind.
721 2011-12-03 Anatoly Sokolov <aesok@post.ru>
723 * config/arm/arm.h (LIBCALL_VALUE, FUNCTION_VALUE_REGNO_P): Remove.
724 * config/arm/arm-protos.h (aapcs_libcall_value): Remove.
725 * config/arm/arm.c (TARGET_FUNCTION_VALUE_REGNO_P): Define.
726 (arm_libcall_value_1, arm_function_value_regno_p): New function.
727 (arm_function_value, arm_libcall_value): Use arm_libcall_value_1.
728 (aapcs_libcall_value): Make static.
729 (arm_libcall_value): Add static qualifier.
731 2011-12-02 Jakub Jelinek <jakub@redhat.com>
734 * config/i386/sse.md (mul<mode>3 with VI1_AVX2 iterator): For
735 V32QImode use { 0,2,..,14,32,34,..,46,16,18,..,30,48,50,..,62 }
736 permutation instead of extract even permutation.
738 2011-12-02 Nathan Sidwell <nathan@acm.org>
740 * gcov.c (struct arc_info): Add is_throw field.
741 (struct (block_info): Add exceptional field, reduce flags size to
743 (struct function_info): Add has_catch field.
744 (struct line_info): Add unexceptional field.
745 (process_file): Call find_exception_blocks if necessary.
746 (read_graph_file): Adjust. Note if an exceptional edge is seen.
747 (find_exception_blocks): New.
748 (add_line_counts): Set line's unexceptional flag if not
750 (output_branch_count): Note exceptional arcs, lines and blocks.
751 * gcov-dump.c (tag_arcs): Decode arc flags.
752 * doc/gcov.texi: Document '=====' lines.
754 2011-12-02 Anatoly Sokolov <aesok@post.ru>
756 * config/ia64/ia64.h (PRINT_OPERAND, PRINT_OPERAND_ADDRESS,
757 PRINT_OPERAND_PUNCT_VALID_P): Remove macros.
758 * config/ia64/ia64-protos.h (ia64_print_operand,
759 ia64_print_operand_address): Remove.
760 * config/ia64/ia64.c (TARGET_PRINT_OPERAND,
761 TARGET_PRINT_OPERAND_ADDRESS, TARGET_PRINT_OPERAND_PUNCT_VALID_P):
763 (ia64_print_operand_punct_valid_p): New function.
764 (ia64_print_operand, ia64_print_operand_address): Make static.
766 2011-12-02 Michael Meissner <meissner@the-meissners.org>
769 * config/rs6000/rs6000.c (def_builtin): Use the correct field to
770 figure out the function's attributes.
771 (struct builtin_description): Mark mask field as const since we no
772 longer need to modify it for SPE and PAIRED builtins.
774 2011-12-02 Joseph Myers <joseph@codesourcery.com>
778 2008-09-18 Andrew Pinski <andrew_pinski@playstation.sony.com>
781 * loop-doloop.c (doloop_modify): New argument zero_extend_p and
782 zero extend count after the correction to it is done.
783 (doloop_optimize): Update call to doloop_modify, don't zero extend
786 2008-11-03 Andrew Pinski <andrew_pinski@playstation.sony.com>
789 * loop-doloop.c (doloop_modify): Add from_mode argument that says what
791 (doloop_optimize): Update call to doloop_modify.
793 2011-12-02 Richard Guenther <rguenther@suse.de>
796 * ipa.c (varpool_externally_visible_p): Register variables
797 are always externally visible.
799 2011-12-02 Sameera Deshpande <sameera.deshpande@arm.com>
801 * gimple-pretty-print.c (dump_gimple_call): Dereference fn only if
804 2011-12-02 Martin Jambor <mjambor@suse.cz>
806 PR tree-optimization/50622
807 * tree-sra.c (load_assign_lhs_subreplacements): Force gimple operand
808 if both lacc and racc are grp_partial_lhs.
810 2011-12-01 Kaz Kojima <kkojima@gcc.gnu.org>
813 * config/sh/sh.c (expand_ashiftrt): Handle TARGET_SH2A same as
815 (shl_sext_kind): Likewise.
816 * config/sh/sh.h (SH_DYNAMIC_SHIFT_COST): Likewise.
817 * config/sh/sh.md (ashlsi3_sh2a, ashrsi3_sh2a, lshrsi3_sh2a): Remove.
818 (ashlsi3_std): Handle TARGET_SH2A same as TARGET_SH3.
820 (ashrsi3_d): Likewise.
821 (lshrsi3_d): Likewise.
824 2011-12-01 Diego Novillo <dnovillo@google.com>
827 * ipa-inline.c (can_inline_edge_p): If the edge E has a statement,
828 use the statement's inline indicator instead of E's.
829 Remove consistency check.
831 2011-12-01 Diego Novillo <dnovillo@google.com>
836 2011-11-29 Diego Novillo <dnovillo@google.com>
838 * gimple.c (gimple_call_set_cannot_inline): Move from gimple.h.
839 Update field call_stmt_cannot_inline_p from call
840 graph edge, if needed.
841 * gimple.h (gimple_call_set_cannot_inline): Move to gimple.c.
843 2011-12-01 Nathan Sidwell <nathan@acm.org>
845 PR gcov-profile/51113
846 * coverage.c (build_var): Keep coverage variables static.
848 2011-12-01 Jakub Jelinek <jakub@redhat.com>
850 PR tree-optimization/51356
851 * tree-vect-patterns.c (vect_recog_bool_pattern): Give up if
852 vectype doesn't have VECTOR_MODE_P.
855 * tree-ssa-dce.c (remove_dead_stmt): Add a debug stmt when removing
856 as unnecessary a store to a variable with gimple reg type.
857 * tree-ssa-live.c (remove_unused_locals): Clear TREE_ADDRESSABLE bit
858 on local unreferenced variables.
859 * cfgexpand.c (expand_gimple_basic_block): Don't emit DEBUG_INSNs
860 for !target_for_debug_bind variables.
862 2011-12-01 Patrick Marlier <patrick.marlier@gmail.com>
865 * cgraph.h (cgraph_call_node_duplication_hooks): Declare.
866 * cgraph.c (cgraph_call_node_duplication_hooks): Make global.
867 * cgraphunit.c (cgraph_copy_node_for_versioning): Call it.
869 2011-12-01 Andrew Pinski <apinski@cavium.com>
872 * tree.c (free_lang_data_in_decl): Clear FIELD_DECL's
875 2011-12-01 Jakub Jelinek <jakub@redhat.com>
877 PR tree-optimization/51246
878 * tree-predcom.c (replace_ref_with): Handle also clobber on the rhs.
880 PR rtl-optimization/51014
881 * loop-unroll.c (apply_opt_in_copies): Ignore label DEBUG_INSNs
882 both from bb and orig_bb.
884 2011-12-01 Joern Rennecke <joern.rennecke@embecosm.com>
886 PR tree-optimization/50802
887 * tree-vrp.c (simplify_conversion_using_ranges): Rewrite test
888 considering what happens to ranges during sign changes and/or
889 intermediate narrowing conversions.
891 2011-11-30 John David Anglin <dave.anglin@nrc-cnrc.gc.ca>
894 * config/pa/pa.md (in_branch_delay): Disallow frame related insns.
895 (in_nullified_branch_delay): Likewise.
896 (in_call_delay): Likewise.
898 2011-11-30 Richard Henderson <rth@redhat.com>
900 * predict.c (expr_expected_value_1): Assume compare-and-swap builtin
901 boolean return is true.
903 2011-11-30 Jakub Jelinek <jakub@redhat.com>
905 PR rtl-optimization/51044
906 * dse.c (emit_inc_dec_insn_before): Ensure new_insn is an instruction
907 rather than just insn body.
910 * function.c (thread_prologue_and_epilogue_insns): If
911 stack_realign_drap, add drap_reg to SET_UP_BY_PROLOGUE
915 * tree-eh.c (cleanup_empty_eh_merge_phis): Add check to
916 avoid creating duplicate edges here.
917 (cleanup_empty_eh_unsplit): And remove it in the caller.
919 2011-11-30 Andrew Pinski <apinski@cavium.com>
922 * c-parser.c (c_parser_postfix_expression): Check groktypename results
923 before looking at the main variant.
925 2011-11-30 Jakub Jelinek <jakub@redhat.com>
927 PR rtl-optimization/48721
928 * sched-deps.c (sched_analyze_insn): For SIBLING_CALL_P set
929 reg_pending_barrier to TRUE_BARRIER.
931 PR rtl-optimization/48721
932 * sched-ebb.c (begin_move_insn): Insert empty unreachable
933 block after BARRIER if insn is followed by it.
935 2011-11-30 Richard Henderson <rth@redhat.com>
937 * config/sparc/sparc-opts.h (enum sparc_memory_model_type): New.
938 * config/sparc/sparc.opt (mmemory-model=): New option.
939 * doc/invoke.texi (Sparc Options): Document it.
940 * config/sparc/sparc.c (sparc_option_override): Provide default
941 for sparc_memory_model.
942 (sparc_emit_membar_for_model): Omit barrier combinations that are
943 implied by the memory model.
945 2011-11-30 Richard Henderson <rth@redhat.com>
947 * config/sparc/sync.md (I124MODE): New mode iterator.
948 (memory_barrier): Remove.
949 (atomic_exchangesi): New.
950 (swapsi): Rename from *swapsi.
951 (atomic_test_and_set<I124MODE>): New.
952 (ldstubqi): Rename from *ldstubqi, merge with expander.
953 (ldstub<I24MODE>): Rename from *ldstub<I24MODE>, merge with expander.
954 (sync_lock_test_and_setsi): Remove.
955 (sync_lock_test_and_set<I12MODE>): Remove.
957 2011-11-30 Richard Henderson <rth@redhat.com>
959 * config/sparc/constraints.md ("w"): New.
960 * config/sparc/predicates.md (mem_noofs_operand): New.
961 * config/sparc/sparc.c (sparc_expand_compare_and_swap_12): Make static.
962 Generate the boolean result of the atomic_compare_exchange.
963 (sparc_expand_compare_and_swap): New.
964 * config/sparc/sync.md (atomic_compare_and_swap<I>): New.
965 (atomic_compare_and_swap<I48MODE>_1): Rename from
966 *sync_compare_and_swap<I48MODE>, use mem_noofs_operand.
967 (*atomic_compare_and_swapdi_v8plus): Rename from
968 *sync_compare_and_swapdi_v8plus, use mem_noofs_operand.
969 (sync_compare_and_swap<I12MODE>): Remove.
970 (sync_compare_and_swap<I48MODE>): Remove.
972 2011-11-30 Richard Henderson <rth@redhat.com>
974 * config/sparc/predicates.md (register_or_v9_zero_operand): New.
975 * config/sparc/sparc.md (UNSPEC_ATOMIC): New.
976 * config/sparc/sync.md (atomic_load<I>): New.
977 (atomic_loaddi_1, atomic_store<I>, atomic_storedi_1): New.
979 2011-11-30 Richard Henderson <rth@redhat.com>
981 * config/sparc/predicates.md (zero_or_v7_operand): New.
982 * config/sparc/sparc.c (sparc_emit_membar_for_model): New.
983 * config/sparc/sparc-protos.h: Update.
984 * config/sparc/sync.md (mem_thread_fence): New.
985 (memory_barrier): Use sparc_emit_membar_for_model.
986 (membar, *membar_empty, *membar_storestore, *membar_storeload): New.
987 (*membar_v8): Accept and ignore the membar mask.
988 (*membar): Accept and print the membar mask.
990 2011-11-30 Matthew Gretton-Dann <matthew.gretton-dann@arm.com>
992 * config/arm/arm.c (arm_issue_rate): Cortex-A15 can triple issue.
993 * config/arm/arm.md (mul64): New attribute.
994 (generic_sched): Cortex-A15 is not scheduled generically.
995 (cortex-a15.md): Include.
996 * config/arm/cortex-a15.md: New machine description.
997 * config/arm/t-arm (MD_INCLUDES): Add cortex-a15.md.
999 2011-11-30 Matthew Gretton-Dann <matthew.gretton-dann@arm.com>
1001 * config/arm/t-arm (MD_INCLUDES): Ensure all md files are listed.
1003 2011-11-30 Iain Sandoe <iains@gcc.gnu.org>
1005 * doc/tm.texi.in (NEXT_OBJC_RUNTIME): Update macro description.
1006 * doc/tm.texi: Regenerate.
1007 * flags.h (flag_next_runtime): Remove references.
1008 * toplev.c: Likewise.
1009 * defaults.h (NEXT_OBJC_RUNTIME): Provide default.
1010 * gccspec.c (lang_specific_driver): Adjust use of NEXT_OBJC_RUNTIME.
1011 * config/darwin.c (darwin_override_options): Provide default
1012 Objective-C abi settings and target conflict checks.
1013 * config/darwin.h (SUBTARGET_C_COMMON_OVERRIDE_OPTIONS): Remove unused
1014 code. Adjust indenting.
1016 2011-11-29 Joseph Myers <joseph@codesourcery.com>
1018 * config/sh/sh.h (enum reg_class, REG_CLASS_NAMES)
1019 (REG_CLASS_CONTENTS): Add NON_SP_REGS.
1020 (REGCLASS_HAS_GENERAL_REG): Handle NON_SP_REGS.
1021 * config/sh/constraints.md (u): New constraint.
1023 2011-11-29 Oleg Endo <oleg.endo@t-online.de>
1026 * config/sh/sh.c (sh_secondary_reload): Add case when FPUL
1027 register is being loaded from a pseudo in memory.
1029 2011-11-29 DJ Delorie <dj@redhat.com>
1031 * config.gcc (rl78-*-elf): New case.
1032 * doc/extend.texi: Add RL78 documentation.
1033 * doc/invoke.texi: Likewise.
1034 * doc/md.texi: Likewise.
1035 * doc/contrib.texi: Add RL78.
1036 * doc/install.texi: Add rl78-*-elf.
1037 * config/rl78: New directory for the Renesas RL78.
1039 2011-11-29 Jakub Jelinek <jakub@redhat.com>
1041 PR tree-optimization/51247
1042 * tree-vrp.c (extract_range_from_assert): For signed 1-bit precision
1043 types instead of adding 1 subtract -1 and instead of subtracting 1
1044 add -1 to avoid overflows.
1046 2011-11-29 Andrew MacLeod <amacleod@redhat.com>
1049 * optabs.c (maybe_optimize_fetch_op): New. Look for more optimal
1050 instructions for a FECTH_OP or OP_FECTH sequence.
1051 (expand_atomic_fetch_op): Call maybe_optimize_fetch_op.
1053 2011-11-29 Uros Bizjak <ubizjak@gmail.com>
1055 * config/i386/sync.md (UNSPEC_LDA, UNSPEC_STA): New unspecs.
1056 (movdi_via_fpu): Remove.
1057 (loaddi_via_fpu): New insn pattern.
1058 (storedi_via_fpu): Ditto.
1059 (atomic_loaddi_fpu): Use loaddi_via_fpu and storedi_via_fpu.
1060 (atomic_storedi_fpu): Ditto.
1061 * reg-stack.c (get_true_reg): Handle UNSPEC_LDA.
1062 (subst_stack_regs_pat): Handle UNSPEC_STA.
1064 2011-11-29 Uros Bizjak <ubizjak@gmail.com>
1066 * config/i386/i386.md (*floathi<mode>2_i387_with_temp): Do not
1067 allocate scratch memory for alternative 0.
1069 2011-11-29 Michael Meissner <meissner@linux.vnet.ibm.com>
1071 * config/rs6000/rs6000-builtins.def: Completely rewrite builtin
1072 handling to centralize more of the builtins in this file. Change
1073 some builtin enumerations to be more consistant. Use a new mask
1074 to hold the current builtins, including SPE and PAIRED builtins
1075 which no longer are set via target_flags masks. Add
1076 -mdebug=builtin debug support. For power machines, define all
1077 Altivec and VSX buitins when the compiler starts, but don't allow
1078 the use of a builtin unless the appropriate switch is used, or
1079 #pragma GCC target is used to change the options. If the user
1080 uses #pragma GCC target, update the appropriate hardware macros.
1081 * common/config/rs6000/rs6000-common.c (rs6000_handle_option): Ditto.
1082 * config/rs6000/rs6000.opt (rs6000_builtin_mask): Ditto.
1083 * config/rs6000/rs6000-c.c (rs6000_macro_to_expand): Ditto.
1084 (rs6000_define_or_undefine_macro): Ditto.
1085 (rs6000_target_modify_macros): Ditto.
1086 (rs6000_cpu_cpp_builtins): Ditto.
1087 (altivec_overloaded_builtins): Ditto.
1088 (altivec_build_resolved_builtin): Ditto.
1089 * config/rs6000/rs6000.c (rs6000_target_modify_macros_ptr): Ditto.
1090 (rs6000_builtin_info): Ditto.
1091 (def_builtin): Ditto.
1092 (enable_mask_for_builtins): Ditto.
1093 (DEBUG_FMT_X): Ditto.
1094 (rs6000_debug_reg_global): Ditto.
1095 (rs6000_builtin_mask_calculate): Ditto.
1096 (rs6000_option_override_internal): Ditto.
1097 (rs6000_builtin_conversion): Ditto.
1098 (rs6000_builtin_vectorized_function): Ditto.
1099 (bdesc_3arg): Ditto.
1101 (bdesc_2arg): Ditto.
1102 (builtin_description_predicates): Ditto.
1103 (bdesc_altivec_preds): Ditto.
1104 (bdesc_spe_predicates): Ditto.
1105 (bdesc_spe_evsel): Ditto.
1106 (bdesc_paired_preds): Ditto.
1108 (bdesc_1arg): Ditto.
1109 (rs6000_overloaded_builtin_p): Ditto.
1110 (rs6000_expand_unop_builtin): Ditto.
1111 (bdesc_2arg_spe): Ditto.
1112 (spe_expand_builtin): Ditto.
1113 (rs6000_invalid_builtin): Ditto.
1114 (rs6000_expand_builtin): Ditto.
1115 (rs6000_init_builtins): Ditto.
1116 (spe_init_builtins): Ditto.
1117 (paired_init_builtins): Ditto.
1118 (altivec_init_builtins): Ditto.
1119 (builtin_function_type): Ditto.
1120 (rs6000_common_init_builtins): Ditto.
1121 (rs6000_builtin_reciprocal): Ditto.
1122 (rs6000_builtin_mask_names): Ditto.
1123 (rs6000_pragma_target_parse): Ditto.
1124 (rs6000_function_specific_print): Ditto.
1125 * config/rs6000/rs6000.h (MASK_DEBUG_BUILTIN): Ditto.
1126 (MASK_DEBUG_ALL): Ditto.
1127 (TARGET_DEBUG_BUILTIN): Ditto.
1128 (TARGET_EXTRA_BUILTINS): Ditto.
1129 (REGISTER_TARGET_PRAGMAS): Ditto.
1130 (enum rs6000_btc): Ditto.
1131 (RS6000_BTC_*): Ditto.
1132 (RS6000_BTM_*): Ditto.
1133 (enum rs6000_builtins): Ditto.
1134 * config/rs6000/rs6000-protos.h (rs6000_overloaded_builtin_p): Ditto.
1135 (rs6000_target_modify_macros): Ditto.
1136 (rs6000_target_modify_macros_ptr): Ditto.
1138 * config/rs6000/vector.md (unsfloat<VEC_int><mode>2): Use the
1139 standard name for converting vector unsigned values to floating
1140 point. Delete the TARGET_VECTORIZE_BUILTIN_CONVERSION hook, which
1141 is handled by machine independent code.
1142 * config/rs6000/rs6000.c (TARGET_VECTORIZE_BUILTIN_CONVERSION): Ditto.
1143 (rs6000_builtin_conversion): Ditto.
1145 2011-11-29 Dodji Seketeli <dodji@redhat.com>
1147 * tree-diagnostic (struct loc_t): Rename into struct loc_map_pair.
1148 (maybe_unwind_expanded_macro_loc): Adjust.
1150 2011-11-29 David Edelsohn <dje.gcc@gmail.com>
1151 Aldy Hernandez <aldyh@redhat.com>
1153 * trans-mem.c (ipa_tm_create_version_alias): Mangle new_decl
1155 (ipa_tm_create_version): Same.
1157 2011-11-29 Bernd Schmidt <bernds@codesourcery.com>
1159 * haifa-sched.c (recompute_todo_spec): Simplify and correct the
1160 code checking for a clobber of a condition register when deciding
1161 whether to predicate.
1163 2011-11-29 Diego Novillo <dnovillo@google.com>
1165 * gimple.c (gimple_call_set_cannot_inline): Move from gimple.h.
1166 Update field call_stmt_cannot_inline_p from call graph edge, if needed.
1167 * gimple.h (gimple_call_set_cannot_inline): Move to gimple.c.
1169 2011-11-29 Sameera Deshpande <sameera.deshpande@arm.com>
1171 * config/arm/arm.md (arm_movdi): Update NEG_POOL_RANGE.
1172 (movdf_soft_insn): Likewise.
1173 * config/arm/fpa.md (thumb2_movdf_fpa): Likewise.
1174 * config/arm/neon.md (neon_mov<mode>): Likewise.
1175 * config/arm/vfp.md (movdi_vfp): Likewise.
1176 (movdi_vfp_cortexa8): Likewise.
1177 (movdf_vfp): Likewise.
1179 2011-11-29 Jakub Jelinek <jakub@redhat.com>
1182 * expr.c (expand_expr_addr_expr_1): Don't call force_operand for
1183 EXPAND_SUM modifier.
1185 2011-11-29 Ira Rosen <ira.rosen@linaro.org>
1187 PR tree-optimization/51301
1188 * tree-vect-patterns.c (vect_recog_over_widening_pattern): Check that
1189 the last statement doesn't convert to a bigger type than the original
1190 type of the computation.
1192 2011-11-28 Richard Henderson <rth@redhat.com>
1194 * config/rs6000/rs6000.c (rs6000_expand_atomic_compare_and_swap):
1195 Handle overlap between retval and oldval. Always compute boolval
1198 2011-11-28 Jakub Jelinek <jakub@redhat.com>
1201 * tree-ssa.c (execute_update_addresses_taken): Remove
1202 var ={v} {CLOBBER} stmts instead of rewriting them into
1203 var_N ={v} {CLOBBER}.
1206 * function.c (convert_jumps_to_returns): When redirecting an edge
1207 succ to EXIT_BLOCK_PTR, clear EDGE_CROSSING flag.
1209 PR tree-optimization/50078
1210 * tree-ssa-forwprop.c (forward_propagate_addr_expr_1): Copy over
1211 TREE_THIS_VOLATILE also from the old to new lhs resp. rhs.
1213 PR tree-optimization/50682
1214 * tree-eh.c (maybe_remove_unreachable_handlers): New function.
1215 * tree-flow.h (maybe_remove_unreachable_handlers): New prototype.
1216 * tree-optimize.c (execute_cleanup_cfg_post_optimizing): Call it.
1218 2011-11-28 Georg-Johann Lay <avr@gjlay.de>
1220 * doc/extend.texi (AVR Built-in Functions): Add documentation for
1221 __builtin_avr_map8 and __builtin_avr_map16.
1223 * config/avr/avr.md: Document new %t and %T asm output codes.
1224 (define_c_enum "unspec"): Add UNSPEC_MAP_BITS.
1225 (adjust_len): Add map_bits.
1226 (map_bitsqi, map_bitshi): New insns.
1227 * config/avr/avr-protos.h (avr_out_map_bits): New.
1228 * config/avr/avr-protos.c (print_operand): Implement %t and %T.
1229 (adjust_insn_length): Handle ADJUST_LEN_MAP_BITS.
1230 (avr_double_int_push_digit): New function.
1231 (avr_map, avr_revert_map, avr_swap_map, avr_id_map): New functions.
1232 (avr_sig_map, avr_map_hamming_byte): New functions.
1233 (avr_out_swap_bits, avr_out_revert_bits, avr_move_bits,
1234 avr_out_map_bits): New functions.
1235 (enum avr_builtin_id): Add AVR_BUILTIN_MAP8, AVR_BUILTIN_MAP16.
1236 (avr_init_builtins): Populate __builtin_avr_map8, __builtin_avr_map16.
1237 (bdesc_2arg): Add __builtin_avr_map8, __builtin_avr_map16 ...
1238 (avr_expand_builtin): ...and expand them.
1239 * config/avr/avr-c.c (avr_cpu_cpp_builtins): New built-in defines:
1240 __BUILTIN_AVR_MAP8, __BUILTIN_AVR_MAP16.
1242 2011-11-27 Richard Sandiford <rdsandiford@googlemail.com>
1245 * config/mips/mips.c (mips_rtx_costs): Handle baddu.
1247 2011-11-27 Richard Sandiford <rdsandiford@googlemail.com>
1249 * config/mips/mips.c (mips16_unextended_reference_p): Test for BLKmode.
1251 2011-11-27 Richard Sandiford <rdsandiford@googlemail.com>
1253 * config/mips/mips-protos.h (mips_emit_binary): Declare.
1254 * config/mips/mips.c (mips_emit_binary): Make global.
1255 (mips_set_mips16_mode): Turn off -mfix-r4000 in MIPS16 mode.
1256 (mips_conditional_register_usage): Don't treat LO and HI as
1257 register operands in MIPS16 mode.
1258 (mips_mulsidi3_gen_fn): Use {u,}mulsidi3_{32,64}bit_mips16
1260 * config/mips/predicates.md (muldiv_target_operand): New predicate.
1261 (move_operand): Allow hilo_operand.
1262 * config/mips/mips.md (mul<mode>3): Explicitly specify LO as the
1263 target of MIPS16 multiplies, then move it into the target register.
1264 (mul<mode>3_internal, *macc2, *msac2): Use muldiv_target_operand.
1265 (<u>mulsidi3_32bit_mips16): New expander.
1266 (<u>mulsidi3_32bit): Use muldiv_target_operand.
1267 (<u>mulsidi3_32bit_r4000): Disable for ISA_HAS_DSP.
1268 (<u>mulsidi3_64bit): Require !TARGET_MIPS16. Split into
1269 <u>mulsidi3_64bit_split.
1270 (<u>mulsidi3_64bit_mips16): New expander.
1271 (<u>mulsidi3_64bit_split): Likewise, using expansions from
1272 two previous define_splits.
1273 (<u>mulsidi3_64bit_hilo, *muls<u>_di, <u>msubsidi4): Use
1274 muldiv_target_operand.
1275 (<su>mulsi3_highpart): Use <su>mulsi3_highpart_split for MIPS16 code.
1276 (<su>mulsi3_highpart_internal): Require !TARGET_MIPS16.
1277 Split into <su>mulsi3_highpart_split.
1278 (<su>mulsi3_highpart_split): New expander.
1279 (<su>muldi3_highpart): Turn into a define_expand.
1280 Use <su>muldi3_highpart_split for MIPS16 code.
1281 (<su>muldi3_highpart_internal): Renamed from <su>muldi3_highpart.
1282 Require !TARGET_MIPS16. Split into <su>muldi3_highpart_split.
1283 (<su>muldi3_highpart_split): New expander.
1284 (<u>mulditi3): Explicitly specify LO as the target of MIPS16
1285 multiplies, then move it into the target register.
1286 (<u>mulditi3_internal, <u>maddsidi4): Use muldiv_target_operand.
1287 (divmod<mode>4, udivmod<mode>4): Turn into define_expands.
1288 Use <u>divmod<mode>4_split for MIPS16 code, then explicitly
1289 move LO into operand 0.
1290 (divmod<mode>4_internal, udivmod<mode>4_internal): Renamed
1291 from <u>divmod<mode>4. Use muldiv_target_operand.
1292 Require !TARGET_MIPS16. Split into <u>divmod<mode>4_split.
1293 (<u>divmod<mode>4_split): New expander.
1294 (<u>divmod<GPR:mode>4_hilo_<HILO:mode>): Use muldiv_target_operand.
1295 (mfhi<GPR:mode>_<HILO:mode>): Use hilo_operand.
1297 2011-11-27 Richard Sandiford <rdsandiford@googlemail.com>
1299 * hard-reg-set.h (target_hard_regs): Add x_accessible_reg_set
1300 and x_operand_reg_set.
1301 (accessible_reg_set, operand_reg_set): New macros.
1302 * reginfo.c (init_reg_sets): Initialize accessible_reg_set and
1304 (saved_accessible_reg_set, saved_operand_reg_set): New variables.
1305 (save_register_info): Save them.
1306 (restore_register_info): Restore them.
1307 (init_reg_sets_1): Limit operand_reg_set to accessible_reg_set.
1308 Remove NO_REGS registers from operand_reg_set. Treat members
1309 of operand_reg_set as fixed.
1310 * recog.c (general_operand): Check operand_reg_set rather than NO_REGS.
1311 (register_operand, nonmemory_operand): Likewise.
1312 * varasm.c (make_decl_rtl): Always use DECL_MODE as the mode of
1313 register variables. Check accessible_reg_set and operand_reg_set.
1314 * config/mips/mips.c (mips_conditional_register_usage): Remove
1315 inaccessible register from accessible_reg_set, rather than just
1318 2011-11-27 Gerald Pfeifer <gerald@pfeifer.com>
1320 * config/pa/pa-linux.h (TARGET_GAS): Remove comment.
1322 2011-11-26 Richard Henderson <rth@redhat.com>
1324 * config/arm/arm.c (arm_init_libfuncs): Call init_sync_libfuncs
1327 2011-11-26 Richard Henderson <rth@redhat.com>
1329 * optabs.c (expand_atomic_fetch_op): Always return result.
1331 * optabs.c (init_sync_libfuncs_1): Include max in iteration.
1333 * omp-low.c (expand_omp_atomic): Assume anything aligned to
1334 BIGGEST_ALIGNMENT is aligned.
1336 2011-11-26 Richard Henderson <rth@redhat.com>
1338 * config/m68k/m68k.md (UNSPECV_CAS_1, UNSPECV_CAS_2): New.
1339 (UNSPECV_TAS_1, UNSPECV_TAS_2): New.
1340 (I): New mode iterator.
1341 (xz): New mode attribute.
1342 * config/m68k/sync.md: New file.
1344 * config/m68k/linux.h (TARGET_INIT_LIBFUNCS): New.
1345 * config/m68k/m68k.c (m68k_init_sync_libfuncs): New.
1347 2011-11-26 Nathan Sidwell <nathan@acm.org>
1349 PR gcov-profile/51297
1350 * gcov.c (main): Allocate initial names and sources arrays.
1351 (find_source): Don't check for null name or source arrays here.
1353 2011-11-26 Jakub Jelinek <jakub@redhat.com>
1355 PR rtl-optimization/49912
1356 * cfgrtl.c (rtl_verify_flow_info_1): Ignore also EDGE_PRESERVE bit
1357 when counting n_branch.
1359 2011-11-26 Uros Bizjak <ubizjak@gmail.com>
1361 * config/i386/sync.md (movdi_via_fpu): Add %Z insn suffixes.
1363 2011-11-26 Joern Rennecke <joern.rennecke@embecosm.com>
1366 * calls.c (mem_overlaps_already_clobbered_arg_p):
1367 Return false if no outgoing arguments have been stored so far.
1369 2011-11-25 Georg-Johann Lay <avr@gjlay.de>
1371 * config/avr/avr.c (print_operand): Support code = 'i' for CONST_INT.
1373 2011-11-24 Andrew MacLeod <amacleod@redhat.com>
1376 * tree.h (is_builtin_name): No longer external.
1377 * builtins.c (is_builtin_name): Make static.
1378 * varasm.c (incorporeal_function_p): __sync and __atomic external calls
1379 are not incorporeal and may need asm label processing.
1381 2011-11-25 Georg-Johann Lay <avr@gjlay.de>
1384 * config/avr/avr-protos.h (avr_log_t): Add field .builtin.
1385 * config/avr/avr-log.c (avr_log_set_avr_log): Initialize it.
1386 Don't bypass TARGET_ALL_DEBUG. Print self-info with ?.
1387 (avr_log_vadump): Support %D and %X to print double_int.
1388 (avr_double_int_pop_digit): New static function.
1389 (avr_dump_double_int_hex): New static function.
1391 2011-11-24 Enkovich Ilya <ilya.enkovich@intel.com>
1394 * config/i386/i386.c (distance_non_agu_define_in_bb): Fix insn
1397 2011-11-24 Andrew MacLeod <amacleod@redhat.com>
1399 * optab.c (maybe_emit_atomic_exchange): New. Try to emit an
1400 atomic_exchange pattern.
1401 (maybe_emit_sync_lock_test_and_set): New. Try to emit an exchange
1402 using __sync_lock_test_and_set.
1403 (maybe_emit_compare_and_swap_exchange_loop): New. Try to emit an
1404 exchange using a compare_and_swap loop.
1405 (expand_sync_lock_test_and_set): New. Expand sync_lock_test_and_set.
1406 (expand_atomic_test_and_set): New. Expand test_and_set operation.
1407 (expand_atomic_exchange): Use new maybe_emit_* functions.
1408 (expand_atomic_store): Use new maybe_emit_* functions.
1409 * builtins.c (expand_builtin_sync_lock_test_and_set): Call
1410 expand_sync_lock_test_and_set routine.
1411 (expand_builtin_atomic_exchange): Remove parameter from call.
1412 (expand_builtin_atomic_clear): Use atomic_clear pattern if present.
1413 (expand_builtin_atomic_test_and_set): Add target and simply call
1414 expand_atomic_test_and_set.
1415 (expand_builtin): Add target to expand_builtin_atomic_test_and_set.
1416 * expr.h (expand_atomic_exchange): Add parameter.
1417 (expand_sync_lock_test_and_set): New prototype.
1418 (expand_atomic_test_and_set, expand_atomic_clear): New prototypes.
1420 2011-11-24 H.J. Lu <hongjiu.lu@intel.com>
1423 * config/i386/i386.h (processor_costs): Revert revision 181357.
1424 * config/i386/i386.c (cost models): Likewise.
1425 (core_cost): Likewise.
1426 (promote_duplicated_reg): Likewise.
1427 (promote_duplicated_reg_to_size): Likewise.
1428 (processor_target): Likewise.
1429 (expand_set_or_movmem_via_loop_with_iter): Likewise.
1430 (expand_set_or_movmem_via_loop): Likewise.
1431 (emit_strset): Likewise.
1432 (expand_movmem_epilogue): Likewise.
1433 (expand_setmem_epilogue): Likewise.
1434 (expand_movmem_prologue): Likewise.
1435 (expand_setmem_prologue): Likewise.
1436 (expand_constant_movmem_prologue): Likewise.
1437 (expand_constant_setmem_prologue): Likewise.
1438 (decide_alg): Likewise.
1439 (decide_alignment): Likewise.
1440 (ix86_expand_movmem): Likewise.
1441 (ix86_expand_setmem): Likewise.
1442 (ix86_slow_unaligned_access): Likewise.
1443 * config/i386/i386.md (strset): Likewise.
1444 * config/i386/sse.md (vec_dupv4si): Likewise.
1445 (vec_dupv2di): Likewise.
1447 2011-11-24 Georg-Johann Lay <avr@gjlay.de>
1449 * config/avr/avr.md (*rotlhi2.15): Set length to 4.
1451 2011-11-24 Razya Ladelsky <razya@il.ibm.com>
1453 * tree-data-ref.c (initialize_data_dependence_relation): Update
1454 comment for the self dependence case.
1455 (compute_self_dependence): Remove.
1456 * tree-vect-data-refs.c (vect_analyze_data_refs): Remove call to
1457 compute_self_dependenc.
1459 2011-11-24 Alan Modra <amodra@gmail.com>
1461 * c-decl.c (warn_if_shadowing): Don't warn if shadowed
1462 identifier is from system header.
1464 2011-11-23 Jakub Jelinek <jakub@redhat.com>
1467 * config/i386/i386.c (decide_alg): Initialize *dynamic_check
1470 2011-11-23 Vladimir Makarov <vmakarov@redhat.com>
1472 PR rtl-optimization/48455
1473 * doc/invoke.texi (-fira-region): Document default values.
1475 * flags-types.h (enum ira_region): Add new value
1476 IRA_REGION_AUTODETECT.
1478 * common.opt (fira-region): Set up initial value to
1479 IRA_REGION_AUTODETECT.
1481 * toplev.c (process_options): Set up flag_ira_region depending on
1484 * ira.c (ira.c): Remove optimize guard for ira_build.
1486 2011-11-23 Chung-Lin Tang <cltang@codesourcery.com>
1488 PR rtl-optimization/50496
1489 * jump.c (redirect_jump): Assert fail on nlabel == NULL_RTX
1490 only after epilogue is created. Add comments.
1492 2011-11-22 Richard Henderson <rth@redhat.com>
1494 * config/ia64/ia64.c (ia64_expand_atomic_op): Add model parameter.
1495 Generate the barrier required for the memory model.
1496 (rtx_needs_barrier): Handle UNSPEC_FETCHADD_REL, UNSPEC_CMPXCHG_REL.
1497 * config/ia64/ia64-protos.h: Update.
1498 * config/ia64/ia64.md (UNSPEC_FETCHADD_REL): New.
1499 (UNSPEC_CMPXCHG_REL): New.
1500 * config/ia64/sync.md (mem_thread_fence): New.
1501 (atomic_load<IMODE>, atomic_store<IMODE>): New.
1502 (atomic_compare_and_swap<IMODE>): New.
1503 (cmpxchg_acq_<I124MODE>, cmpxchg_acq_di): New.
1504 (atomic_exchange<IMODE>): New.
1505 (xchg_acq_<IMODE>): Rename from sync_lock_test_and_set<IMODE>.
1506 (atomic_<FETCHOP><IMODE>, atomic_nand<IMODE>): New.
1507 (atomic_fetch_<FETCHOP><IMODE>, atomic_fetch_nand<IMODE>): New.
1508 (atomic_<FETCHOP>_fetch<IMODE>, atomic_nand_fetch<IMODE>): New.
1509 (fetchadd_rel_<I48MODE>): New.
1510 (sync_<FETCHOP><IMODE>, sync_nand<IMODE>): Remove.
1511 (sync_old_<FETCHOP><IMODE>, sync_old_nand<IMODE>): Remove.
1512 (sync_new_<FETCHOP><IMODE>, sync_new_nand<IMODE>): Remove.
1513 (sync_compare_and_swap<IMODE>): Remove.
1514 (sync_lock_release<IMODE>): Remove.
1516 * config/ia64/ia64.md: Use define_c_enum for UNSPEC_*
1517 and UNSPECV_* constants.
1519 2011-11-22 Tom de Vries <tom@codesourcery.com>
1521 PR rtl-optimization/50764
1522 * sched-deps.c (sched_analyze_insn): Make sure frame-related insns are
1523 not moved past preceding jump.
1525 2011-11-22 Jeff Law <law@redhat.com>
1527 * doc/contrib.texi: Add entry for David Binderman.
1529 2011-11-22 Andreas Krebbel <Andreas.Krebbel@de.ibm.com>
1531 * postreload.c (reload_combine): Mark reg_state as invalid at
1532 volatile insns if there has been a use already.
1534 2011-11-21 Aldy Hernandez <aldyh@redhat.com>
1536 * opts.c (finish_options): Do not fail for -fgnu-tm.
1537 * gimple-streamer-out.c (output_gimple_stmt): Handle
1539 * gimple-streamer-in.c (input_gimple_stmt): Same.
1540 * lto-cgraph.c (input_overwrite_node): Read tm_clone bit.
1541 (lto_output_node): Write tm_clone bit.
1543 2011-11-22 Ian Lance Taylor <iant@google.com>
1545 * doc/install.texi (Configuration): Correct doc of
1546 --enable-build-poststage1-with-cxx: it is not experimental.
1548 2011-11-22 Jakub Jelinek <jakub@redhat.com>
1550 PR tree-optimization/51074
1551 * fold-const.c (fold_binary_loc): Fix up VEC_INTERLEAVE_*_EXPR
1552 handling for BYTES_BIG_ENDIAN.
1553 * optabs.c (can_vec_perm_for_code_p): Likewise.
1555 2011-11-22 Michael Matz <matz@suse.de>
1558 * trans-mem.c (expand_block_tm): Ignore clobbers.
1560 2011-11-22 Iain Sandoe <iains@gcc.gnu.org>
1562 * config/darwin.h (ENDFILE_SPEC): New.
1563 (DARWIN_CRT1_SPEC): Add crttms.o.
1564 (STARTFILE_SPEC): Likewise for dynamic libs and bundles.
1565 * config/i386.h (ENDFILE_SPEC): Amend to include crttme.o.
1567 2011-11-22 Michael Matz <matz@suse.de>
1570 * tree.c (iterative_hash_expr): Remove break after return.
1572 2011-11-22 Iain Sandoe <iains@gcc.gnu.org>
1574 * target.def (tm_clone_table_section): New hook.
1575 * doc/tm.texi.in (TARGET_ASM_TM_CLONE_TABLE_SECTION): Define.
1576 * doc/tm.texi: Regenerate.
1577 * varasm.c (dump_tm_clone_pairs): Use target tm_clone_table_section.
1578 * output.h (default_clone_table_section): New prototype.
1579 * config/darwin.h (TARGET_ASM_TM_CLONE_TABLE_SECTION): New.
1580 * config/darwin-protos.h (darwin_tm_clone_table_section): New prototype.
1581 * config/darwin.c (darwin_tm_clone_table_section): New.
1583 2011-11-21 Torvald Riegel <triegel@redhat.com>
1585 * trans-mem.c (diagnose_tm_1): Print an expression instead of a
1586 declaration in error messages for indirect calls.
1588 2011-11-21 David S. Miller <davem@davemloft.net>
1590 * config/sparc/sparc.c (sparc_regmode_natural_size): New function
1591 implementing REGMODE_NATURAL_SIZE taking into consideration vector
1593 (sparc_modes_tieable_p): Similarly for MODES_TIEABLE_P.
1594 * config/sparc/sparc-protos.h (sparc_regmode_natural_size,
1595 sparc_modes_tieable_p): Declare.
1596 * gcc/config/sparc/sparc.h (REGMODE_NATURAL_SIZE,
1597 MODES_TIEABLE_P): Use new helper functions.
1600 2011-11-16 Andreas Krebbel <Andreas.Krebbel@de.ibm.com>
1603 * expmed.c (store_bit_field_1): Use extract_bit_field on big
1604 endian targets if the source cannot be exactly covered by word
1607 2011-11-21 Jakub Jelinek <jakub@redhat.com>
1610 * var-tracking.c (loc_cmp): For ENTRY_VALUEs use ENTRY_VALUE_EXP
1611 macro instead of XEXP.
1613 2011-11-21 Andreas Tobler <andreast@fgznet.ch>
1615 * configure: Regenerate.
1617 2011-11-21 Georg-Johann Lay <avr@gjlay.de>
1619 * config/avr/avr.c (output_reload_in_const): Loading a byte with 0
1620 must not affect cc0.
1621 * config/avr/avr.md (*movhi, *movpsi, *movsi, *movsf): Zero to any
1622 register does not change cc0. Same for any constant to ld-register.
1624 2011-11-21 Uros Bizjak <ubizjak@gmail.com>
1626 * config/i386/mmx.md (unspec) <UNSPEC_MOVNTQ, UNSPEC_PFRCP,
1627 UNSPEC_PFRCPIT1, UNSPEC_PFRCPIT2, UNSPEC_PFRSQRT, UNSPEC_PFRSQIT1>:
1628 Move from config/i386/i386.md
1629 (unspecv) <UNSPECV_EMMS, UNSPECV_FEMMS>: Ditto.
1630 * config/i386/sse.md (unspec) <UNSPEC_MOVNT,UNSPEC_MOVU, UNSPEC_LDDQU,
1631 UNSPEC_PSHUFB, UNSPEC_PSIGN, UNSPEC_PALIGNR, UNSPEC_EXTRQI,
1632 UNSPEC_EXTRQ, UNSPEC_INSERTQI, UNSPEC_INSERTQ, UNSPEC_BLENDV,
1633 UNSPEC_INSERTPS, UNSPEC_DP, UNSPEC_MOVNTDQA, UNSPEC_MPSADBW,
1634 UNSPEC_PHMINPOSUW, UNSPEC_PTEST, UNSPEC_PCMPESTR, UNSPEC_PCMPISTR,
1635 UNSPEC_FMADDSUB, UNSPEC_XOP_UNSIGNED_CMP, UNSPEC_XOP_TRUEFALSE,
1636 UNSPEC_XOP_PERMUTE, UNSPEC_FRCZ, UNSPEC_AESENC, UNSPEC_AESENCLAST,
1637 UNSPEC_AESDEC, UNSPEC_AESDECLAST, UNSPEC_AESIMC,
1638 UNSPEC_AESKEYGENASSIST, UNSPEC_PCLMUL, UNSPEC_PCMP, UNSPEC_VPERMIL,
1639 UNSPEC_VPERMIL2, UNSPEC_VPERMIL2F128, UNSPEC_CAST, UNSPEC_VTESTP,
1640 UNSPEC_VCVTPH2PS, UNSPEC_VCVTPS2PH, UNSPEC_VPERMSI, UNSPEC_VPERMDF,
1641 UNSPEC_VPERMSF, UNSPEC_VPERMTI, UNSPEC_GATHER, UNSPEC_VSIBADDR>: Ditto.
1642 (unspecv) <UNSPECV_LDMXCSR, UNSPECV_STMXCSR, UNSPECV_CLFLUSH,
1643 UNSPECV_MONITOR, UNSPECV_MWAIT, UNSPECV_VZEROALL, UNSPECV_VZEROUPPER>:
1645 * config/i386/sync.md (unspec) <UNSPEC_LFENCE, UNSPEC_SFENCE,
1646 UNSPEC_MFENCE, UNSPEC_MOVA>: Ditto.
1647 (unspecv) <UNSPECV_CMPXCHG_1, UNSPECV_CMPXCHG_2, UNSPECV_CMPXCHG_3,
1648 UNSPECV_CMPXCHG_4, UNSPECV_XCHG, UNSPECV_LOCK>: Ditto.
1649 (sse2_lfence): Move from config/i386/sse.md.
1650 (*sse2_lfence): Ditto.
1651 (sse_sfence): Ditto.
1652 (*sse_sfence): Ditto.
1653 (sse2_mfence): Ditto.
1654 (mfence_sse2): Ditto. Rename from *sse2_mfence. Enable also
1656 (mem_thread_fence): Use mfence_sse2.
1658 2011-11-21 Georg-Johann Lay <avr@gjlay.de>
1660 * config/avr/avr.h (struct base_arch_s): Add field sfr_offset.
1661 * config/avr/avr-devices.c: Ditto. And initialize it.
1662 * config/avr/avr-c.c (avr_cpu_cpp_builtins): New built-in define
1664 * config/avr/avr-protos.h (out_movqi_r_mr, out_movqi_mr_r): Remove.
1665 (out_movhi_r_mr, out_movhi_mr_r): Remove.
1666 (out_movsi_r_mr, out_movsi_mr_r): Remove.
1667 * config/avr/avr.md (*cbi, *sbi): Use %i instead of %m-0x20.
1668 (*insv.io, *insv.not.io): Ditto.
1669 * config/avr/avr.c (out_movsi_r_mr, out_movsi_mr_r): Make static.
1670 (print_operand): Implement "%i" to print address as I/O address.
1671 (output_movqi): Clean up call of out_movqi_mr_r.
1672 (output_movhi): Clean up call of out_movhi_mr_r.
1673 (avr_file_start): Use avr_current_arch->sfr_offset instead of
1674 magic -0x20. Use TMP_REGNO, ZERO_REGNO instead of 0, 1.
1675 (avr_out_sbxx_branch): Use %i instead of %m-0x20.
1676 (out_movqi_r_mr, out_movqi_mr_r): Ditto. And make static.
1677 (out_movhi_r_mr, out_movhi_mr_r): Ditto. And use avr_asm_len.
1678 (out_shift_with_cnt): Clean up code: Use avr_asm_len.
1679 (output_movsisf): Use output_reload_insisf for all CONSTANT_P sources.
1680 (avr_out_movpsi): USE avr_out_reload_inpsi for all CONSTANT_P sources.
1681 Clean up call of avr_out_store_psi.
1682 (output_reload_in_const): Don't cut symbols longer than 2 bytes.
1683 (output_reload_insisf): Filter CONST_INT_P or CONST_DOUBLE_P to
1684 try if setting pre-cleared register is advantageous.
1685 (avr_out_plus_1): Use gen_int_mode instead of GEN_INT.
1687 2011-11-20 Joey Ye <joey.ye@arm.com>
1689 * expr.c (expand_expr_real_1): Correctly handle strict volatile
1690 bitfield loads smaller than mode size.
1692 2011-11-20 Richard Henderson <rth@redhat.com>
1694 * config/mips/mips.c (mips_init_libfuncs): Call init_sync_libfuncs.
1696 2011-11-20 Uros Bizjak <ubizjak@gmail.com>
1699 * config/i386/i386.c (ix86_expand_vcond): Generate TARGET_XOP
1700 patterns for supported mode only.
1703 * config/i386/i386.c (ix86_expand_builtin)
1704 <IX86_BUILTIN_GATHERALTSIV4DI>: Use CODE_FOR_avx2_gathersiv4di.
1706 2011-11-20 Uros Bizjak <ubizjak@gmail.com>
1708 * config/i386/i386.md (UNSPEC_MOVNTI): Remove.
1709 (UNSPEC_MOVNTQ): New unspec.
1710 * config/i386/mmx.md (sse_movntq): Rename from sse_movntdi.
1711 Use UNSPEC_MOVNTQ instead of UNSPEC_MOVNT.
1712 * config/i386/sse.md (sse2_movnti<mode>): Use UNSPEC_MOVNT instead of
1714 (STORENT_MODE): Add DI and V4DI modes.
1716 2011-11-20 Nathan Sidwell <nathan@acm.org>
1718 PR gcov-profile/51113
1719 * coverage.c (build_var): Propagate visibility for public
1720 decls. Use make_decl_one_only for PIC correctness.
1723 * gcc.misc-tests/gcov-13.c: Check gcovpart-13b coverage
1724 * gcc.misc-tests/gcov-16.c: New.
1725 * gcc.misc-tests/gcov-17.c: New.
1726 * g++.dg/gcov/gcov-8.C: New.
1727 * g++.dg/gcov/gcov-9.C: New.
1728 * g++.dg/gcov/gcov-10.C: New.
1730 2011-11-19 Eric Botcazou <ebotcazou@adacore.com>
1732 PR rtl-optimization/51187
1733 * reorg.c (relax_delay_slots): Do not consider a jump useless if there
1734 is a barrier between the jump and its target label.
1736 2011-11-19 Patrick Marlier <patrick.marlier@gmail.com>
1739 * tracer.c (ignore_bb_p): Don't copy GIMPLE_TRANSACTION.
1741 2011-11-19 Eric Botcazou <ebotcazou@adacore.com>
1743 * expmed.c (store_bit_field_1): Revert bogus formatting change.
1745 2011-11-19 Richard Earnshaw <rearnsha@arm.com>
1748 * config/arm/arm.c (neon_disambiguate_copy): Correctly handle partial
1749 overlap of src and dest operands.
1751 2011-11-19 Iain Sandoe <iains@gcc.gnu.org>
1753 * config/darwin.h (ASM_DEBUG_SPEC): New.
1754 * config/darwin9.h (ASM_DEBUG_SPEC): New.
1756 2011-11-18 Jan Hubicka <jh@suse.cz>
1758 * config/i386/i386.c (atom_cost): Disable SSE loop until alignment
1761 2011-11-18 Anatoly Sokolov <aesok@post.ru>
1763 * config/cris/cris.c (cris_function_value_regno_p): Make static.
1764 (TARGET_FUNCTION_VALUE_REGNO_P): Define.
1765 * config/cris/cris.h (FUNCTION_VALUE_REGNO_P): Remove.
1766 * config/cris/cris-protos.h (cris_function_value_regno_p): Remove.
1768 2011-11-18 H.J. Lu <hongjiu.lu@intel.com>
1771 * doc/extend.texi: Document __builtin_ia32_movnti64.
1773 * config/i386/emmintrin.h (_mm_stream_si64): New.
1775 * config/i386/i386-builtin-types.def: Add VOID_FTYPE_PLONGLONG_LONGLONG.
1777 * config/i386/i386.c (ix86_builtins): Add IX86_BUILTIN_MOVNTI64.
1778 (bdesc_special_args): Update __builtin_ia32_movnti. Add
1779 __builtin_ia32_movnti64.
1780 (ix86_expand_special_args_builtin): Handle
1781 VOID_FTYPE_PLONGLONG_LONGLONG.
1783 * config/i386/i386.md (UNSPEC_MOVNTI): New.
1785 * config/i386/sse.md (sse2_movntsi): Renamed to ...
1786 (sse2_movnti<mode>): This.
1788 2011-11-18 Georg-Johann Lay <avr@gjlay.de>
1791 * config/avr/avr.h (base_arch_s): Add field n_segments.
1792 (ADDR_SPACE_PGM1, ADDR_SPACE_PGM2, ADDR_SPACE_PGM3,
1793 ADDR_SPACE_PGM4, ADDR_SPACE_PGM5, ADDR_SPACE_PGMX): New address spaces.
1794 (AVR_HAVE_ELPM, AVR_HAVE_ELPMX): New defines.
1795 (INIT_EXPANDERS): New define.
1796 * config/avr/avr-protos.h (avr_mem_pgmx_p): New.
1797 (avr_init_expanders): New.
1798 (avr_emit_movmemhi, avr_out_movmem): New.
1799 (avr_xload_libgcc_p): New.
1800 * config/avr/avr-c.c (avr_register_target_pragmas): Register
1801 address spaces __pgm1, __pgm2, __pgm3, __pgm4 __pgm5, __pgmx.
1802 (avr_cpu_cpp_builtins): Add built-in defines __PGM1,
1803 __PGM2, __PGM3, __PGM4, __PGM5, __PGMX.
1804 * config/avr/avr-devices.c (avr_arch_types): Set field n_segments.
1806 * config/avr/avr.c (AVR_SECTION_PROGMEM): Change define to cover
1807 3 bits instead of just 1.
1808 (xstring_empty, xstring_e, rampz_rtx): New static GTYed variables.
1809 (progmem_section): Change from section to array of sections.
1810 (progmem_section_prefix): New static variable.
1811 (avr_file_start): Print set for __RAMPZ__
1812 (avr_option_override): Move initialization of RTXes from here...
1813 (avr_init_expanders): ...to this new function.
1814 (avr_pgm_segment): New static function.
1815 (avr_decl_pgm_p): Handle error_mark_node.
1816 (avr_mem_pgmx_p, avr_decl_pgmx_p): New static functions.
1817 (avr_out_xload, avr_find_unused_d_reg): New static functions.
1818 (expand_prologue, expand_epilogue): Use rampz_rtx.
1819 (print_operand): Hande CONST_STRING.
1820 (avr_xload_libgcc_p): New static function.
1821 (avr_out_lpm_no_lpmx, avr_out_lpm): Handle ELPM.
1822 (avr_progmem_p): Return 2 for 24-bit flash address space.
1823 (avr_out_sbxx_branch): Clean-up code from ASn macros.
1824 (out_movqi_r_mr, out_movqi_mr_r): Ditto. And recognize RAMPZ's
1825 address and print symbolically.
1826 (avr_asm_named_section, avr_section_type_flags,
1827 avr_encode_section_info, avr_asm_select_section,
1828 avr_addr_space_address_mode, avr_addr_space_pointer_mode,
1829 avr_addr_space_legitimate_address_p, avr_addr_space_convert,
1830 avr_addr_space_legitimize_address): Handle new address spaces.
1831 (avr_output_progmem_section_asm_op): New static function.
1832 (avr_asm_init_sections): Initialize progmem_section[].
1833 (adjust_insn_length): Handle ADJUST_LEN_XLOAD, ADJUST_LEN_MOVMEM.
1834 (avr_const_address_lo16): New static function.
1835 (avr_assemble_integer): Use it to handle 3-byte integers.
1836 (avr_emit_movmemhi, avr_out_movmem): New functions.
1838 * config/avr/predicates.md (nox_general_operand): Handle new
1840 * config/avr/avr.md (unspec): Add UNSPEC_MOVMEM.
1841 (adjust_len): Add xload, movmem.
1842 (SP_ADDR): New define_constants.
1843 (isa): Add "lpm", "lpmx", "elpm", "elpmx".
1844 (enabled): Handle them.
1845 (load<mode>_libgcc): New expander.
1846 (*load.<mode>.libgcc): Rename to load_<mode>_libgcc.
1847 (xload8_A, xload<mode>_A): New insn-and-splits.
1848 (xload_8, xload_<mode>_libgcc, xload_<mode>, loadmem_elpm): New insns.
1849 (mov<mode>): Handle new address spaces.
1850 (movmemhi): Rewrite using avr_emit_movmemhi.
1851 (MOVMEM_r_d): New mode attribute.
1852 (movmem_<mode>, movmem_qi_elpm): New insns.
1853 (setmemhi, *clrmemqi, *clrmemhi, strlenhi, *strlenhi): Unquote
1854 C-code. Use label instead of hard-coded instrunction lengths.
1856 2011-11-18 Martin Jambor <mjambor@suse.cz>
1858 PR tree-optimization/50605
1859 * gimple.c (is_gimple_ip_invariant_address): Also handle MEM_REFs
1860 of IPA invariant decls.
1862 2011-11-18 Bill Schmidt <wschmidt@linux.vnet.ibm.com>
1864 * tree-outof-ssa.c (insert_back_edge_copies): Add call to
1865 mark_dfs_back_edges.
1867 2011-11-18 Iain Sandoe <iains@gcc.gnu.org>
1870 * configure.ac: Remove ranlib special-casing for Darwin.
1871 * configure: Regenerate.
1873 2011-11-18 Uros Bizjak <ubizjak@gmail.com>
1875 PR tree-optimization/51118
1876 * fold-const.c (fold_checksum_tree): Check for TS_TYPED structure
1877 before using TREE_TYPE accessor on expr.
1879 2011-11-17 Jan Hubicka <jh@suse.cz>
1882 * i386.c (atom_cost): Fix 32bit memset description.
1883 (expand_set_or_movmem_via_loop_with_iter): Output proper bounds check
1885 (expand_movmem_epilogue): Handle epilogues up to size 15 w/o producing
1887 (decide_alg): sse_loop is not useable wthen SSE2 is disabled;
1888 when not optimizing always use rep movsb or lincall; do not produce
1889 word sized loops when optimizing memset for size (to avoid need
1890 for large constants).
1891 (ix86_expand_movmem): Get into sync with ix86_expand_setmem;
1892 choose unroll factors better; always do 128bit moves when producing
1893 SSE loops; do not produce loopy epilogue when size is too small.
1894 (promote_duplicated_reg_to_size): Do not look into desired alignments
1895 when doing vector expansion.
1896 (ix86_expand_setmem): Track better when promoted value is available;
1897 choose unroll factors more sanely. Output loopy epilogue only
1900 2011-11-17 Steve Ellcey <sje@cup.hp.com>
1903 * output.h (fprint_w): Remove.
1904 * final.c (fprint_w): Remove.
1905 (output_addr_const): Change fprint_w back to fprintf.
1907 2011-11-17 Andrew Pinski <apinski@cavium.com>
1909 * config/host-linux.c (TRY_EMPTY_VM_SPACE): Define for MIPS.
1911 2011-11-17 Andrew MacLeod <amacleod@redhat.com>
1913 * builtins.c (expand_builtin): Remove 4th parameter representing
1914 weak/strong mode when __atomic_compare_exchange becomes a library call.
1916 2011-11-17 Richard Henderson <rth@redhat.com>
1918 * config/rs6000/rs6000.c (rs6000_expand_atomic_compare_and_swap): Get
1919 new pseudo for target after convert_modes.
1920 (rs6000_expand_atomic_exchange, rs6000_expand_atomic_op): Likewise.
1922 2011-11-17 Richard Henderson <rth@redhat.com>
1924 * config/rs6000/rs6000.c (rs6000_expand_atomic_compare_and_swap): Get
1925 new pseudo for target after convert_modes.
1926 (rs6000_expand_atomic_exchange, rs6000_expand_atomic_op): Likewise.
1928 2011-11-17 Richard Henderson <rth@redhat.com>
1930 * builtins.c (expand_builtin_mem_thread_fence): Remove.
1931 (expand_builtin_mem_signal_fence): Remove.
1932 (expand_builtin_atomic_thread_fence): Use expand_mem_thread_fence.
1933 (expand_builtin_sync_synchronize): Likewise.
1934 (expand_builtin_atomic_signal_fence): Use expand_mem_signal_fence.
1935 * optabs.c (expand_asm_memory_barrier): Split out from
1936 expand_builtin_mem_signal_fence.
1937 (expand_mem_thread_fence): New, a combination of code from
1938 expand_builtin_mem_thread_fence and expand_builtin_sync_synchronize.
1939 (expand_mem_signal_fence): Moved and renamed from
1940 expand_builtin_mem_signal_fence.
1941 (expand_atomic_exchange): Use expand_mem_thread_fence.
1942 (expand_atomic_load, expand_atomic_store): Likewise.
1943 * expr.h, optabs.h: Update decls.
1945 2011-11-17 Bin Cheng <bin.cheng@arm.com>
1947 PR rtl-optimization/50663
1948 * cprop.c (implicit_set_indexes): New global variable.
1949 (insert_set_in_table): Add additional parameter and record implicit
1951 (hash_scan_set): Add additional parameter and pass it to above.
1952 (hash_scan_insn): Pass false to hash_scan_set.
1953 (compute_hash_table_work): Pass true to hash_scan_set.
1954 (compute_cprop_data): Add implicit set to AVIN of block which the
1955 implicit set is recorded for.
1956 (one_cprop_pass): Handle implicit_set_indexes array.
1958 2011-11-17 Michael Matz <matz@suse.de>
1962 * tree-ssa-live.c (mark_all_vars_used_1): Recurse only for decls of
1964 (remove_unused_locals): Ditto.
1966 2011-11-16 Richard Henderson <rth@redhat.com>
1968 * config/alpha/alpha.c (alpha_split_compare_and_swap_12): Copy
1969 ALIAS_SET_MEMORY_BARRIER when creating a new memory.
1970 (alpha_split_atomic_exchange_12): Likewise.
1971 * config/rs6000/rs6000.c (rs6000_adjust_atomic_subword): Likewise.
1973 2011-11-16 Joseph Myers <joseph@codesourcery.com>
1975 * config/i386/i386elf.h (PREFERRED_DEBUGGING_TYPE): Remove.
1977 2011-11-16 David Edelsohn <dje.gcc@gmail.com>
1979 * config/rs6000/rs6000.c (rs6000_xcoff_section_type_flags):
1980 Default to minimum alignment if decl is NULL.
1982 2011-11-16 Uros Bizjak <ubizjak@gmail.com>
1984 * config/i386/sse.md (round<mode>2_vec_pack_sfix): Optimize V2DFmode
1986 (<sse4_1>_round<ssemodesuffix>_vec_pack_sfix<avxsizesuffix>): Ditto.
1988 2011-11-16 Venkataramanan Kumar <venkataramanan.kumar@amd.com>
1990 * doc/invoke.texi: Document AMD bdver1 and btver1.
1992 2011-11-16 Richard Earnshaw <rearnsha@arm.com>
1993 Bernd Schmidt <bernds@coudesourcery.com>
1994 Sebastian Huber <sebastian.huber@embedded-brains.de>
1997 * config/arm/arm.c (store_multiple_sequence): Avoid cases where
1998 the base reg is stored iff compiling for Thumb1.
2000 2011-11-16 Razya Ladelsky <razya@il.ibm.com>
2002 PR tree-optimization/49960
2003 * tree-data-ref.c (initialize_data_dependence_relation): Add
2005 Remove call to compute_self_dependence.
2006 (compute_affine_dependence): Remove the !DDR_SELF_REFERENCE condition.
2007 (compute_self_dependence): Remove old code. Add call to
2008 compute_affine_dependence.
2009 (compute_all_dependences): Remove call to compute_self_dependence.
2010 Add call to compute_affine_dependence.
2012 2011-11-16 Andreas Krebbel <Andreas.Krebbel@de.ibm.com>
2015 * expmed.c (store_bit_field_1): Use extract_bit_field on big
2016 endian targets if the source cannot be exactly covered by word
2019 2011-11-15 Joseph Myers <joseph@codesourcery.com>
2021 * config/i386/i386elf.h (ASM_OUTPUT_ASCII): Change STRING_LIMIT to
2024 2011-11-15 Richard Henderson <rth@redhat.com>
2026 * config/alpha/alpha.c (alpha_pre_atomic_barrier): New.
2027 (alpha_post_atomic_barrier): New.
2028 (alpha_split_atomic_op): New memmodel argument; honor it.
2029 (alpha_split_compare_and_swap): Take array of operands. Honor
2030 memmodel; always set bool output
2031 (alpha_expand_compare_and_swap_12): Similarly.
2032 (alpha_split_compare_and_swap_12): Similarly.
2033 (alpha_split_atomic_exchange): Similarly. Rename from
2034 alpha_split_lock_test_and_set.
2035 (alpha_expand_atomic_exchange_12): Similarly. Rename from
2036 alpha_expand_lock_test_and_set_12.
2037 (alpha_split_atomic_exchange_12): Similarly. Rename from
2038 alpha_split_lock_test_and_set_12.
2039 * config/alpha/alpha-protos.h: Update.
2040 * config/alpha/alpha.md (UNSPECV_CMPXCHG): New.
2041 * config/alpha/constraints.md ("w"): New.
2042 * config/alpha/predicates.md (mem_noofs_operand): New.
2043 * config/alpha/sync.md (atomic_compare_and_swap<mode>): Rename from
2044 sync_compare_and_swap<mode>; add the new parameters.
2045 (atomic_exchange<mode>): Update from sync_test_and_set<mode>.
2046 (atomic_fetch_<op><mode>): Update from sync_old_<op><mode>.
2047 (atomic_<op>_fetch<mode>): Update from sync_new_<op><mode>.
2048 (atomic_<op><mode>): Update from sync_<op><mode>.
2050 2011-11-16 Tom de Vries <tom@codesourcery.com>
2052 * tree-ssa-tail-merge.c (replace_block_by): Add frequency of bb2 to bb1.
2054 2011-11-16 Alan Modra <amodra@gmail.com>
2056 PR rtl-optimization/51051
2058 * function.c (thread_prologue_and_epilogue_insns): Guard
2059 emitting return with single_succ_p test.
2061 2011-11-15 Joern Rennecke <joern.rennecke@embecosm.com>
2063 * config/epiphany/epiphany.md (mov<mode>cc): Fix code to
2064 get mode from CMP_OP1 if CMP_OP0 is VOIDmode.
2066 2011-11-15 Uros Bizjak <ubizjak@gmail.com>
2068 * config/i386/sse.md (vec_pack_trunc_v2df): Optimize sequence for AVX.
2069 (vec_pack_sfix_trunc_v2df): Ditto.
2070 (vec_pack_sfix_v2df): Ditto.
2071 (vec_pack_sfix_trunc_v4df): Generate fix_truncv4dfv4si2 and
2072 avx_vec_concatv8si patterns.
2073 (vec_pack_sfix_v4df): Generate avx_cvtpd2dq256 and
2074 avx_vec_concatv8si patterns.
2076 2011-11-15 Torvald Riegel <triegel@redhat.com>
2078 * c-parser.c (c_parser_transaction_expression): Require parentheses
2079 when parsing transaction expressions.
2081 2011-11-15 Tristan Gingold <gingold@adacore.com>
2083 * incpath.c (get_added_cpp_dirs): New function.
2084 * incpath.h (get_added_cpp_dirs): Declare.
2085 * config/vms/vms-c.c (vms_c_register_includes): New function.
2086 (vms_std_modules): New variable.
2087 * config/vms/vms.h (TARGET_EXTRA_INCLUDES): Define.
2088 (vms_c_register_includes): Declare.
2090 2011-11-15 Tristan Gingold <gingold@adacore.com>
2092 * c-family/c-pragma.h (pragma_extern_prefix): Declare.
2093 * c-family/c-pragma.c (pragma_extern_prefix): Make it public.
2094 * config/vms/vms-c.c (saved_extern_prefix): New variable.
2095 (vms_pragma_extern_prefix): New function.
2096 (vms_c_register_pragma): Register vms_pragma_extern_prefix.
2098 2011-11-15 Georg-Johann Lay <avr@gjlay.de>
2101 * config/avr/avr.h (ADDR_SPACE_PGM): New address spaces.
2102 (REGISTER_TARGET_PRAGMAS): New define.
2103 * config/avr/avr-protos.h (avr_mem_pgm_p): New.
2104 (avr_load_libgcc_p): New.
2105 (avr_register_target_pragmas): New.
2106 (asm_output_external_libcall): Remove.
2107 (avr_log_t): Add field "progmem". Order alphabetically.
2108 * config/avr/avr-log.c (avr_log_set_avr_log): Set avr_log.progmem.
2109 * config/avr/avr-c.c (langhooks.h): New include.
2110 (avr_register_target_pragmas): New function. Register address
2112 (avr_cpu_cpp_builtins): Add built-in define __PGM.
2114 * config/avr/avr.c: Include "c-family/c-common.h".
2115 (TARGET_LEGITIMATE_ADDRESS_P): Remove define.
2116 (TARGET_LEGITIMIZE_ADDRESS): Remove define.
2117 (TARGET_ADDR_SPACE_SUBSET_P): Define to...
2118 (avr_addr_space_subset_p): ...this new static function.
2119 (TARGET_ADDR_SPACE_CONVERT): Define to...
2120 (avr_addr_space_convert): ...this new static function.
2121 (TARGET_ADDR_SPACE_ADDRESS_MODE): Define to...
2122 (avr_addr_space_address_mode): ...this new static function.
2123 (TARGET_ADDR_SPACE_POINTER_MODE): Define to...
2124 (avr_addr_space_pointer_mode): ...this new static function.
2125 (TARGET_ADDR_SPACE_LEGITIMATE_ADDRESS_P): Define to...
2126 (avr_addr_space_legitimate_address_p): ...this new static function.
2127 (TARGET_ADDR_SPACE_LEGITIMIZE_ADDRESS): Define to...
2128 (avr_addr_space_legitimize_address): ...this new static function.
2129 (avr_mode_code_base_reg_class): Handle address spaces.
2130 (avr_regno_mode_code_ok_for_base_p): Ditto.
2131 (lpm_addr_reg_rtx, lpm_reg_rtx, all_regs_rtx): New static variables.
2132 (avr_option_override): Initialize them.
2133 (output_reload_in_const): Use all_regs_rtx. Fix signedness of loop
2135 (avr_pgm_segment): New static function.
2136 (avr_decl_pgm_p, avr_mem_pgm_p): New static functions.
2137 (avr_out_lpm, avr_out_lpm_no_lpmx): New static functions.
2138 (output_movqi, output_movhi, output_movsisf, avr_out_movpsi): Call
2139 avr_out_lpm to handle loads from progmem.
2140 (avr_load_libgcc_p): New static function.
2141 (avr_progmem_p): Test if decl is in flash.
2142 (avr_pgm_pointer_const_p): New static function.
2143 (avr_nonconst_pointer_addrspace): New static function.
2144 (avr_pgm_check_var_decl): New static function.
2145 (avr_insert_attributes): Use it. Change error message to report
2146 cause (progmem or address space) when code wants to write to flash.
2147 (avr_section_type_flags): Unset section flag SECTION_BSS for
2150 * config/avr/predicates.md (nop_general_operand): New predicate.
2151 (nox_general_operand): New predicate.
2152 * config/avr/avr.md (LPM_REGNO): New define_constant.
2153 (load<mode>_libgcc): New expander.
2154 (*load.<mode>.libgcc): New insn.
2155 (mov<mode>): Handle loads from non-generic AS.
2156 (movmemhi): Ditto. Propagate address space information to newly
2158 (movqi_insn, *movhi, *movpsi, *movsi, *movsf): Change predicate #1
2159 to nox_general_operand.
2160 (ashrqi3, ashrhi3, ashrsi3): Change predicate #1 to
2161 nop_general_operand.
2162 (ashlqi3, *ashlqi3, ashlhi3, ashlsi3): Ditto.
2163 (lshrqi3, *lshrqi3, lshrhi3, lshrsi3): Ditto.
2164 (split-lpmx): New split.
2165 (*ashlhi3_const, *ashlsi3_const, *ashrhi3_const, *ashrsi3_const,
2166 *lshrhi3_const, *lshrsi3_const): Indent, unquote C.
2168 2011-11-15 Maxim Kuvyrkov <maxim@codesourcery.com>
2170 * ipa-cp.c (ipa_value_from_jfunc): Make global.
2171 (ipa_cst_from_jfunc): Remove, use ipa_value_from_jfunc instead.
2172 (get_indirect_edge_target): Rename, make global.
2173 (devirtualization_time_bonus, estimate_local_effects,)
2174 (ipcp_discover_new_direct_edges): Update.
2175 * ipa-inline-analysis.c (evaluate_conditions_for_edge):
2176 Generalize to also handle types. Rename to ...
2177 (evaluate_properties_for_edge): Use instead of
2178 evaluate_conditions_for_edge.
2179 (estimate_edge_devirt_benefit): New function.
2180 (estimate_calls_size_and_time): Use it.
2181 (estimate_node_size_and_time, estimate_ipcp_clone_size_and_time,)
2182 (inline_merge_summary): Update.
2183 (do_estimate_edge_time, do_estimate_edge_growth): Update. Calculate
2184 parameter information at the call site and pass it on to subroutines.
2185 * tree-inline.c (estimate_num_insns): Distinguish between direct and
2187 (init_inline_once): Set size and time costs or indirect calls.
2188 * tree-inline.h (eni_weights): Add indirect_call_cost.
2190 2011-11-15 Tom de Vries <tom@codesourcery.com>
2192 PR tree-optimization/51005
2193 * tree-ssa-tail-merge.c (delete_basic_block_same_succ): Rename to
2194 mark_basic_block_deleted.
2195 (update_worklist): Inline purge_bbs.
2196 (purge_bbs, unlink_virtual_phi, update_vuses, vop_at_entry)
2197 (delete_block_update_dominator_info): Remove.
2198 (replace_block_by): Remove update_vops parameter. Partially evaluate
2199 for update_vops == false.
2200 (apply_clusters): Remove update_vops parameter. Remove update_vops
2201 argument in replace_block_by call.
2202 (update_debug_stmts): Remove MAY_HAVE_DEBUG_STMTS test.
2203 (tail_merge_optimize): Remove update_vops argument to apply_clusters.
2204 Remove call to purge_bbs. Add calls to calculate_dominance_info and
2205 free_dominance_info. Add MAY_HAVE_DEBUG_STMTS before calling
2206 update_debug_stmts. Mark vop var for renaming, if necessary.
2208 2011-11-15 Bernd Schmidt <bernds@codesourcery.com>
2210 PR rtl-optimization/51051
2211 * cfgrtl.c (cfg_layout_can_merge_blocks_p): Return FALSE if the
2212 move would cause fallthrough into the exit block.
2214 2011-11-14 Richard Henderson <rth@redhat.com>
2216 * config/rs6000/rs6000.c (emit_load_locked): Assert the mode is
2218 (emit_store_conditional): Likewise.
2219 (rs6000_pre_atomic_barrier, rs6000_post_atomic_barrier): New.
2220 (rs6000_adjust_atomic_subword): New.
2221 (rs6000_mask_atomic_subword, rs6000_finish_atomic_subword): New.
2222 (rs6000_expand_atomic_op): Rename from rs6000_emit_sync; rewrite
2223 for pre-reload expansion.
2224 (rs6000_split_compare_and_swap, rs6000_split_compare_and_swapqhi,
2225 rs6000_expand_compare_and_swapqhi): Merge into ...
2226 (rs6000_expand_atomic_compare_and_swap): ... here. New function.
2227 rs6000_split_lock_test_and_set; expand immediately. Handle
2229 * config/rs6000/rs6000.md (UNSPEC_LWSYNC): Move and rename
2230 from UNSPECV_LWSYNC.
2231 * config/rs6000/sync.md (fetchopsi_constr, fetchopdi_constr): Remove.
2232 (mem_thread_fence): New.
2233 (hwsync): Rename from memory_barrier.
2234 (*hwsync): Rename from *sync_internal.
2235 (lwsync, *lwsync): Mirror hwsync implementation.
2236 (isync): Don't reference memory.
2238 (atomic_load<INT>, atomic_store<INT>): New.
2239 (ATOMIC): New mode iterator.
2240 (load_locked<ATOMIC>): Rename from load_locked_<GPR>.
2241 (store_conditional<ATOMIC>): Rename from store_conditional_<GPR>.
2242 (sync_compare_and_swap<GPR>): Remove.
2243 (sync_compare_and_swaphi, sync_compare_and_swapqi): Remove.
2244 (sync_compare_and_swapqhi_internal): Remove.
2245 (sync_lock_test_and_set<GPR>): Remove.
2246 (sync_<FETCHOP><INT1>): Remove.
2247 (*sync_<FETCHOP>si_internal, *sync_<FETCHOP>di_internal): Remove.
2248 (sync_nand<INT1>, *sync_nand<GPR>_internal): Remove.
2249 (sync_old_<FETCHOP><GPR>): Remove.
2250 (*sync_old_<FETCHOP>si_internal): Remove.
2251 (*sync_old_<FETCHOP>di_internal): Remove.
2252 (sync_old_nand<INT1>): Remove.
2253 (*sync_old_nand<GPR>_internal): Remove.
2254 (sync_new_<FETCHOP><GPR>): Remove.
2255 (*sync_new_<FETCHOP>si_internal): Remove.
2256 (*sync_new_<FETCHOP>di_internal): Remove.
2257 (sync_new_nand<INT1>): Remove.
2258 (*sync_new_nand<GPR>_internal): Remove.
2259 (*atomic_andsi, *atomic_anddi): Remove.
2260 (*sync_addshort_internal, *sync_subshort_internal): Remove.
2261 (*sync_andsi_internal, *sync_boolsi_internal): Remove.
2262 (*sync_boolcshort_internal): Remove.
2263 (sync_lock_release<INT1>): Remove.
2264 (atomic_compare_and_swap<INT1>): New.
2265 (atomic_exchange<INT1>): New.
2266 (atomic_<FETCHOP><INT1>, atomic_nand<INT1>): New.
2267 (atomic_fetch_<FETCHOP><INT1>, atomic_fetch_nand<INT1>): New.
2268 (atomic_<FETCHOP>_fetch<INT1>, atomic_nand_fetch<INT1>): New.
2270 2011-11-14 Uros Bizjak <ubizjak@gmail.com>
2272 * config/i386/sse.md (round<mode>2): Use register_operand for
2273 operand 1 predicate.
2274 (round<mode>2_sfix): Ditto.
2275 (round<mode>2_vec_pack_sfix): Ditto for operand 1 and operand 2.
2277 2011-11-14 Nathan Sidwell <nathan@acm.org>
2279 * gcov.c (canonicalize_name): Protect use of S_ISLNK.
2281 2011-11-14 Jan Hubicka <jh@suse.cz>
2284 * config/i386/i386.c (core cost model): Correct pasto.
2286 2011-11-14 Uros Bizjak <ubizjak@gmail.com>
2288 * config/i386/sse.md (round<mode>2_sfix): New expander.
2289 (round<mode>2_vec_pack_sfix): Ditto.
2290 (<sse4_1>_round<ssemodesuffix>_sfix<avxsizesuffix>): Ditto.
2291 (<sse4_1>_round<ssemodesuffix>_vec_pack_sfix<avxsizesuffix>): Ditto.
2292 * config/i386/builtin-types.def (V4SI_FTYPE_V4SF_ROUND,
2293 V8SI_FTYPE_V8SF_ROUND, V4SI_FTYPE_V2DF_V2DF_ROUND,
2294 V8SI_FTYPE_V4DF_V4DF_ROUND): New builtin types.
2295 * config/i386/i386.c (ix86_builtins): Add
2296 IX86_BUILTIN_{FLOORPD,CEILPD,ROUNDPD_AZ}_VEC_PACK_SFIX{,256} and
2297 IX86_BUILTIN_{FLOORPS,CEILPS,ROUNDPS_AZ}_SFIX{,256} defines.
2298 (bdesc_args): Add __builtin_ia32_{floorpd,ceilpd}_vec_pack_sfix{,256},
2299 __builtin_ia32_roundpd_az_vec_pack_sfix{,256},
2300 __builtin_ia32_{floorps,ceilps}_sfix{,256}and
2301 __builtin_ia32_roundps_az_sfix{,256} descriptions.
2302 (ix86_expand_sse_round_vec_pack_sfix): New.
2303 (ix86_expand_args_builtin): Handle V4SI_FTYPE_V4SF_ROUND,
2304 V8SI_FTYPE_V8SF_ROUND, V4SI_FTYPE_V2DF_V2DF_ROUND and
2305 V8SI_FTYPE_V4DF_V4DF_ROUND types. Check last argument of
2306 CODE_FOR_sse4_1_roundpd_vec_pack_sfix, CODE_FOR_sse4_1_roundps_sfix,
2307 CODE_FOR_avx_roundpd_vec_pack_sfix256 and CODE_FOR_avx_roundps_sfix256.
2308 (ix86_builtin_vectorized_function): Handle
2309 BUILT_IN_{I,L,LL}FLOOR{,F}, BUILT_IN_{I,L,LL}CEIL{,F} and
2310 BUILT_IN_{I,L,LL}ROUND{,F}
2312 2011-11-14 Jan Hubicka <jh@suse.cz>
2315 * cgraph.h (varpool_externally_visible_p): Declare.
2316 (varpool_add_new_variable): Declare.
2317 * tree-emultls.c (get_emutls_init_templ_addr,
2318 new_emutls_decl): Use varpool_add_new_variable.
2319 * ipa.c (varpool_externally_visible_p): Export.
2320 * varpool.c (varpool_add_new_variable): New function.
2322 2011-11-14 Michael Zolotukhin <michael.v.zolotukhin@gmail.com>
2323 Jan Hubicka <jh@suse.cz>
2325 * config/i386/i386.h (processor_costs): Add second dimension to
2326 stringop_algs array.
2327 * config/i386/i386.c (cost models): Initialize second dimension of
2328 stringop_algs arrays.
2329 (core_cost): New costs based on generic64 costs with updated stringop
2331 (promote_duplicated_reg): Add support for vector modes, add
2333 (promote_duplicated_reg_to_size): Likewise.
2334 (processor_target): Set core costs for core variants.
2335 (expand_set_or_movmem_via_loop_with_iter): New function.
2336 (expand_set_or_movmem_via_loop): Enable reuse of the same iters in
2337 different loops, produced by this function.
2338 (emit_strset): New function.
2339 (expand_movmem_epilogue): Add epilogue generation for bigger sizes,
2340 use SSE-moves where possible.
2341 (expand_setmem_epilogue): Likewise.
2342 (expand_movmem_prologue): Likewise for prologue.
2343 (expand_setmem_prologue): Likewise.
2344 (expand_constant_movmem_prologue): Likewise.
2345 (expand_constant_setmem_prologue): Likewise.
2346 (decide_alg): Add new argument align_unknown. Fix algorithm of
2347 strategy selection if TARGET_INLINE_ALL_STRINGOPS is set; Skip sse_loop
2348 (decide_alignment): Update desired alignment according to chosen move
2350 (ix86_expand_movmem): Change unrolled_loop strategy to use SSE-moves.
2351 (ix86_expand_setmem): Likewise.
2352 (ix86_slow_unaligned_access): Implementation of new hook
2353 slow_unaligned_access.
2354 * config/i386/i386.md (strset): Enable half-SSE moves.
2355 * config/i386/sse.md (vec_dupv4si): Add expand for vec_dupv4si.
2356 (vec_dupv2di): Add expand for vec_dupv2di.
2358 2011-11-14 Dimitrios Apostolou <jimis@gmx.net>
2362 * config/elfos.h (TARGET_ASM_INTERNAL_LABEL): Remove.
2363 * varasm.c (default_elf_internal_label): Remove.
2365 2011-11-14 Kai Tietz <ktietz@redhat.com>
2367 * gcov.c (generate_results): Add missing semicolon and correct indent.
2369 2011-11-14 Ira Rosen <ira.rosen@linaro.org>
2372 * tree-vect-stmts.c (vectorizable_condition): Initialize comp_vectype.
2374 2011-11-14 Mingjie Xing <mingjie.xing@gmail.com>
2376 * doc/invoke.texi (Wunused-result): Change @pxref{Variable Attributes}
2377 to @pxref{Function Attributes}.
2379 2011-11-13 Oleg Endo <oleg.endo@t-online.de>
2382 * config/sh/sh.h (IS_LITTLE_ENDIAN_OPTION, UNSUPPORTED_SH2A):
2384 (DRIVER_SELF_SPECS): Use new macros to filter out unsupported options
2385 taking the default configuration into account.
2387 2011-11-13 Jonathan Wakely <jwakely.gcc@gmail.com>
2389 * doc/install.texi (Specific): Fix anchor for
2390 x86_64-*-solaris2.1[0-9]*.
2392 2011-11-13 Nathan Sidwell <nathan@acm.org>
2394 * gcov.c (source_prefix, source_length): New globals.
2395 (flag_relative_only): Likewise.
2396 (print_usage, options, process_args): Update.
2397 (generate_results): Use coverage.name, check
2398 flag_relative_only. Adjust messages.
2399 (find_source): Check source_prefix.
2400 (output_lines): Use coverage.name, adjust messages.
2401 * doc/gcov.texi (Invoking Gcov): Document new options.
2403 2011-11-12 Jason Merrill <jason@redhat.com>
2406 * gimplify.c (gimplify_target_expr): Add a clobber to the cleanup.
2407 (gimplify_modify_expr): Don't try to simplify it.
2409 2011-11-12 Dimitrios Apostolou <jimis@gmx.net>
2412 * config/elfos.h (STRING_ASM_OP): Define.
2413 * varasm.c (default_elf_asm_output_limited_string): Use it.
2416 * gcc/configure.ac: Check for stpcpy declaration.
2417 * system.h: Declare it if not.
2418 * config.in, configure: Regenerate.
2420 2011-11-12 Richard Henderson <rth@redhat.com>
2422 * config/rs6000/rs6000.md (fix_trunc<SFDF>si2_stfiwx): Use
2423 nonimmediate_operand for the destination.
2424 (fixuns_trunc<SFDF>si2_stfiwx): Likewise.
2426 * builtins.c (expand_builtin_compare_and_swap): If target is const0,
2427 don't pass the target to expand_atomic_compare_and_swap.
2428 (expand_builtin_atomic_compare_exchange): Likewise.
2430 * config/sh/linux.h (TARGET_INIT_LIBFUNCS): New.
2431 * config/sh/sh.c (sh_init_sync_libfuncs): New.
2433 * config/pa/pa-linux.h (TARGET_SYNC_LIBCALL): New.
2434 * config/pa/pa.h (TARGET_SYNC_LIBCALL): New default.
2435 * config/pa/pa.c (pa_init_libfuncs): Use init_sync_libfuncs.
2437 2011-11-12 Iain Sandoe <iains@gcc.gnu.org>
2440 * config/rs6000/rs6000.c (rs6000_legitimize_reload_address):
2441 Only expand a symbol ref. into an access when the entity is defined
2444 2011-11-12 Jan Hubicka <jh@suse.cz>
2447 * cgraphunit.c (output_weakrefs): Output really only weakrefs.
2449 2011-11-12 Nathan Sidwell <nathan@acm.org>
2451 * gcov.c (struct name_map): New.
2452 (names, n_names, a_names): New global vars.
2453 (print_usage): Adjust usage.
2454 (generate_results): Canonicalize main file name.
2455 (release_structures): Adjust.
2456 (name_search, name_sort): New callbacks.
2457 (find_source): Look for and create a canonical name.
2458 (canonicalize_name): New.
2459 (make_gcov_file_name): Reimplement and fix mangling.
2461 * doc/gcov.texi: Update documentation about path preservation.
2463 2011-11-11 David S. Miller <davem@davemloft.net>
2465 * config/sparc/linux.h (ASM_GENERATE_INTERNAL_LABEL): Delete.
2466 * config/sparc/linux64.h (ASM_GENERATE_INTERNAL_LABEL): Delete.
2468 2011-11-11 Jakub Jelinek <jakub@redhat.com>
2470 * config/i386/i386-protos.h (ix86_maybe_emit_epilogue_vzeroupper):
2472 * config/i386/i386.c (ix86_maybe_emit_epilogue_vzeroupper): New
2474 (ix86_expand_epilogue): Use it.
2475 * config/i386/i386.md (return, simple_return): Call it in the
2478 PR tree-optimization/51091
2479 * tree-stdarg.c (execute_optimize_stdarg): Ignore TREE_CLOBBER_P
2480 rhs also in the va_list_simple_ptr case.
2482 PR tree-optimization/51058
2483 * tree-vect-slp.c (vect_remove_slp_scalar_calls): New function.
2484 (vect_schedule_slp): Call it.
2485 * tree-vect-stmts.c (vectorizable_call): If slp_node != NULL,
2486 don't replace scalar calls with setting of their lhs to zero here.
2488 PR tree-optimization/51074
2489 * fold-const.c (vec_cst_ctor_to_array, fold_vec_perm): New functions.
2490 (fold_binary_loc): Handle VEC_EXTRACT_EVEN_EXPR,
2491 VEC_EXTRACT_ODD_EXPR, VEC_INTERLEAVE_HIGH_EXPR and
2492 VEC_INTERLEAVE_LOW_EXPR with VECTOR_CST or CONSTRUCTOR operands.
2493 (fold_ternary_loc): Handle VEC_PERM_EXPR with VECTOR_CST or
2494 CONSTRUCTOR operands.
2495 * tree-ssa-propagate.c (valid_gimple_rhs_p): Handle ternary
2497 * tree-vect-generic.c (lower_vec_perm): Mask sel_int elements
2498 to 0 .. 2 * elements - 1.
2500 2011-11-11 Richard Henderson <rth@redhat.com>
2502 * gimple-pretty-print.c (dump_gimple_omp_atomic_load): Dump needed.
2503 (dump_gimple_omp_atomic_store): Likewise.
2504 * optabs.c (can_atomic_exchange_p): New.
2505 * optabs.h (can_atomic_exchange_p): Declare.
2506 * omp-low.c (expand_omp_atomic_load): Implement.
2507 (expand_omp_atomic_store): Likewise.
2508 (expand_omp_atomic): Update for new arguments to load/store.
2510 2011-11-11 Eric Botcazou <ebotcazou@adacore.com>
2512 * cprop.c: Adjust outdated comments throughout.
2513 (hash_scan_set): Rename PAT parameter into SET.
2514 (cprop_pavloc): Rename into...
2515 (cprop_avloc): ...this.
2516 (cprop_absaltered): Rename into...
2517 (cprop_kill): ...this.
2518 (alloc_cprop_mem): Adjust for above renaming.
2519 (free_cprop_mem): Likewise.
2520 (compute_cprop_data): Likewise.
2521 (compute_local_properties): Rename TRANSP parameter into KILL and
2522 adjust throughout. Rework comments.
2523 (try_replace_reg): Fix long line.
2524 (cprop_jump): Likewise.
2525 (constprop_register): Fix prototype and take INSN last.
2526 (cprop_insn): Adjust calls to above function. Fix long lines.
2527 (bypass_block): Likewise.
2528 (one_cprop_pass): Likewise.
2530 2011-11-11 Uros Bizjak <ubizjak@gmail.com>
2532 * config/alpha/elf.h (ELF_ASCII_ESCAPES): Rename from ESCAPES.
2533 (ELF_STRING_LIMIT): Rename from STRING_LIMIT.
2535 2011-11-11 Jason Merrill <jason@redhat.com>
2537 * varasm.c (default_elf_asm_output_limited_string): #ifdef
2539 (default_elf_asm_output_ascii): Likewise.
2541 2011-11-11 Uros Bizjak <ubizjak@gmail.com>
2544 * config/i386/constraints.md (j): New address constraint.
2545 * config/i386/predicates.md (lea_address_operand): Redefine as
2547 * config/i386/i386.md (*lea_3_zext): Use "j" constraint for operand 1.
2548 (*lea_4_zext): Ditto.
2550 2011-11-11 David S. Miller <davem@davemloft.net>
2553 2011-11-05 David S. Miller <davem@davemloft.net>
2555 * config/sparc/sparc.md (UNSPEC_SHORT_LOAD): New unspec.
2556 (zero-extend_v8qi_vis, zero_extend_v4hi_vis): New expanders.
2557 (*zero_extend_v8qi_<P:mode>_insn,
2558 *zero_extend_v4hi_<P:mode>_insn): New insns.
2559 * config/sparc/sparc.c (vector_init_move_words,
2560 vector_init_prepare_elts, sparc_expand_vector_init_vis2,
2561 sparc_expand_vector_init_vis1): New functions.
2562 (vector_init_bshuffle): Rewrite to handle more cases and make use
2563 of locs[] array prepared by vector_init_prepare_elts.
2564 (vector_init_fpmerge, vector_init_faligndata): Delete.
2565 (sparc_expand_vector_init): Rewrite using new infrastructure.
2567 2011-11-11 Jakub Jelinek <jakub@redhat.com>
2569 * opts-common.c (generate_canonical_option): Free opt_text
2570 it it has been allocated here and not stored anywhere.
2572 * tree-vect-slp.c (vect_free_slp_tree): Also free SLP_TREE_CHILDREN
2574 (vect_create_new_slp_node): Don't allocate node before checking stmt
2576 (vect_free_oprnd_info): Remove FREE_DEF_STMTS argument, always
2577 free def_stmts vectors and additionally free oprnd_info.
2578 (vect_build_slp_tree): Adjust callers. Call it even if
2579 stop_recursion. If vect_create_new_slp_node or
2580 vect_build_slp_tree fails, properly handle freeing memory.
2581 If it succeeded, clear def_stmts in oprnd_info.
2583 2011-11-11 Dimitrios Apostolou <jimis@gmx.net>
2585 * defaults.h (ASM_OUTPUT_LABEL, ASM_OUTPUT_INTERNAL_LABEL): Expand on
2586 multiple lines for readability.
2587 * output.h (fprint_whex, fprint_w, fprint_ul, sprint_ul): Declare.
2588 (ASM_OUTPUT_LABELREF): Call fputs instead of asm_fprintf.
2589 * dwarf2asm.c (dw2_assemble_integer, dw2_asm_output_data,
2590 dw2_asm_data_uleb128, dw2_asm_delta_uleb128,
2591 dw2_asm_delta_sleb128): Convert fprintf calls to the new functions.
2592 * dwarf2out.c (dwarf2out_source_line): Call fprint_ul instead of
2594 * final.c (fprint_whex, fprint_w, fprint_ul, sprint_ul): New functions
2595 serving as fast replacements for fprintf integer to string conversions.
2596 (sprint_ul_rev): Internal helper for the above.
2597 (output_addr_const) <CONST_INT>: Don't use fprintf.
2598 * varasm.c: Fix some whitespace inconsistencies.
2599 (default_elf_asm_output_limited_string): New.
2600 (default_elf_asm_output_ascii): Likewise.
2601 (default_elf_internal_label): Likewise.
2602 * config/elfos.h (ASM_GENERATE_INTERNAL_LABEL): Use sprint_ul and
2603 stpcpy instead of sprintf.
2604 (TARGET_ASM_INTERNAL_LABEL): Define as default_elf_internal_label.
2605 (ELF_ASCII_ESCAPES, ELF_STRING_LIMIT): Rename from old ESCAPES and
2606 STRING_LIMIT macros.
2607 (ASM_OUTPUT_LIMITED_STRING, ASM_OUTPUT_ASCII): Call functions that
2608 provide the same functionality.
2609 * config/i386/i386.c (print_reg): Call fprint_ul instead of fprintf.
2611 2011-11-10 Andrew MacLeod <amacleod@redhat.com>
2613 * doc/extend.texi: Document __atomic_test_and_set and __atomic_clear.
2615 2011-11-10 Andrew MacLeod <amacleod@redhat.com>
2618 * builtins.c (expand_builtin_atomic_clear): New. Expand atomic_clear.
2619 (expand_builtin_atomic_test_and_set): New. Expand atomic test_and_set.
2620 (expand_builtin): Add cases for test_and_set and clear.
2621 * sync-builtins.def (BUILT_IN_ATOMIC_TEST_AND_SET): New.
2622 (BUILT_IN_ATOMIC_CLEAR): New.
2624 2011-11-10 Roberto Agostino Vitillo <ravitillo@lbl.gov>
2627 * dwarf2out.c (set_cur_line_info_table): Restore the last is_stmt
2628 value in the current line table.
2630 2011-11-10 Nathan Sidwell <nathan@acm.org>
2632 * gcov.c (struct function_info): Make src an index, not a pointer.
2633 (struct source_info): Remove index and next source fields.
2634 (fn_end): New static var.
2635 (sources_index): Remove.
2636 (sources): Now a pointer to an array, not a list.
2637 (n_sources, a_sources): New.
2638 (process_file): Adjust for changes to read_graph_file. Insert
2639 functions into source lists and check line numbers here.
2640 (generate_results): Only allocate lines for sources with
2641 contents. Adjust for source array.
2642 (release_structures): Likewise.
2643 (find_source): Return source index, adjust for source array.
2644 (read_graph_file): Return function list. Don't insert into source
2646 (read_count_file): Take list of functions.
2647 (solve_flow_graph): Reverse the arc lists here.
2648 (add_line_counts): Adjust for source array.
2650 2011-11-10 Jakub Jelinek <jakub@redhat.com>
2653 * tree-object-size.c (addr_object_size): Check TREE_CODE of
2654 MEM_REF's operand rather than code of the MEM_REF itself.
2656 2011-11-10 Andrew MacLeod <amacleod@redhat.com>
2658 PR rtl-optimization/51040
2659 * optabs.c (expand_atomic_fetch_op): Patchup code for NAND should
2660 be AND followed by NOT.
2661 * builtins.c (expand_builtin_atomic_fetch_op): Patchup code for NAND
2662 should be AND followed by NOT.
2664 2011-11-10 Jakub Jelinek <jakub@redhat.com>
2666 * vec.h (VEC_BASE): If base is at offset 0 in the structure,
2667 use &(P)->base even if P is NULL.
2669 PR rtl-optimization/51023
2670 * combine.c (simplify_comparison) <case SIGN_EXTEND>: Don't use
2671 val_signbit_known_clear_p for signed comparison narrowing
2672 optimization. Don't check for non-VOIDmode, use
2673 HWI_COMPUTABLE_MODE_P macro.
2674 <case ZERO_EXTEND>: Don't check for non-VOIDmode.
2675 Optimize even when const_op is equal to GET_MODE_MASK (mode),
2676 don't optimize if const_op is negative.
2678 2011-11-10 Richard Guenther <rguenther@suse.de>
2680 PR tree-optimization/51042
2681 * tree-ssa-pre.c (phi_translate_1): Avoid recursing on
2682 self-referential expressions. Refactor code to avoid duplication.
2684 2011-11-10 Richard Guenther <rguenther@suse.de>
2686 PR tree-optimization/51070
2687 * tree-loop-distribution.c (generate_builtin): Do not replace
2688 the loop with a builtin if the partition contains statements which
2689 results are used outside of the loop.
2690 (pass_loop_distribution): Verify and collect.
2692 2011-11-10 Richard Guenther <rguenther@suse.de>
2694 PR tree-optimization/51030
2695 * tree-ssa-phiopt.c (jump_function_from_stmt): New function.
2696 (value_replacement): Use it to handle trivial non-empty
2697 intermediate blocks.
2699 2011-11-10 Richard Guenther <rguenther@suse.de>
2702 * gimple.c (gimple_has_side_effects): Remove checking code
2703 that doesn't belong here.
2705 2011-11-10 Ira Rosen <ira.rosen@linaro.org>
2707 PR tree-optimization/51058
2708 * tree-vect-slp.c (vect_get_constant_vectors): Handle CALL_EXPR.
2710 2011-11-10 Jakub Jelinek <jakub@redhat.com>
2712 PR tree-optimization/51000
2713 * tree-vect-patterns.c (vect_recog_bool_pattern): If adding
2714 a pattern stmt for a bool store, adjust DR_STMT too.
2715 Don't handle bool conversions to single bit precision lhs.
2716 * tree-vect-stmts.c (vect_remove_stores): If next is a pattern
2717 stmt, remove its related stmt and free its stmt_vinfo.
2718 (free_stmt_vec_info): Free also pattern stmt's vinfo and
2719 pattern def stmt's vinfo.
2720 * tree-vect-loop.c (destroy_loop_vec_info): Don't try to
2721 free pattern stmt's vinfo here.
2722 (vect_transform_loop): When calling vect_remove_stores,
2723 do gsi_next first and don't call gsi_remove. If not strided
2724 store, free stmt vinfo for gsi_stmt (si) rather than stmt.
2726 2011-11-09 Jakub Jelinek <jakub@redhat.com>
2729 * config/i386/i386.c (expand_vec_perm_interleave2): If d->vmode is
2730 V4SImode, !TARGET_SSE2 and punpck[lh]* is needed, change dremap.vmode
2733 * function.h (requires_stack_frame_p): New prototype.
2734 * function.c (requires_stack_frame_p): No longer static.
2735 * config/i386/i386.c (ix86_finalize_stack_realign_flags): If
2736 stack_realign_fp was just a conservative guess for a function
2737 which doesn't use sp/fp/argp at all, clear frame_pointer_needed
2738 and stack realignment.
2740 2011-11-09 Paolo Carlini <paolo.carlini@oracle.com>
2742 PR preprocessor/51061
2743 * incpath.c (merge_include_chains): Make sure to not pass null
2744 pointers to free_path.
2746 2011-11-09 Paolo Carlini <paolo.carlini@oracle.com>
2748 * doc/invoke.texi ([Option Summary, C++ Language Options]):
2749 Add -Wzero-as-null-pointer-constant.
2751 2011-11-07 Matthew Gretton-Dann <matthew.gretton-dann@arm.com>
2753 * config/arm/arm-cores.def: Add -mcpu=cortex-a7.
2754 * config/arm/arm-tables.opt: Regenerate.
2755 * config/arm/arm-tune.md: Likewise.
2756 * config/arm/bpabi.h (BE8_LINK_SPEC): Add Cortex A-7.
2757 * doc/invoke.texi: Document -mcpu=cortex-a7.
2759 2011-11-09 Richard Guenther <rguenther@suse.de>
2762 2011-11-09 Richard Guenther <rguenther@suse.de>
2764 * tree-cfg.c (verify_gimple_call): Verify that
2765 gimple_call_cannot_inline_p is returning a conservative
2766 correct result according to gimple_check_call_matching_types.
2768 2011-11-09 Richard Guenther <rguenther@suse.de>
2770 PR tree-optimization/51039
2771 * tree-cfg.c (verify_gimple_call): Verify that
2772 gimple_call_cannot_inline_p is returning a conservative
2773 correct result according to gimple_check_call_matching_types.
2774 * ipa-inline-analysis.c (estimate_function_body_sizes): Remove
2775 code dealing with un-inlinablility.
2776 * gimple-streamer-in.c (input_gimple_stmt): Update the
2779 2011-11-09 Richard Guenther <rguenther@suse.de>
2781 PR tree-optimization/51039
2782 * tree-inline.c (setup_one_parameter): Always perform a
2783 valid gimple type change.
2784 (declare_return_variable): Likewise.
2786 2011-11-09 Jakub Jelinek <jakub@redhat.com>
2788 * config/rs6000/vector.md (vcondv4sfv4si, vcondv4siv4sf,
2789 vconduv4sfv4si): New patterns.
2790 * config/rs6000/rs6000.c (rs6000_emit_vector_cond_expr): Handle
2791 different dest_mode from comparison mode.
2793 2011-11-09 Richard Guenther <rguenther@suse.de>
2795 * gimple-fold.c (canonicalize_constructor_val): Mark
2796 address-taken variables addressable.
2798 2011-11-09 Ira Rosen <ira.rosen@linaro.org>
2800 PR tree-optimization/51015
2801 * tree-vect-loop.c (vect_determine_vectorization_factor): Expect
2802 vectype to be set for pattern def stmts.
2804 2011-11-09 Alan Modra <amodra@gmail.com>
2806 * function.c (bb_active_p): Delete.
2807 (dup_block_and_redirect, active_insn_between): New functions.
2808 (convert_jumps_to_returns, emit_return_for_exit): New functions,
2810 (thread_prologue_and_epilogue_insns): ..here. Delete
2811 shadowing variables. Don't do prologue register clobber tests
2812 when shrink wrapping already failed. Delete all last_bb_active
2813 code. Instead compute tail block candidates for duplicating
2814 exit path. Remove these from antic set. Duplicate tails when
2815 reached from both blocks needing a prologue/epilogue and
2816 blocks not needing such.
2817 * ifcvt.c (dead_or_predicable): Test both flag_shrink_wrap and
2819 * bb-reorder.c (get_uncond_jump_length): Make global.
2820 * bb-reorder.h (get_uncond_jump_length): Declare.
2821 * cfgrtl.c (rtl_create_basic_block): Comment typo fix.
2822 (rtl_split_edge): Likewise. Warning fix.
2823 (rtl_duplicate_bb): New function.
2824 (rtl_cfg_hooks): Enable can_duplicate_block_p and duplicate_block.
2825 * Makefile.in (function.o): Update dependencies.
2827 2011-11-08 Ulrich Weigand <Ulrich.Weigand@de.ibm.com>
2828 Georg-Johann Lay <avr@gjlay.de>
2830 * doc/tm.texi.in (MODE_CODE_BASE_REG_CLASS): Add address space
2832 (REGNO_MODE_CODE_OK_FOR_BASE_P): Likewise.
2833 * doc/tm.texi: Regenerate.
2835 * config/cris/cris.h (MODE_CODE_BASE_REG_CLASS): Add address
2837 (REGNO_MODE_CODE_OK_FOR_BASE_P): Likewise.
2838 * config/bfin/bfin.h (MODE_CODE_BASE_REG_CLASS): Likewise.
2839 (REGNO_MODE_CODE_OK_FOR_BASE_P): Likewise.
2840 * config/avr/avr.h (MODE_CODE_BASE_REG_CLASS): Add address space
2842 (REGNO_MODE_CODE_OK_FOR_BASE_P): Ditto.
2843 * config/avr/avr-protos.h (avr_mode_code_base_reg_class): Ditto.
2844 (avr_regno_mode_code_ok_for_base_p): Ditto.
2845 * config/avr/avr.c (avr_mode_code_base_reg_class): Ditto.
2846 (avr_regno_mode_code_ok_for_base_p): Ditto.
2847 (avr_reg_ok_for_addr_p): Pass AS down to
2848 avr_regno_mode_code_ok_for_base_p.
2850 * addresses.h (base_reg_class): Add address space argument.
2851 Pass to MODE_CODE_BASE_REG_CLASS.
2852 (ok_for_base_p_1): Add address space argument. Pass to
2853 REGNO_MODE_CODE_OK_FOR_BASE_P.
2854 (regno_ok_for_base_p): Add address space argument. Pass to
2857 * regrename.c (scan_rtx_address): Add address space argument.
2858 Pass address space to regno_ok_for_base_p and base_reg_class.
2859 Update recursive calls.
2860 (scan_rtx): Pass address space to scan_rtx_address.
2861 (build_def_use): Likewise.
2862 * regcprop.c (replace_oldest_value_addr): Add address space
2863 argument. Pass to regno_ok_for_base_p and base_reg_class.
2864 Update recursive calls.
2865 (replace_oldest_value_mem): Pass address space to
2866 replace_oldest_value_addr.
2867 (copyprop_hardreg_forward_1): Likewise.
2869 * reload.c (find_reloads_address_1): Add address space argument.
2870 Pass address space to base_reg_class and regno_ok_for_base_p.
2871 Update recursive calls.
2872 (find_reloads_address): Pass address space to base_reg_class,
2873 regno_ok_for_base_p, and find_reloads_address_1.
2874 (find_reloads): Pass address space to base_reg_class.
2875 (find_reloads_subreg_address): Likewise.
2877 * ira-costs.c (record_reg_classes): Update calls to base_reg_class.
2878 (ok_for_base_p_nonstrict): Add address space argument. Pass to
2880 (record_address_regs): Add address space argument. Pass to
2881 base_reg_class and ok_for_base_p_nonstrict. Update recursive calls.
2882 (record_operand_costs): Pass address space to record_address_regs.
2883 (scan_one_insn): Likewise.
2885 * caller-save.c (init_caller_save): Update call to base_reg_class.
2886 * ira-conflicts.c (ira_build_conflicts): Likewise.
2887 * reload1.c (maybe_fix_stack_asms): Likewise.
2889 2011-11-08 Michael Matz <matz@suse.de>
2891 * gengtype.c (write_field_root): Avoid out-of-scope access of newv.
2893 * tree-stdarg.c (execute_optimize_stdarg): Accept clobbers.
2895 * tree.h (TREE_CLOBBER_P): New macro.
2896 * gimple.h (gimple_clobber_p): New inline function.
2897 * gimplify.c (gimplify_bind_expr): Add clobbers for all variables
2898 that go out of scope and live in memory.
2899 * tree-ssa-operands.c (get_expr_operands): Transfer volatility also
2901 * cfgexpand.c (decl_to_stack_part): New static variable.
2902 (add_stack_var): Allocate it, and remember mapping.
2903 (fini_vars_expansion): Deallocate it.
2904 (stack_var_conflict_p): Add early outs.
2905 (visit_op, visit_conflict, add_scope_conflicts_1,
2906 add_scope_conflicts): New static functions.
2907 (expand_used_vars_for_block): Don't call add_stack_var_conflict, tidy.
2908 (expand_used_vars): Add scope conflicts.
2909 (expand_gimple_stmt_1): Expand clobbers to nothing.
2910 (expand_debug_expr): Ditto.
2912 * tree-pretty-print.c (dump_generic_node): Dump clobbers nicely.
2913 * tree-ssa-live.c (remove_unused_locals): Remove clobbers that
2914 refer to otherwise unused locals.
2915 * tree-sra.c (build_accesses_from_assign): Ignore clobbers.
2916 * tree-ssa-dce.c (mark_stmt_if_obviously_necessary): Clobbers of
2917 SSA names aren't necessary.
2918 (propagate_necessity): Accept and ignore constructors on the rhs, tidy.
2919 * gimple.c (walk_gimple_op): Accept constructors like mem_rhs.
2920 * tree-ssa-structalias.c (find_func_aliases): Clobbers don't store
2922 * tree-ssa-sccvn.c (vn_reference_lookup_3): Ditto, in particular they
2923 don't zero-initialize something.
2924 * tree-ssa-phiopt.c (cond_if_else_store_replacement_1): Ignore
2925 clobber RHS, we don't want PHI nodes with those.
2927 2011-11-08 Jakub Jelinek <jakub@redhat.com>
2929 * config/i386/i386.c (ix86_preferred_simd_mode): Even for TARGET_AVX
2930 if not TARGET_PREFER_AVX128 return 32-byte integer vectors.
2932 2011-11-08 Richard Guenther <rguenther@suse.de>
2934 PR tree-optimization/51012
2935 * ipa-prop.c (update_indirect_edges_after_inlining): Fixup
2936 non-inlinable state.
2937 * cgraph.c (cgraph_make_edge_direct): Likewise.
2939 2011-11-08 Eric Botcazou <ebotcazou@adacore.com>
2941 PR rtl-optimization/47698
2942 * ifcvt.c (noce_operand_ok): Move around comment.
2944 2011-11-08 Richard Guenther <rguenther@suse.de>
2947 * lto-opts.c (append_to_collect_gcc_options): Split out from...
2948 (lto_write_options): ... here. Prepend frontend specific flags.
2950 2011-11-08 Jakub Jelinek <jakub@redhat.com>
2952 * config/i386/sse.md (*avx_vperm2f128<mode>3_nozero): Emit mask
2953 0x12 and 0x20 as vinsert[fi]128 instead of vperm2[fi]128.
2955 * tree-vect-stmts.c (vectorizable_call): Add SLP_NODE argument.
2956 Handle vectorization of SLP calls.
2957 (vect_analyze_stmt): Adjust caller, add call to it for SLP too.
2958 (vect_transform_stmt): Adjust vectorizable_call caller, remove
2960 * tree-vect-slp.c (vect_get_and_check_slp_defs): For calls start
2962 (vect_build_slp_tree): Allow CALL_EXPR.
2964 2011-11-08 Richard Guenther <rguenther@suse.de>
2966 * gimple-fold.c (canonicalize_constructor_val): Make sure
2967 we have referenced vars setup before adding to them.
2969 2011-11-07 Richard Henderson <rth@redhat.com>
2970 Aldy Hernandez <aldyh@redhat.com>
2971 Andrew MacLeod <amacleod@redhat.com>
2972 Torvald Riegel <triegel@redhat.com>
2974 Merged from transactional-memory.
2976 * gtm-builtins.def: New file.
2977 * trans-mem.c: New file.
2978 * trans-mem.h: New file.
2980 * opts.c (finish_options): Error out when using -flto and -fgnu-tm.
2982 * config/i386/i386.c: Define TARGET_VECTORIZE* transactional variants.
2983 (ix86_handle_tm_regparm_attribute, struct bdesc_tm,
2984 ix86_builtin_tm_load, ix86_builtin_tm_store,
2985 ix86_init_tm_builtins): New.
2986 (ix86_init_builtins): Initialize TM builtins.
2987 (struct ix86_attribute_table): Add "*tm regparm".
2988 * config/i386/i386-builtin-types.def (PV2SI): Define.
2990 Define V2SI_FTYPE_PCV2SI.
2991 Define V4SF_FTYPE_PCV4SF.
2992 Define V8SF_FTYPE_PCV8SF.
2993 Define VOID_PV2SI_V2SI.
2995 * doc/invoke.texi (C Dialect Options): Document -fgnu-tm and
2996 tm-max-aggregate-size.
2997 * doc/tm.texi.in: Add TARGET_VECTORIZE_BUILTIN_TM_LOAD and
2998 TARGET_VECTORIZE_BUILTIN_TM_STORE hooks.
2999 * doc/tm.texi: Regenerate.
3001 * attribs.c (apply_tm_attr): New.
3002 (init_attributes): Allow '*' prefix for overrides.
3003 (register_attribute): Likewise.
3004 * builtin-attrs.def (ATTR_TM_TMPURE, ATTR_TM_REGPARM): New.
3005 (ATTR_TM_NOTHROW_LIST, ATTR_TM_TMPURE_NOTHROW_LIST,
3006 ATTR_TM_PURE_TMPURE_NOTHROW_LIST, ATTR_TM_NORETURN_NOTHROW_LIST,
3007 ATTR_TM_CONST_NOTHROW_LIST, ATTR_TMPURE_MALLOC_NOTHROW_LIST,
3008 ATTR_TMPURE_NOTHROW_LIST): New.
3009 * builtin-types.def (BT_FN_I[1248]_VPTR, BT_FN_FLOAT_VPTR,
3010 BT_FN_DOUBLE_VPTR, BT_FN_LDOUBLE_VPTR, BT_FN_VOID_VPTR_I[1248],
3011 BT_FN_VOID_VPTR_FLOAT, BT_FN_VOID_VPTR_DOUBLE,
3012 BT_FN_VOID_VPTR_LDOUBLE, BT_FN_VOID_VPTR_SIZE): New.
3013 * builtins.def: Include gtm-builtins.def. Add comments regarding
3014 transactional memory synchronization.
3015 (DEF_TM_BUILTIN): New.
3016 * c-parser.c (struct c_parser): Add in_transaction.
3017 (c_parser_transaction, c_parser_transaction_expression,
3018 c_parser_transaction_cancel, c_parser_transaction_attributes): New.
3019 (c_parser_attribute_any_word): Split out from c_parser_attributes.
3020 (c_parser_statement_after_labels): Handle RID_TRANSACTION*.
3021 (c_parser_unary_expression): Same.
3022 * c-tree.h (c_finish_transaction): Declare.
3023 * c-typeck.c (c_finish_transaction): New.
3024 (build_function_call_vec): Call tm_malloc_replacement.
3025 * calls.c (is_tm_builtin): New.
3026 (flags_from_decl_or_type): Add ECF_TM_BUILTIN and ECF_TM_PURE.
3027 * cfgbuild.c (make_edges): Add edges for REG_TM notes.
3028 * cfgexpand.c (expand_call_stmt): Call
3029 mark_transaction_restart_calls.
3030 (gimple_expand_cfg): Free the tm_restart map.
3031 (mark_transaction_restart_calls): New.
3032 * cfgrtl.c (purge_dead_edges): Look for REG_TM notes.
3033 * cgraph.c (dump_cgraph_node): Handle tm_clone.
3034 * cgraph.h (struct cgraph_node): Add tm_clone field.
3035 (decl_is_tm_clone): New.
3036 (struct cgraph_local_info): Add tm_may_enter_irr.
3037 (cgraph_copy_node_for_versioning): Declare.
3038 * cgraphunit.c (cgraph_copy_node_for_versioning): Export;
3039 copy analyzed from old version.
3040 * combine.c (distribute_notes): Handle REG_TM notes.
3041 * common.opt: Add -fgnu-tm.
3042 * crtstuff.c (__TMC_LIST__, __TMC_END__): New.
3043 (__do_global_dtors_aux): Deregister clone table.
3044 (frame_dummy): Register clone table.
3045 * emit-rtl.c (try_split): Handle REG_TM. Early return if no function
3047 * gimple-low.c (lower_stmt): Handle GIMPLE_EH_ELSE and
3049 (gimple_stmt_may_fallthru): Handle GIMPLE_EH_ELSE.
3050 * gimple-pretty-print.c: Include trans-mem.h.
3051 (dump_gimple_fmt): Add %x.
3052 (dump_gimple_call): Dump arguments for calls to _ITM_beginTransaction.
3053 (dump_gimple_eh_else, dump_gimple_transaction): New.
3054 (dump_gimple_stmt): Handle GIMPLE_EH_ELSE and GIMPLE_TRANSACTION.
3055 * gimple.c (gimple_build_eh_else, gimple_build_transaction): New.
3056 (walk_gimple_seq): Honor removed_stmt. Document usage of removed_stmt
3058 (walk_gimple_op): Handle GIMPLE_TRANSACTION.
3059 (walk_gimple_stmt): Initialize and honor removed_stmt.
3060 Handle GIMPLE_EH_ELSE and GIMPLE_TRANSACTION.
3061 (gimple_copy): Handle GIMPLE_EH_ELSE and GIMPLE_TRANSACTION.
3062 * gimple.def (GIMPLE_TRANSACTION, GIMPLE_EH_ELSE): New.
3063 * gimple.h (struct gimple_statement_eh_else,
3064 gimple_statement_transaction, GTMA_*): New.
3065 (gimple_statement_d): Add gimple_statement_eh_else and
3067 (gimple_build_eh_else, gimple_build_transaction,
3068 gimple_fold_call, diagnose_tm_safe_errors): Declare.
3069 (get_call_expr_in): Remove prototype.
3070 (gimple_has_substatements): Add GIMPLE_EH_ELSE and GIMPLE_TRANSACTION.
3071 (gimple_eh_else_n_body, gimple_eh_else_e_body,
3072 gimple_eh_else_set_n_body, gimple_eh_else_set_e_body,
3073 gimple_transaction_body, gimple_transaction_label,
3074 gimple_transaction_label_ptr, gimple_transaction_subcode,
3075 gimple_transaction_set_body, gimple_transaction_set_label,
3076 gimple_transaction_set_subcode): New.
3077 (struct walk_stmt_info): Use BOOL_BITFIELD; add removed_stmt.
3078 * gimplify.c (create_tmp_var_name): Use clean_symbol_name.
3079 (voidify_wrapper_expr): Handle TRANSACTION_EXPR.
3080 (gimplify_transaction): New.
3081 (gimplify_expr): Handle TRANSACTION_EXPR.
3082 * gsstruct.def (GSS_EH_ELSE, GSS_TRANSACTION): New.
3083 * ipa-inline.c (can_inline_edge_p): Do not inline TM safe calling
3085 * Makefile.in: Add trans-mem.o and dependencies.
3086 (BUILTINS_DEF): Add gtm-builtins.def.
3087 (gimple-pretty-print.o): Depend on TRANS_MEM_H.
3088 (GTFILES): Add trans-mem.c.
3089 * omp-low.c (WALK_SUBSTMTS): Add GIMPLE_TRANSACTION.
3090 * output.h (record_tm_clone_pair, finish_tm_clone_pairs,
3091 get_tm_clone_pair): Declare.
3092 * params.def (PARAM_TM_MAX_AGGREGATE_SIZE): New.
3093 * passes.c (init_optimization_passes): Place transactional memory
3095 * print-tree.c (print_node): Dump tm-clone.
3096 * recog.c (peep2_attempt): Handle REG_TM.
3097 * reg-notes.def (TM): New.
3098 * rtlanal.c (alloc_reg_note): Handle REG_TM.
3099 * target.def (builtin_tm_load, builtin_tm_store): New.
3100 * targhooks.c (default_builtin_tm_load_store): New.
3101 * targhooks.h (default_builtin_tm_load_store): Declare.
3102 * timevar.def (TV_TRANS_MEM): New.
3103 * toplev.c (compile_file): Call finish_tm_clone_pairs.
3104 * tree-cfg.c (make_edges): Handle GIMPLE_TRANSACTION.
3105 (cleanup_dead_labels): Handle GIMPLE_TRANSACTION. Avoid unnecessary
3106 writes into the statements to update labels.
3107 (is_ctrl_altering_stmt): Add TM ending statements. Handle
3109 (verify_gimple_transaction): New.
3110 (verify_gimple_stmt): Handle GIMPLE_TRANSACTION.
3111 (verify_gimple_in_seq_2): Handle GIMPLE_EH_ELSE and GIMPLE_TRANSACTION.
3112 (gimple_redirect_edge_and_branch): Handle TM_TRANSACTION.
3113 (dump_function_to_file): Display [tm-clone] if applicable.
3114 * tree-eh.c (struct_ptr_eq): Make inline and move to tree.h.
3115 (struct_ptr_hash): Same.
3116 (collect_finally_tree): Handle GIMPLE_EH_ELSE.
3117 (replace_goto_queue_1): Likewise.
3119 (honor_protect_cleanup_actions): Handle GIMPLE_EH_ELSE.
3120 (lower_try_finally_nofallthru): Likewise.
3121 (lower_try_finally_onedest): Likewise.
3122 (lower_try_finally_copy): Likewise.
3123 (lower_try_finally_switch): Likewise.
3124 (lower_try_finally): Likewise.
3125 (decide_copy_try_finally): Likewise.
3126 (lower_eh_constructs_2): Likewise.
3127 (refactor_eh_r): Likewise.
3128 * tree-flow.h (struct gimple_df): Add tm_restart field.
3129 Define tm_restart_node.
3130 * tree-inline.c (remap_gimple_stmt): Handle GIMPLE_TRANSACTION.
3131 (estimate_num_insns): Likewise.
3132 (init_inline_once): Init tm_cost.
3133 * tree-inline.h (struct eni_weights_d): Add tm_cost.
3134 * tree-pass.h (pass_diagnose_tm_blocks, pass_lower_tm, pass_tm_init,
3135 pass_tm_mark, pass_tm_memopt, pass_tm_edges, pass_ipa_tm): Declare.
3136 * tree-pretty-print.c (dump_generic_node): Handle TRANSACTION_EXPR.
3137 * tree-ssa-alias.c (ref_maybe_used_by_call_p_1): Handle
3138 BUILT_IN_TM_MEMSET, BUILT_IN_TM_MEMCPY, BUILT_IN_TM_MEMMOVE.
3139 Add support for TM vector loads. Add support for TM logging builtins.
3140 (call_may_clobber_ref_p_1): Add support for vector stores.
3141 * tree-ssa-structalias.c (find_func_aliases): Add support for TM
3142 vector stores and loads. Handle BUILT_IN_TM_MEMSET,
3143 BUILT_IN_TM_MEMCPY, BUILT_IN_TM_MEMMOVE.
3144 * tree.c (strip_invariant_refs): Moved from gimple.c to here.
3145 (local_define_builtin): Handle ECF_TM_PURE.
3146 (build_common_builtin_nodes): Set __builtin_eh_pointer to ECF_TM_PURE.
3147 * tree.def (TRANSACTION_EXPR): New.
3148 * tree.h (strip_invariant_refs): Moved from gimple.h to here.
3149 (TRANSACTION_EXPR_BODY, TRANSACTION_EXPR_CHECK,
3150 TRANSACTION_EXPR_OUTER, TRANSACTION_EXPR_RELAXED,
3151 BUILTIN_TM_LOAD_STORE_P, BUILTIN_TM_LOAD_P, BUILTIN_TM_STORE_P,
3152 CASE_BUILT_IN_TM_LOAD, CASE_BUILT_IN_TM_STORE): New.
3153 (ECF_TM_PURE, ECF_TM_BUILTIN): New.
3154 (struct tree_function_decl): Add tm_clone_flag.
3155 (struct_ptr_eq, struct_ptr_hash): New.
3156 (apply_tm_attr): Declare.
3157 (is_tm_safe_or_pure): New.
3158 (build_tm_abort_call, is_tm_safe, is_tm_pure,
3159 is_tm_may_cancel_outer, is_tm_ending_fndecl, record_tm_replacement,
3160 tm_malloc_replacement): Declare.
3161 * varasm.c (tm_clone_hash): New.
3162 (record_tm_clone_pair, finish_tm_clone_pairs, get_tm_clone_pair,
3163 dump_tm_clone_to_vec, dump_tm_clone_pairs, tm_alias_pair_cmp): New.
3164 (struct tm_alias_pair): New. Declare VEC types for object.
3166 2011-11-07 Richard Henderson <rth@redhat.com>
3168 * optabs.h (OTI_sync_compare_and_swap, OTI_sync_lock_test_and_set,
3169 OTI_sync_old_add, OTI_sync_old_sub, OTI_sync_old_ior,
3170 OTI_sync_old_and, OTI_sync_old_xor, OTI_sync_old_nand,
3171 OTI_sync_new_add, OTI_sync_new_sub, OTI_sync_new_ior,
3172 OTI_sync_new_and, OTI_sync_new_xor, OTI_sync_new_nand): Move and
3173 rename from the direct_optab_index enum.
3174 (sync_compare_and_swap_optab, sync_lock_test_and_set_optab,
3175 sync_old_add_optab, sync_old_sub_optab, sync_old_ior_optab,
3176 sync_old_and_optab, sync_old_xor_optab, sync_old_nand_optab,
3177 sync_new_add_optab, sync_new_sub_optab, sync_new_ior_optab,
3178 sync_new_and_optab, sync_new_xor_optab, sync_new_nand_optab): Read
3179 from the optab_table, not the direct_optab_table.
3180 (init_sync_libfuncs): Declare.
3181 (can_compare_and_swap_p): Update parameters.
3182 * optabs.c (init_sync_libfuncs_1, init_sync_libfuncs): New.
3183 (can_compare_and_swap_p): Add allow_libcall parameter; if true,
3184 test for the legacy compare-and-swap libcall.
3185 (expand_atomic_exchange): Use the legacy test-and-set libcall.
3186 (expand_atomic_compare_and_swap): Use the legacy CAS libcall.
3187 (struct atomic_op_functions): Update for optab type changes.
3188 (maybe_emit_op): Likewise.
3189 (expand_atomic_fetch_op): Use the legacy fetch-op libcalls.
3190 * builtins.c (fold_builtin_atomic_always_lock_free): Update call
3191 to can_compare_and_swap_p.
3192 * omp-low.c (expand_omp_atomic_fetch_op): Likewise.
3193 (expand_omp_atomic_pipeline): Likewise.
3194 * genopinit.c (optabs): Make sync_old_*_optab, sync_new_*_optab,
3195 sync_compare_and_swap_optab, sync_lock_test_and_set_optab regular
3197 * doc/md.texi (sync_compare_and_swap): Update docs for libcalls.
3199 2011-11-07 Jakub Jelinek <jakub@redhat.com>
3201 * config/i386/i386-bultin-types.def (V8SI_FTYPE_V4DF_V4DF): Add.
3202 * config/i386/i386.c (enum ix86_builtins): Add
3203 IX86_BUILTIN_VEC_PACK_SFIX256.
3204 (bdesc_args): Add __builtin_ia32_vec_pack_sfix256.
3205 (ix86_expand_args_builtin): Handle V8SI_FTYPE_V4DF_V4DF.
3206 (ix86_builtin_vectorized_function): Also vectorize lrint using
3207 256-bit vectors for -mavx.
3209 2011-11-07 Anatoly Sokolov <aesok@post.ru>
3211 * config/cris/constraints.md: New file.
3212 * config/cris/cris.h (REG_CLASS_FROM_LETTER, CONSTRAINT_LEN,
3213 CRIS_CONST_OK_FOR_LETTER_P, CONST_OK_FOR_CONSTRAINT_P,
3214 CONST_DOUBLE_OK_FOR_LETTER_P, EXTRA_MEMORY_CONSTRAINT,
3215 EXTRA_CONSTRAINT, EXTRA_CONSTRAINT_Q, EXTRA_CONSTRAINT_R,
3216 EXTRA_CONSTRAINT_T, EXTRA_CONSTRAINT_S, EXTRA_CONSTRAINT_U): Remove.
3217 * config/cris/cris.c: Incule "tm-constrs.h".
3218 (cris_print_operand): Use satisfies_constraint_O.
3219 (cris_normal_notice_update_cc, cris_rtx_costs): Use
3220 satisfies_constraint_I.
3221 (cris_address_cost): Use satisfies_constraint_L.
3222 * config/cris/cris.md: Include "constraints.md".
3223 (*mov_side<mode>, *mov_sidesisf, *mov_side<mode>_mem,
3224 *mov_sidesisf_mem, *clear_side<mode>, *ext_sideqihi,
3225 *ext_side<mode>si, *op_side<mode>, *op_swap_side<mode>,
3226 *extopqihi_side, *extop<mode>si_side, *extopqihi_swap_side,
3227 *extop<mode>si_swap_side): Use satisfies_constraint_N and
3228 satisfies_constraint_J.
3229 (moversideqi movemsideqi mover2side peephole2): Use
3230 satisfies_constraint_N and satisfies_constraint_J.
3231 (andu peephole2): Use satisfies_constraint_I and
3232 satisfies_constraint_O.
3234 2011-11-07 Uros Bizjak <ubizjak@gmail.com>
3236 * config/i386/i386.c (ix86_builtin_vectorized_function): Handle
3237 BUILT_IN_IRINT, BUILT_IN_IRINTF, BUILT_IN_LLRINT and BUILT_IN_LLRINTF.
3239 2011-11-07 Andrew MacLeod <amacleod@redhat.com>
3241 * optabs.c (get_atomic_op_for_code): Fill in optab table at runtime so
3242 SWITCHABLE_TARGET can change the values during compilation.
3243 (expand_atomic_fetch_op): Handle parameter change ripples for
3244 get_atomic_op_for_code call.
3246 2011-11-07 Andrew MacLeod <amacleod@redhat.com>
3248 * doc/extend.texi: Docuemnt behaviour change for __atomic_exchange and
3250 * optabs.c (expand_atomic_exchange): Expand to __sync_lock_test_and_set
3251 only when originated from that builtin.
3252 (expand_atomic_store): Expand to __sync_lock_release when originated
3254 * builtins.c (expand_builtin_sync_lock_test_and_set): Add flag that
3255 expand_atomic_exchange call originated from here.
3256 (expand_builtin_sync_lock_release): Add flag that expand_atomic_store
3257 call originated from here.
3258 (expand_builtin_atomic_exchange): Add origination flag.
3259 (expand_builtin_atomic_store): Add origination flag.
3260 * expr.h (expand_atomic_exchange, expand_atomic_store): Add boolean
3261 parameters to indicate implementation fall back options.
3263 2011-11-07 Georg-Johann Lay <avr@gjlay.de>
3265 * config/avr/avr.c (output_reload_in_const): Can handle CONSTANT_P
3266 now, not only CONST_INT and CONST_DOUBLE.
3267 (output_movqi): Use output_reload_in_const.
3268 (output_reload_inhi): Ditto.
3269 (output_reload_insisf): Move assertion to output_reload_in_const.
3270 (avr_out_reload_inpsi): Ditto.
3272 2011-11-07 Nathan Sidwell <nathan@acm.org>
3274 * gcov.c (object_summary): Replace with ...
3275 (object_runs): ... this.
3276 (process_file): Remove functions with no data.
3277 (generate_results): Ignore files with no lines.
3278 (release_function): New helper, broken out of ...
3279 (release_structures): ... here. Use it.
3280 (read_count_file): Adjust for new data file format.
3281 (output_lines): Use object_runs.
3282 * gcov-io.h (GCOV_TAG_OBJECT_SUMMARY): Obsolete.
3283 (struct gcov_ctr_info): Move definition.
3284 (struct gcov_fn_info): Add key field, use gcov_ctr_info for
3286 (struct gcov_info): Add merge function array, remove mask and
3287 counts. Trailing array is array of pointers to function info.
3288 * coverage.c (struct function_list): Replace counter numbers with
3289 counter arrays. Add fndecl field. GTYify.
3290 (counts_entry): Remove chain workspace.
3291 (functions_head): GTYify.
3292 (prg_n_ctrs): Remove.
3294 (tree_ctr_tables): Remove.
3295 (read_counts_file): Cope with blank entries and expect program
3296 summaries before functions. Don't warn on missing entries.
3297 (coverage_counter_alloc): Allocate individual function arrays.
3298 (tree_coverage_counter_ref, tree_coverage_counter_addr): Adjust
3299 for individual function arrays.
3300 (coverage_end_function): GTYify function list object. Finalize
3301 function's counter arrays.
3302 (build_var): New. Create a counter-related variable with
3303 appropriate linkage.
3304 (build_fn_info_type): Adjust for new runtime structure.
3305 (build_fn_info_value): Rename to ...
3306 (build_fn_info): ... here. Build new format data.
3307 (build_ctr_info_type, build_ctr_info_value): Remove.
3308 (build_info_type): New. Build new format data structure.
3309 (build_info): Adjust for new format data.
3310 (create_coverage): Likewise.
3311 * gcov-dump.c (tag_function): Recognize placeholders.
3313 2011-11-07 Georg-Johann Lay <avr@gjlay.de>
3315 * config/avr/constraints.md (Cm2): New constraint for int -2.
3316 * config/avr/avr.md (addqi3): Use it. New alternatives for +/-2.
3317 (*negqihi2): New insn.
3319 2011-11-07 H.J. Lu <hongjiu.lu@intel.com>
3321 * dwarf2cfi.c (dwarf2out_frame_debug_expr): Check
3322 HARD_FRAME_POINTER_REGNUM instead of hard_frame_pointer_rtx in Rule 18.
3324 2011-11-07 Jakub Jelinek <jakub@redhat.com>
3326 * config/i386/i386.c (ix86_expand_builtin): If gather mask
3327 argument is known to have all high bits set, pass pc_rtx as
3328 second argument to the expander instead of op0.
3329 * config/i386/sse.md (*avx2_gathersi<mode>_2,
3330 *avx2_gatherdi<mode>_2): New patterns.
3331 * config/i386/avx2intrin.h (_mm256_i32gather_pd,
3332 _mm256_i64gather_pd, _mm256_i32gather_ps): Set mask using
3333 _mm256_cmp_pd with zero vector arguments and _CMP_EQ_OQ instead of
3336 PR tree-optimization/50789
3337 * tree-vect-stmts.c (process_use): Add force argument, avoid
3338 exist_non_indexing_operands_for_use_p check if true.
3339 (vect_mark_stmts_to_be_vectorized): Adjust callers. Handle
3340 STMT_VINFO_GATHER_P.
3341 (gen_perm_mask): New function.
3342 (perm_mask_for_reverse): Use it.
3343 (reverse_vec_element): Rename to...
3344 (permute_vec_elements): ... this. Add Y and MASK_VEC arguments,
3345 generalize for any permutations.
3346 (vectorizable_load): Adjust caller. Handle STMT_VINFO_GATHER_P.
3347 * target.def (TARGET_VECTORIZE_BUILTIN_GATHER): New hook.
3348 * doc/tm.texi.in (TARGET_VECTORIZE_BUILTIN_GATHER): Document it.
3349 * doc/tm.texi: Regenerate.
3350 * tree-data-ref.c (initialize_data_dependence_relation,
3351 compute_self_dependence): No longer static.
3352 * tree-data-ref.h (initialize_data_dependence_relation,
3353 compute_self_dependence): New prototypes.
3354 * tree-vect-data-refs.c (vect_check_gather): New function.
3355 (vect_analyze_data_refs): Detect possible gather load data refs.
3356 * tree-vectorizer.h (struct _stmt_vec_info): Add gather_p field.
3357 (STMT_VINFO_GATHER_P): Define.
3358 (vect_check_gather): New prototype.
3359 * config/i386/i386-builtin-types.def: Add types for alternate
3361 * config/i386/sse.md (AVXMODE48P_DI): Remove.
3362 (VEC_GATHER_MODE): Rename mode_attr to...
3363 (VEC_GATHER_IDXSI): ... this.
3364 (VEC_GATHER_IDXDI, VEC_GATHER_SRCDI): New mode_attrs.
3365 (avx2_gathersi<mode>, *avx2_gathersi<mode>): Use <VEC_GATHER_IDXSI>
3366 instead of <VEC_GATHER_MODE>.
3367 (avx2_gatherdi<mode>): Use <VEC_GATHER_IDXDI> instead of
3368 <AVXMODE48P_DI> and <VEC_GATHER_SRCDI> instead of VEC_GATHER_MODE
3369 on src and mask operands.
3370 (*avx2_gatherdi<mode>): Likewise. Use VEC_GATHER_MODE iterator
3371 instead of AVXMODE48P_DI.
3372 (avx2_gatherdi<mode>256, *avx2_gatherdi<mode>256): Removed.
3373 * config/i386/i386.c (enum ix86_builtins): Add
3374 IX86_BUILTIN_GATHERALTSIV4DF, IX86_BUILTIN_GATHERALTDIV8SF,
3375 IX86_BUILTIN_GATHERALTSIV4DI and IX86_BUILTIN_GATHERALTDIV8SI.
3376 (ix86_init_mmx_sse_builtins): Create those builtins.
3377 (ix86_expand_builtin): Handle those builtins and adjust expansions
3378 of other gather builtins.
3379 (ix86_vectorize_builtin_gather): New function.
3380 (TARGET_VECTORIZE_BUILTIN_GATHER): Define.
3382 2011-11-07 Uros Bizjak <ubizjak@gmail.com>
3384 * config/i386/f16cintrin.h: Remove extra _X86INTRIN_H_INCLUDED check.
3386 2011-11-07 Tristan Gingold <gingold@adacore.com>
3388 * config.gcc (*-*-*vms*): Set c_target_objs, cxx_target_objs.
3389 * config/vms/t-vms: Add vms-c.o rule.
3390 * config/vms/vms-c.c: New file.
3391 * config/vms/vms-protos.h (vms_c_register_pragma): New prototype.
3392 * config/vms/vms.h (REGISTER_TARGET_PRAGMAS): Define.
3394 2011-11-07 Tristan Gingold <gingold@adacore.com>
3396 * config/alpha/vms.h (TARGET_OBJECT_SUFFIX,
3397 TARGET_EXECUTABLE_SUFFIX, TARGET_OS_CPP_BUILTINS,
3398 TARGET_ABI_OPEN_VMS, LONG_TYPE_SIZE, ADA_LONG_TYPE_SIZE,
3399 POINTER_SIZE, POINTERS_EXTEND_UNSIGNED): Move to config/vms/vms.h
3400 (SUBTARGET_OS_CPP_BUILTINS): Define.
3401 (TARGET_DEFAULT): Tune according to POINTER_SIZE.
3402 (MASK_RETURN_ADDR): Define in 64 bit mode.
3403 * config/ia64/vms.h: Likewise.
3404 * config/vms/vms.h: New file.
3405 * config/vms/vms64.h: New file.
3406 * config/alpha/vms64.h: Removed.
3407 * config/ia64/vms64.h: Removed.
3408 * config.gcc (alpha64-dec-*vms*, alpha*-dec-*vms*, ia64-hp-*vms*):
3409 Adjust for above change.
3411 2011-11-07 Enkovich Ilya <ilya.enkovich@intel.com>