Discussion :

[InticIntic]

Bonjour,

Je veux écrire un code assembleur (utilisant le inlining) dans une boucle for parallèle.

Est ce qu'il y a un moyen de le faire et ne pas avoir de segmentation fault

Code :

Sélectionner tout - Visualiser dans une fenêtre à part

1
2
3
4
5
6
 
#pragma omp parallel for
for (i = 0; i < 10; i++)
{
	asm volatile("movss 0(%rsi), %xmm0");
}

J'ai pensé à faire quelque chose du genre

Code :

Sélectionner tout - Visualiser dans une fenêtre à part

1
2
3
4
 
register double int x asm("%xmm0");
int r asm("0(%rsi)");
asm volatile("movss %0, %1" : "=r"(x) : "m"(r));

et déclarer les variables utilisées comme des variable private mais cette syntaxe n'est pas acceptée.

[Obsidian]

Hmm. Je n'ai jamais eu affaire à OpenMP, donc je ne suis probablement pas en mesure de t'aider. Mais cela dit, comment est initialisé RSI ? Es-tu sûr que l'adresse qu'il contient est accessible par tout les threads, dans un premier temps ?

[InticIntic]

Je pense que ce n'est pas ça qui pose problème sinon ça n'aurait pas marché pour un seul thread (sans #pragma...).
Je veux juste savoir est ce que cette ligne

Code :

Sélectionner tout - Visualiser dans une fenêtre à part

register int x asm("%xmm0");

associe le registre xmm0 à la variable x, parce que le code assembleur généré n'est pas celui que je veux.

[Obsidian]

Je pense que ce n'est pas ça qui pose problème sinon ça n'aurait pas marché pour un seul thread (sans #pragma...).

Ça dépend comment sont lancés les threads, justement. S'ils ne partagent pas leur plan mémoire comme on pourrait s'y attendre et que ce sont en fait des processus distincts, le comportement serait cohérent.

Je veux juste savoir est ce que cette ligne

Code :

Sélectionner tout - Visualiser dans une fenêtre à part

register double int x asm("%xmm0");

associe le registre xmm0 à la variable x, parce que le code assembleur généré n'est pas celui que je veux.

À part « double int » qui ne compilera pas en l'état, ça fonctionne bien chez moi.

[InticIntic]

oui le double int est une erreur de frappe sinon

Code :

Sélectionner tout - Visualiser dans une fenêtre à part

1
2
3
register double x asm("%xmm0");
int r asm("0(%rsi)");
asm volatile("movss %0, %1" : "=r"(x) : "m"(r));

à la compilation voila l'erreur que j'ai
Error: operand type mismatch for `movss'
ça ne marche pas aussi pour le movsd, movaps, ...