Skip to content

R
riscv-gcc-1
Commit 192af6e8 by Richard Earnshaw
Options

[multiple changes] 

2012-02-28  Richard Earnshaw  <rearnsha@arm.com>

	* arm.c (aapcs_vfp_is_call_or_return_candidate): Only use the machine
	mode if there is no type information available.

2012-02-28  Ramana Radhakrishnan  <ramana.radhakrishnan@arm.com>

	* gcc.target/arm/vfp1.c (dg_do run): Run on all eabi variants.
	* gcc.target/arm/vfp2.c: Likewise.
	* gcc.target/arm/vfp3.c: Likewise.
	* gcc.target/arm/vfp4.c: Likewise.
	* gcc.target/arm/vfp5.c: Likewise.
	* gcc.target/arm/vfp6.c: Likewise.
	* gcc.target/arm/vfp7.c: Likewise.
	* gcc.target/arm/vfp8.c: Likewise.
	* gcc.target/arm/vfp9.c: Likewise.
	* gcc.target/arm/vfp10.c: Likewise.
	* gcc.target/arm/vfp11.c: Likewise.
	* gcc.target/arm/vfp12.c: Likewise.
	* gcc.target/arm/vfp13.c: Likewise.
	* gcc.target/arm/vfp14.c: Likewise.
	* gcc.target/arm/vfp15.c: Likewise.
	* gcc.target/arm/vfp16.c: Likewise.
	* gcc.target/arm/vfp17.c: Likewise.
	* gcc.target/arm/neon-constants.h: New file.
	* gcc.target/arm/neon-vect1.c: New test.
	* gcc.target/arm/neon-vect2.c: New test.
	* gcc.target/arm/neon-vect3.c: New test.
	* gcc.target/arm/neon-vect4.c: New test.
	* gcc.target/arm/neon-vect5.c: New test.
	* gcc.target/arm/neon-vect6.c: New test.
	* gcc.target/arm/neon-vect7.c: New test.
	* gcc.target/arm/neon-vect8.c: New test.

From-SVN: r184625
parent 7a8d8cad
Showing with 328 additions and 42 deletions
gcc/ChangeLog
2012-02-28 Richard Earnshaw <rearnsha@arm.com>
* arm.c (aapcs_vfp_is_call_or_return_candidate): Only use the machine
mode if there is no type information available.
2012-02-28 Thomas Koenig <tkoenig@gcc.gnu.org>
PR tree-optimization/53207
......
gcc/config/arm/arm.c
......@@ -4264,6 +4264,11 @@ use_vfp_abi (enum arm_pcs pcs_variant, bool is_double)
(TARGET_VFP_DOUBLE || !is_double));
}
/* Return true if an argument whose type is TYPE, or mode is MODE, is
suitable for passing or returning in VFP registers for the PCS
variant selected. If it is, then *BASE_MODE is updated to contain
a machine mode describing each element of the argument's type and
*COUNT to hold the number of such elements. */
static bool
aapcs_vfp_is_call_or_return_candidate (enum arm_pcs pcs_variant,
enum machine_mode mode, const_tree type,
......@@ -4271,9 +4276,20 @@ aapcs_vfp_is_call_or_return_candidate (enum arm_pcs pcs_variant,
{
enum machine_mode new_mode = VOIDmode;
if (GET_MODE_CLASS (mode) == MODE_FLOAT
|| GET_MODE_CLASS (mode) == MODE_VECTOR_INT
|| GET_MODE_CLASS (mode) == MODE_VECTOR_FLOAT)
/* If we have the type information, prefer that to working things
out from the mode. */
if (type)
{
int ag_count = aapcs_vfp_sub_candidate (type, &new_mode);
if (ag_count > 0 && ag_count <= 4)
*count = ag_count;
else
return false;
}
else if (GET_MODE_CLASS (mode) == MODE_FLOAT
|| GET_MODE_CLASS (mode) == MODE_VECTOR_INT
|| GET_MODE_CLASS (mode) == MODE_VECTOR_FLOAT)
{
*count = 1;
new_mode = mode;
......@@ -4283,15 +4299,6 @@ aapcs_vfp_is_call_or_return_candidate (enum arm_pcs pcs_variant,
*count = 2;
new_mode = (mode == DCmode ? DFmode : SFmode);
}
else if (type && (mode == BLKmode || TREE_CODE (type) == VECTOR_TYPE))
{
int ag_count = aapcs_vfp_sub_candidate (type, &new_mode);
if (ag_count > 0 && ag_count <= 4)
*count = ag_count;
else
return false;
}
else
return false;
......
gcc/testsuite/ChangeLog
2012-02-28 Ramana Radhakrishnan <ramana.radhakrishnan@arm.com>
* gcc.target/arm/vfp1.c (dg_do run): Run on all eabi variants.
* gcc.target/arm/vfp2.c: Likewise.
* gcc.target/arm/vfp3.c: Likewise.
* gcc.target/arm/vfp4.c: Likewise.
* gcc.target/arm/vfp5.c: Likewise.
* gcc.target/arm/vfp6.c: Likewise.
* gcc.target/arm/vfp7.c: Likewise.
* gcc.target/arm/vfp8.c: Likewise.
* gcc.target/arm/vfp9.c: Likewise.
* gcc.target/arm/vfp10.c: Likewise.
* gcc.target/arm/vfp11.c: Likewise.
* gcc.target/arm/vfp12.c: Likewise.
* gcc.target/arm/vfp13.c: Likewise.
* gcc.target/arm/vfp14.c: Likewise.
* gcc.target/arm/vfp15.c: Likewise.
* gcc.target/arm/vfp16.c: Likewise.
* gcc.target/arm/vfp17.c: Likewise.
* gcc.target/arm/neon-constants.h: New file.
* gcc.target/arm/neon-vect1.c: New test.
* gcc.target/arm/neon-vect2.c: New test.
* gcc.target/arm/neon-vect3.c: New test.
* gcc.target/arm/neon-vect4.c: New test.
* gcc.target/arm/neon-vect5.c: New test.
* gcc.target/arm/neon-vect6.c: New test.
* gcc.target/arm/neon-vect7.c: New test.
* gcc.target/arm/neon-vect8.c: New test.
2012-02-28 Richard Guenther <rguenther@suse.de>
PR tree-optimization/52402
......
gcc/testsuite/gcc.target/arm/aapcs/abitest.h
#define IN_FRAMEWORK
#ifdef VFP
......@@ -10,6 +11,13 @@
#define D6 48
#define D7 56
#ifdef NEON
#define Q0 D0
#define Q1 D2
#define Q2 D4
#define Q3 D6
#endif
#define S0 64
#define S1 68
#define S2 72
......@@ -27,23 +35,18 @@
#define S14 120
#define S15 124
#define R0 128
#define R1 132
#define R2 136
#define R3 140
#define STACK 144
#define CORE_REG_START 128
#else
#define CORE_REG_START 0
#endif
#define R0 0
#define R1 4
#define R2 8
#define R3 12
#define R0 CORE_REG_START
#define R1 (R0 + 4)
#define R2 (R1 + 4)
#define R3 (R2 + 4)
#define STACK (R3 + 4)
#define STACK 16
#endif
extern void abort (void);
......
gcc/testsuite/gcc.target/arm/aapcs/neon-constants.h 0 → 100644
#include "arm_neon.h"
const int32x4_t i32x4_constvec1 = { 1101, 1102, 1103, 1104};
const int32x4_t i32x4_constvec2 = { 2101, 2102, 2103, 2104};
#define ELEM(INDEX) .val[INDEX]
const int32x4x2_t i32x4x2_constvec1 = {ELEM(0) = {0xaddebccb,11,12,13},
ELEM(1) = {14, 15, 16, 17} };
const int32x4x2_t i32x4x2_constvec2 = { ELEM(0) = {0xaadebcca,11,12,13},
ELEM(1) = {140, 15, 16, 17}};
const int32x4x3_t i32x4x3_constvec1 = { ELEM(0) = {0xabbccdde,8, 9, 10},
ELEM(1) = {0xabcccdde, 26, 27, 28},
ELEM(2) = {0xaccccddf, 29, 30, 31}};
const int32x4x3_t i32x4x3_constvec2 = { ELEM(0) = {0xbccccdd0,8, 9, 10},
ELEM(1) = {0xbdfe1000, 26, 27, 28},
ELEM(2) = {0xaccccddf, 29, 30, 31}};
const float32x4x2_t f32x4x2_constvec1 =
{ ELEM(0) = { 7.101f, 0.201f, 0.301f, 0.401f} ,
ELEM(1) = { 8.101f, 0.501f, 0.601f, 0.701f} };
const float32x4x2_t f32x4x2_constvec2 =
{ ELEM(0) = { 11.99f , 11.21f, 1.27f, 8.74f},
ELEM(1) = { 13.45f , 1.23f ,1.24f, 1.26f}};
const int32x2_t i32x2_constvec1 = { 1283, 1345 };
const int32x2x2_t i32x2x2_constvec1 = { ELEM(0) = { 0xabcdefab, 32 },
ELEM(1) = { 0xabcdefbc, 33 }};
gcc/testsuite/gcc.target/arm/aapcs/neon-vect1.c 0 → 100644
/* Test AAPCS layout (VFP variant for Neon types) */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm_neon_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-add-options arm_neon } */
#ifndef IN_FRAMEWORK
#define VFP
#define NEON
#define TESTFILE "neon-vect1.c"
#include "neon-constants.h"
#include "abitest.h"
#else
ARG(int32x4_t, i32x4_constvec2, Q0) /* D0, D1 */
ARG(float, 3.0f, S4) /* D2, Q1 */
ARG(int32x4x2_t, i32x4x2_constvec1, Q2) /* Q2, Q3 - D4-D6 , s5-s12 */
ARG(double, 12.0, D3) /* Backfill this particular argument. */
ARG(int32x4x2_t, i32x4x2_constvec2, STACK)
ARG(float, 5.0f, STACK+sizeof(int32x4x2_t)) /* No backfill allowed. */
LAST_ARG(int, 3, R0)
#endif
gcc/testsuite/gcc.target/arm/aapcs/neon-vect2.c 0 → 100644
/* Test AAPCS layout (VFP variant for Neon types) */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm_neon_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-add-options arm_neon } */
#ifndef IN_FRAMEWORK
#define VFP
#define NEON
#define TESTFILE "neon-vect2.c"
#include "neon-constants.h"
#include "abitest.h"
#else
ARG(int32x4_t, i32x4_constvec2, Q0) /* D0, D1. */
ARG(float, 3.0f, S4) /* D2, Q1 occupied. */
LAST_ARG(int, 3, R0)
#endif
gcc/testsuite/gcc.target/arm/aapcs/neon-vect3.c 0 → 100644
/* Test AAPCS layout (VFP variant for Neon types) */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm_neon_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-add-options arm_neon } */
#ifndef IN_FRAMEWORK
#define VFP
#define NEON
#define TESTFILE "neon-vect3.c"
#include "neon-constants.h"
#include "abitest.h"
#else
ARG(int32x4_t, i32x4_constvec2, Q0) /* D0, D1 */
ARG(float, 3.0f, S4) /* D2, Q1 */
ARG(int32x4x2_t, i32x4x2_constvec1, Q2) /* Q2, Q3 - D4-D6 , s5-s12 */
ARG(int32x4x2_t, i32x4x2_constvec2, STACK)
ARG(double, 11.0, STACK+sizeof(int32x4x2_t)) /* No backfill in D3. */
LAST_ARG(int, 3, R0)
#endif
gcc/testsuite/gcc.target/arm/aapcs/neon-vect4.c 0 → 100644
/* Test AAPCS layout (VFP variant for Neon types) */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm_neon_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-add-options arm_neon } */
#ifndef IN_FRAMEWORK
#define VFP
#define NEON
#define TESTFILE "neon-vect4.c"
#include "neon-constants.h"
#include "abitest.h"
#else
ARG(int32x4_t, i32x4_constvec2, Q0) /* D0, D1 */
ARG(float, 3.0f, S4) /* D2, Q1 */
ARG(int32x4x2_t, i32x4x2_constvec1, Q2) /* Q2, Q3 - D4-D6 , s5-s12 */
ARG(double, 12.0, D3) /* Backfill this particular argument. */
ARG(float, 5.0f, S5) /* Backfill in S5. */
ARG(int32x4x2_t, i32x4x2_constvec2, STACK)
LAST_ARG(int, 3, R0)
#endif
gcc/testsuite/gcc.target/arm/aapcs/neon-vect5.c 0 → 100644
/* Test AAPCS layout (VFP variant for Neon types) */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm_neon_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-add-options arm_neon } */
#ifndef IN_FRAMEWORK
#define VFP
#define NEON
#define TESTFILE "neon-vect5.c"
#include "neon-constants.h"
#include "abitest.h"
#else
ARG(int32x4_t, i32x4_constvec2, Q0) /* D0, D1 */
ARG(float, 3.0f, S4) /* D2, Q1 */
ARG(float32x4x2_t, f32x4x2_constvec1, Q2) /* Q2, Q3 - D4-D6 , s5-s12 */
ARG(double, 12.0, D3) /* Backfill this particular argument. */
ARG(int32x4x2_t, i32x4x2_constvec2, STACK)
ARG(float, 5.0f, STACK+sizeof(int32x4x2_t)) /* No backfill allowed. */
LAST_ARG(int, 3, R0)
#endif
gcc/testsuite/gcc.target/arm/aapcs/neon-vect6.c 0 → 100644
/* Test AAPCS layout (VFP variant for Neon types) */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm_neon_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-add-options arm_neon } */
#ifndef IN_FRAMEWORK
#define VFP
#define NEON
#define TESTFILE "neon-vect6.c"
#include "neon-constants.h"
#include "abitest.h"
#else
ARG(int32x4_t, i32x4_constvec2, Q0) /* D0, D1 */
ARG(int32x4x3_t, i32x4x3_constvec1, Q1) /* Q1, Q2, Q3 */
ARG(int32x4x3_t, i32x4x3_constvec2, STACK)
LAST_ARG(int, 3, R0)
#endif
gcc/testsuite/gcc.target/arm/aapcs/neon-vect7.c 0 → 100644
/* Test AAPCS layout (VFP variant for Neon types) */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm_neon_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-add-options arm_neon } */
#ifndef IN_FRAMEWORK
#define VFP
#define NEON
#define TESTFILE "neon-vect7.c"
#include "neon-constants.h"
#include "abitest.h"
#else
ARG(float, 24.3f, S0) /* S0 , D0, Q0 */
ARG(int32x4x3_t, i32x4x3_constvec1, Q1) /* Q1, Q2, Q3 */
ARG(double, 25.6, D1)
ARG(float, 12.67f, S1)
ARG(int32x4x3_t, i32x4x3_constvec2, STACK)
ARG(double, 2.47, STACK+sizeof(int32x4x3_t))
LAST_ARG(int, 3, R0)
#endif
gcc/testsuite/gcc.target/arm/aapcs/neon-vect8.c 0 → 100644
/* Test AAPCS layout (VFP variant for Neon types) */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm_neon_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-add-options arm_neon } */
#ifndef IN_FRAMEWORK
#define VFP
#define NEON
#define TESTFILE "neon-vect8.c"
#include "neon-constants.h"
#include "abitest.h"
#else
ARG(float, 24.3f, S0) /* S0 , D0, Q0 */
ARG(int32x2_t, i32x2_constvec1, D1) /* D1 */
ARG(double, 25.6, D2)
ARG(float, 12.67f, S1)
ARG(int32x4x3_t, i32x4x3_constvec2, STACK)
ARG(double, 2.47, STACK+sizeof(int32x4x3_t))
LAST_ARG(int, 3, R0)
#endif
gcc/testsuite/gcc.target/arm/aapcs/vfp1.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp10.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp11.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp12.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp13.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp14.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp15.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp16.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp17.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp2.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp3.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp4.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp5.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp6.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp7.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp8.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
gcc/testsuite/gcc.target/arm/aapcs/vfp9.c
/* Test AAPCS layout (VFP variant) */
/* { dg-do run { target arm*-*-eabi* } } */
/* { dg-do run { target arm*-*-*eabi* } } */
/* { dg-require-effective-target arm_hard_vfp_ok } */
/* { dg-require-effective-target arm32 } */
/* { dg-options "-O -mfpu=vfp -mfloat-abi=hard" } */
......
Markdown is supported
0% or
You are about to add 0 people to the discussion. Proceed with caution.
Finish editing this message first!
Please register or to comment