L-321agn: diverse Watchdogs

marsbewohner · Beitrag von **marsbewohner** » 24 Jun 2011, 22:17

Hallo zusammen,

ein L-321AGN raubt mir im Moment den Nerv, da sich das Gerät ohne ersichtlichen Grund und selbst im absoluten Leerlauf ohne WLAN Betrieb in diverse Watchdogs verabschidet. Kann jemand aus den folgenden Daten eventuell herauslesen weshalb, eventuell ein Speicherschaden?

[TraceStarted] 2011/06/08 15:41:50,022
Used config:
# Show commands
show bootlog

[ShowCmd] 2011/06/08 15:41:50,745
Result of command: "show bootlog "
Boot log (8192 Bytes):
0 destroyed (ptr->size or ptr->next)
previous MCB @0x0193e1a0 has owner @0x012d0700 (FREE)
-> see following LCOS-Watchdog

****

06/04/2011 18:10:35 LCOS-Watchdog
Task name = IT Type=mem_hdrchk_panic(xIosMemAll): MCB destroyed (ptr->size or ptr->next)
Code=0x0193e200 Task=011c46c0/00000000 Nest=0x00000000

R00=0x00861510 SP =0x011c5690 R02=0x00b60000 R03=0x00000044
R04=0x011c5658 R05=0x00aa2ad0 R06=0x00000000 R07=0x00000000
R08=0x00000016 R09=0x00000000 R10=0x00000000 R11=0x011c94b4
R12=0x42440024 R13=0x010e0a78 R14=0x010e0000 R15=0x010e0000
R16=0x010e0000 R17=0x00a84d30 R18=0x00aa2704 R19=0x01079fd8
R20=0x010e0000 R21=0x010e0000 R22=0x011c9354 R23=0x0000040e
R24=0x00000028 R25=0x00a84d30 R26=0x00000003 R27=0x0193e200
R28=0x00aa2c60 R29=0x00aa2c78 R30=0x01209c1c R31=0x0193e1a0

CR =0x22440024 XER =0x20000000 LR =0x00861510 CTR =0x008739b0
DAR =0x00000000 DSR =0x00000000 TBL =0x209f5b26 TBU =0x00000090
IBCR=0x00e20000 DBCR=0x00e20000 DBR =0x01cd92ef DBR2=0x03ffffc7
HID0=0xc090c000 HID1=0x0c000000 HID2=0x04e40000 MBAR=0x00000000
SPR0=0x238f9bdb SPR1=0x011c3248 SPR2=0x00000004 SPR3=0x000010b2
SPR4=0x00000000 SPR5=0x00000000 SPR6=0x00000000 SPR7=0x00000005
TGR0=0x00a02e9c TGR1=0x00a02011 TGR2=0x002280c0 TGR3=0x400a90b2

SRR0(PC) =0x00861554
SRR1(MSR)=0x000090b2
possible Error location /opt/jobs/even850-nHIBjR/top/lcos/ios/common.src/iosmem.c : 3155

Memory dump (256 bytes):
Adr:= 0193e200
Len:= 00000100
0193E200: 01 93 E7 00 01 93 E1 A0 00 00 00 29 01 2B 9B E1 | ........ ...).+..
0193E210: 00 00 00 00 00 AA 67 10 00 00 00 38 53 54 00 58 | ......g. ...8ST.X
0193E220: 01 56 46 E0 00 00 00 00 FF 00 00 00 00 00 00 00 | .VF..... ........
0193E230: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E240: 00 00 00 00 00 00 00 04 FF 34 0B 01 03 20 01 2C | ........ .4... .,
0193E250: 01 05 00 FF 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E260: 01 93 E7 00 01 93 E2 00 00 00 00 25 01 16 87 08 | ........ ...%....
0193E270: 00 00 00 00 00 AA 69 68 00 00 00 2B 53 54 00 A0 | ......ih ...+ST..
0193E280: 30 06 0E 2B 06 01 04 01 92 34 0B 01 30 01 08 8A | 0..+.... .4..0...
0193E290: 02 04 00 30 06 0E 2B 06 01 04 01 92 34 0B 01 03 | ...0..+. ....4...
0193E2A0: 20 01 1E 06 02 01 00 30 06 0E 2B 06 01 04 01 92 | ......0 ..+.....
0193E2B0: 34 0B 01 03 20 01 1E 05 02 02 0E 11 30 06 0E 2B | 4... ... ....0..+
0193E2C0: 06 01 04 01 92 34 0B 01 03 20 01 1E 04 02 02 07 | .....4.. . ......
0193E2D0: 7A 30 06 0E 2B 06 01 04 01 92 34 0B 01 03 20 01 | z0..+... ..4... .
0193E2E0: 1E 03 02 01 00 30 06 0E 2B 06 01 04 01 92 34 0B | .....0.. +.....4.
0193E2F0: 01 03 20 01 1E 02 02 01 00 30 06 0E 2B 06 01 04 | .. ..... .0..+...

Stack dump (1024 bytes):
Adr:= 011c5690
Len:= 00000400
011C5690: 01 1C 56 C0 00 86 15 10 00 00 00 28 01 1C 95 78 | ..V..... ...(...x
011C56A0: 01 1C 93 54 01 10 6F 78 00 A8 4D 30 00 00 04 0E | ...T..ox ..M0....
011C56B0: 49 54 54 54 00 00 00 08 01 1C 94 54 01 1C 46 7C | ITTT.... ...T..F|
011C56C0: 01 1C 57 08 00 86 26 50 01 0D 95 90 02 00 00 24 | ..W...&P .......$
011C56D0: 01 0E 00 00 01 1C 57 C8 01 0E 00 00 01 06 DB 10 | ......W. ........
011C56E0: 01 0D 95 90 01 1C 46 B0 01 1C 46 94 01 10 6F 78 | ......F. ..F...ox
011C56F0: 49 54 54 54 00 00 00 3C 49 54 54 54 00 00 00 08 | ITTT...< ITTT....
011C5700: 00 00 00 01 01 1C 46 7C 01 1C 57 20 00 7B 79 0C | ......F| ..W .{y.
011C5710: 00 00 00 00 00 00 00 01 00 00 90 B2 00 7C 24 B8 | ........ .....|$.
011C5720: 01 1C 57 70 00 7C 24 CC 00 00 00 00 00 00 00 00 | ..Wp.|$. ........
011C5730: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5740: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5750: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5760: 00 00 00 00 00 00 00 02 00 00 00 00 00 7C 21 34 | ........ .....|!4
011C5770: 01 1C 57 88 00 7B 94 64 00 00 00 00 00 00 00 00 | ..W..{.d ........
011C5780: 00 00 00 00 00 00 00 00 00 00 00 00 00 7B B7 70 | ........ .....{.p
011C5790: 55 55 55 55 55 55 55 55 00 00 00 00 FF 00 03 01 | UUUUUUUU ........
011C57A0: 00 00 00 00 00 00 00 01 FF 00 0A 01 00 00 00 00 | ........ ........
011C57B0: 00 00 00 01 00 00 02 BC 00 00 48 79 0D 09 05 00 | ........ ..Hy....
011C57C0: 00 00 00 00 52 E8 E1 D2 01 1C 57 C8 01 1C 57 C8 | ....R... ..W...W.
011C57D0: 00 00 00 00 00 00 00 00 00 00 00 00 01 1C 46 C0 | ........ ......F.
011C57E0: 00 00 00 00 C9 28 B0 91 93 B0 00 00 00 00 00 00 | .....(.. ........
011C57F0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5800: 01 B5 5E 80 00 00 00 00 00 00 00 00 00 00 00 00 | ..^..... ........
011C5810: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5820: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5830: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5840: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5850: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5860: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5870: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5880: 00 00 00 00 00 00 00 00 00 00 00 00 01 22 AE 60 | ........ .....".`
011C5890: 01 B5 57 40 01 B5 57 40 01 B5 59 00 00 00 00 00 | ..W@..W@ ..Y.....
011C58A0: 01 B5 5A 20 01 B5 5B A0 00 00 00 00 01 B5 57 E0 | ..Z ..[. ......W.
011C58B0: 01 B5 57 40 01 06 89 B4 00 A8 FA 34 01 AD A6 20 | ..W@.... ...4...
011C58C0: 00 00 00 00 01 B3 D8 40 00 00 00 00 00 00 00 00 | .......@ ........
011C58D0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C58E0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C58F0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5900: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5910: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5920: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5930: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5940: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5950: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5960: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5970: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5980: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5990: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C59A0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C59B0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C59C0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C59D0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C59E0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C59F0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5A00: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5A10: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5A20: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5A30: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5A40: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
011C5A50: 00 00 00 00 02 00 00 01 01 1C 5E 54 02 00 00 02 | ........ ..^T....
011C5A60: 01 1C 5E 74 02 00 00 03 01 1C 5E 94 02 00 00 04 | ..^t.... ..^.....
011C5A70: 01 1C 5E B4 02 00 00 05 01 1C 5E D4 02 00 00 06 | ..^..... ..^.....
011C5A80: 01 1C 5E F4 02 00 00 07 01 1C 5F 14 02 00 00 08 | ..^..... .._.....
largest available memory block: 36859136 bytes

DEVICE: LANCOM L-321agn Wireless
HW-RELEASE: B
VERSION: 8.50.0091Rel / 08.04.2011

****

06/04/2011 18:10:40 System boot after LCOS-Watchdog

DEVICE: LANCOM L-321agn Wireless
HW-RELEASE: B
VERSION: 8.50.0091Rel / 08.04.2011

MCB chain destroyed, see LCOS-Watchdog below
last MCB: 0193e100
last->next: 0193e1e0
last->prev: 0193e020
last->size: 7 => 0193e1e0
last->owner: 019bb640
last->file: /opt/jobs/even850-nHIBjR/top/lcos/wlan/common.src/reorder.c
last->line: 329
last->job: WI
UpperBound: 124
free state: 0
owner name: WI
first 192 Bytes of MCB
Adr:= 0193e100
Len:= 000000c0
0193E100: 01 93 E1 E0 01 93 E0 20 00 00 00 07 01 9B B6 40 | ....... .......@
0193E110: 00 00 00 00 00 A6 80 48 00 00 01 49 57 49 00 7C | .......H ...IWI.|
0193E120: 00 00 01 45 00 00 01 84 00 00 00 00 00 00 0F FF | ...E.... ........
0193E130: 00 00 01 00 00 00 00 00 00 00 00 00 54 4D 00 00 | ........ ....TM..
0193E140: 00 00 00 28 00 00 00 00 00 00 00 00 FF FF FF FF | ...(.... ........
0193E150: 00 00 00 00 00 00 00 00 08 DA 1F B2 01 93 E1 3C | ........ .......<
0193E160: 00 00 00 00 01 93 E1 4C 01 9B B6 40 00 00 00 00 | .......L ...@....
0193E170: 57 49 46 41 00 01 F8 00 00 00 00 04 00 00 00 F0 | WIFA.... ........
0193E180: 00 00 00 E9 FF 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E190: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E1A0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E1B0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........

last 128 Bytes of MCB
Adr:= 0193e160
Len:= 00000080
0193E160: 00 00 00 00 01 93 E1 4C 01 9B B6 40 00 00 00 00 | .......L ...@....
0193E170: 57 49 46 41 00 01 F8 00 00 00 00 04 00 00 00 F0 | WIFA.... ........
0193E180: 00 00 00 E9 FF 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E190: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E1A0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E1B0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E1C0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E1D0: 00 00 00 00 00 00 00 00 FF 00 00 00 00 00 00 00 | ........ ........

first 64 Bytes of next
Adr:= 0193e1e0
Len:= 00000040
0193E1E0: 01 93 E2 C0 01 93 E1 04 00 00 00 07 01 9B B6 40 | ........ .......@
0193E1F0: 00 00 00 00 00 A6 80 48 00 00 01 49 57 49 00 7C | .......H ...IWI.|
0193E200: 00 00 0F 19 00 00 0F 58 00 00 00 01 00 00 0F FF | .......X ........
0193E210: 00 00 01 00 00 00 00 00 00 00 00 00 54 4D 00 00 | ........ ....TM..
****

06/07/2011 09:43:47 LCOS-Watchdog
Task name = ST Type=xIosMemTotal: MCB destroyed (act->next->prev)
Code=0x0193e1e0 Task=01168708/00000000 Nest=0x00000000

R00=0x0085eda4 SP =0x01170840 R02=0x00b60000 R03=0x0000002d
R04=0x011707f8 R05=0x00aa26d8 R06=0x00000000 R07=0x00000000
R08=0x0000001f R09=0x00000000 R10=0x00000000 R11=0x011c9381
R12=0x42004022 R13=0x010e0a78 R14=0x01164198 R15=0x011684ec
R16=0x010e0000 R17=0x0117099c R18=0x01170998 R19=0x00000004
R20=0x00000000 R21=0x00aa275c R22=0x00aa276c R23=0x010e0000
R24=0x010e0000 R25=0x000011a2 R26=0x00aa2704 R27=0x0193e1e0
R28=0x00aa2794 R29=0x010e0000 R30=0x010e0000 R31=0x0193e100

CR =0x22004022 XER =0x20000000 LR =0x0085eda4 CTR =0x008739b0
DAR =0x00000000 DSR =0x00000000 TBL =0xceb2d71b TBU =0x0000077f
IBCR=0x00e20000 DBCR=0x00e20000 DBR =0x01db9e6f DBR2=0x03ffffc7
HID0=0xc090c000 HID1=0x0c000000 HID2=0x04e40000 MBAR=0x00000000
SPR0=0x00000030 SPR1=0x00000070 SPR2=0x00000020 SPR3=0x000010b2
SPR4=0x00000000 SPR5=0x00000000 SPR6=0x00000000 SPR7=0x00000005
TGR0=0x00a482dc TGR1=0x00a48011 TGR2=0x00229240 TGR3=0x200a90b2

SRR0(PC) =0x0085edd8
SRR1(MSR)=0x000090b2
possible Error location /opt/jobs/even850-nHIBjR/top/lcos/ios/common.src/iosmem.c : 4514

Memory dump (256 bytes):
Adr:= 0193e1e0
Len:= 00000100
0193E1E0: 01 93 E2 C0 01 93 E1 04 00 00 00 07 01 9B B6 40 | ........ .......@
0193E1F0: 00 00 00 00 00 A6 80 48 00 00 01 49 57 49 00 7C | .......H ...IWI.|
0193E200: 00 00 0F 19 00 00 0F 58 00 00 00 01 00 00 0F FF | .......X ........
0193E210: 00 00 01 00 00 00 00 00 00 00 00 00 54 4D 00 00 | ........ ....TM..
0193E220: 00 00 00 28 00 00 00 00 00 00 00 00 FF FF FF FF | ...(.... ........
0193E230: 00 00 00 00 00 00 00 00 00 00 00 00 01 93 E2 1C | ........ ........
0193E240: 00 00 00 00 01 93 E2 0D 00 00 00 00 00 00 00 00 | ........ ........
0193E250: 57 49 46 41 00 01 E2 00 00 00 00 00 00 00 01 9C | WIFA.... ........
0193E260: 00 00 01 99 FF 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E270: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E280: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E290: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E2A0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
0193E2B0: 00 00 00 00 00 00 00 00 FF 00 00 00 00 00 00 00 | ........ ........
0193E2C0: 01 93 E3 A0 01 93 E1 E0 00 00 00 07 01 9B B6 40 | ........ .......@
0193E2D0: 00 00 00 00 00 A6 80 48 00 00 01 49 57 49 00 7C | .......H ...IWI.|

Stack dump (1024 bytes):
Adr:= 01170840
Len:= 00000400
01170840: 01 17 08 68 00 85 ED A4 00 AA 27 94 01 1C 94 54 | ...h.... ..'....T
01170850: 00 AA 27 04 01 0E 00 00 00 00 00 00 01 93 E1 00 | ..'..... ........
01170860: 01 93 E0 20 01 17 08 A8 01 17 08 A0 00 85 F0 24 | ... .... .......$
01170870: 00 AA 79 0C 00 00 00 00 00 00 00 00 01 4F 67 C0 | ..y..... .....Og.
01170880: 00 00 00 00 00 00 00 00 00 00 00 04 01 B5 78 F8 | ........ ......x.
01170890: 00 8A 82 88 01 B5 78 F8 00 00 00 00 01 B5 4B C0 | ......x. ......K.
011708A0: 01 17 08 D8 00 8A 82 A4 00 00 0E 58 00 00 00 02 | ........ ...X....
011708B0: 00 01 08 03 00 03 75 09 00 00 01 E7 00 00 00 02 | ......u. ........
011708C0: 00 00 01 66 00 00 22 FF 01 17 08 D8 00 00 40 02 | ...f..". ......@.
011708D0: 01 17 08 F0 00 88 51 4C 01 17 09 20 00 90 1A 14 | ......QL ... ....
011708E0: 00 AA 27 04 22 00 40 88 00 00 00 00 00 00 00 00 | ..'.".@. ........
011708F0: 00 00 00 00 00 00 00 00 00 00 00 05 01 B5 4B C0 | ........ ......K.
01170900: 00 00 00 00 01 16 84 EC 01 08 CF A4 00 00 00 00 | ........ ........
01170910: 00 00 00 33 01 B5 4B C0 01 CA 3C C1 01 16 84 3C | ...3..K. ..<....<
01170920: 01 17 09 90 00 67 01 B4 00 00 20 88 00 00 00 00 | .....g.. .. .....
01170930: 01 17 32 74 01 CE 27 A0 01 0E 00 00 01 17 09 58 | ..2t..'. .......X
01170940: 00 00 00 01 00 00 00 00 00 00 00 01 00 00 00 06 | ........ ........
01170950: 01 17 09 80 00 87 D3 D8 06 17 09 70 01 C7 14 40 | ........ ...p...@
01170960: 01 17 09 80 00 00 00 34 01 4F 67 C0 00 00 00 34 | .......4 .Og....4
01170970: 01 17 32 74 00 00 00 33 01 4F 67 C0 01 CA 3C C1 | ..2t...3 .Og...<.
01170980: 01 16 87 08 00 00 00 01 00 00 00 01 01 16 84 3C | ........ .......<
01170990: 01 17 09 F0 00 67 1A 08 00 0C 09 B8 00 00 00 00 | .....g.. ........
011709A0: 01 4F 67 C0 01 B6 F2 A0 42 00 20 84 01 17 32 74 | .Og..... B. ...2t
011709B0: 00 00 00 FF 01 17 0B 20 01 17 32 58 00 00 00 01 | ....... ..2X....
011709C0: 01 17 0B E4 01 17 32 74 00 00 00 4F 00 00 00 00 | ......2t ...O....
011709D0: 00 00 00 0B 01 0D 90 C8 01 CA 3C A5 00 A5 75 5C | ........ ..<...u\
011709E0: 00 00 00 0C 01 16 84 3C 00 00 00 44 01 CA 3C B0 | .......< ...D..<.
011709F0: 01 17 0A 10 00 67 23 D4 01 CA 3C A5 01 B5 4B C0 | .....g#. ..<...K.
01170A00: 00 00 00 44 01 CA 3C B0 01 16 41 98 01 16 84 3C | ...D..<. ..A....<
01170A10: 01 17 0A D0 00 67 3E C0 01 17 0A 20 00 00 00 00 | .....g>. ... ....
01170A20: 01 17 0A 28 01 16 84 72 00 09 0A 38 00 00 0C 48 | ...(...r ...8...H
01170A30: 00 00 90 B2 00 88 51 4C 01 17 0A D0 00 67 48 70 | ......QL .....gHp
01170A40: 00 AA 77 10 00 AA 77 28 01 C7 98 C0 00 88 46 18 | ..w...w( ......F.
01170A50: 00 00 00 00 01 2A 46 00 01 17 0A 80 00 86 C9 64 | .....*F. .......d
01170A60: 00 00 90 B2 00 86 CB 7C 01 17 0A 80 00 67 9F 14 | .......| .....g..
01170A70: 01 2A 45 E0 01 C7 30 E0 01 CC 33 80 01 91 E6 40 | .*E...0. ..3....@
01170A80: 01 17 0A D0 00 67 9D 9C 01 1C 94 54 22 00 00 22 | .....g.. ...T".."
01170A90: 01 05 63 78 01 17 0B 20 01 17 32 58 01 17 32 40 | ..cx... ..2X..2@
01170AA0: 01 17 0B E4 01 16 87 08 01 0D BA D8 00 00 00 00 | ........ ........
01170AB0: 00 A5 75 5C 01 16 4D 94 01 16 84 44 01 CA 3C A0 | ..u\..M. ...D..<.
01170AC0: 01 17 0A E0 00 00 00 53 01 16 47 3C 01 CA 3C A1 | .......S ..G<..<.
01170AD0: 01 17 0B 18 00 67 4A 4C 00 52 0B 18 00 00 00 00 | .....gJL .R......
01170AE0: 00 00 00 04 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01170AF0: C0 A8 64 05 01 41 C9 C0 00 00 01 EA 01 17 31 40 | ..d..A.. ......1@
01170B00: 01 17 87 08 00 00 00 00 01 17 87 08 00 00 60 B1 | ........ ......`.
01170B10: 01 45 E9 C0 01 41 C9 C0 01 17 0B 90 00 67 74 C4 | .E...A.. .....gt.
01170B20: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01170B30: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01170B40: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01170B50: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01170B60: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01170B70: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01170B80: 00 00 00 00 01 17 32 9C 00 A4 A7 04 01 17 32 1C | ......2. ......2.
01170B90: 01 17 0B 98 00 7B 7B 10 01 17 0B B0 00 63 BA C0 | .....{{. .....c..
01170BA0: 00 00 00 00 00 00 00 01 00 00 00 00 00 67 78 4C | ........ .....gxL
01170BB0: 01 17 0B B8 00 67 78 90 01 17 0B D0 00 7B 94 64 | .....gx. .....{.d
01170BC0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01170BD0: 00 00 00 00 00 7B B7 70 55 55 55 55 55 55 55 55 | .....{.p UUUUUUUU
01170BE0: 00 00 00 00 00 AA 48 B0 00 A0 82 60 01 17 0B E8 | ......H. ...`....
01170BF0: 01 17 0B E8 00 00 00 00 00 00 00 02 00 00 00 00 | ........ ........
01170C00: 51 42 00 00 00 00 00 00 01 55 7D C0 01 55 7E 40 | QB...... .U}..U~@
01170C10: 51 45 00 00 00 AA 48 B0 00 A0 82 60 01 17 0C 18 | QE....H. ...`....
01170C20: 01 17 0C 18 00 00 00 00 00 00 00 02 00 00 00 00 | ........ ........
01170C30: 51 42 00 00 00 00 00 00 01 55 7E 80 01 55 7F 00 | QB...... .U~..U..
largest available memory block: 35938688 bytes

DEVICE: LANCOM L-321agn Wireless
HW-RELEASE: B
VERSION: 8.50.0091Rel / 08.04.2011

****

06/07/2011 09:43:52 System boot after LCOS-Watchdog

DEVICE: LANCOM L-321agn Wireless
HW-RELEASE: B
VERSION: 8.50.0091Rel / 08.04.2011

Danke & Gruß,

alf29 · Beitrag von **alf29** » 25 Jun 2011, 09:59

Moin,

Speicherschaden ja, aber nicht im hardware-mäßigen Sinne. Solche Meldungen bedeuten
üblicherweise einen Fehler in der dynamischen Speicherverwaltung, d.h. irgendwo hat jemand
einen Speicherblock doppelt freigegeben oder über die Grenzen eines Blocks hinausgeschrieben.
Das Problem an der Sache ist, daß der im os_panic gemeldete "Schuldige" der Task
ist, in dessen Kontext der zerstörte Heap aufgefallen ist, und das ist häufig nicht derjenige, der
den Schaden angerichtet hat. Das macht diese Form von Bugs so schwer zu lösen, und die
Entwicklung kann das in den seltensten Fällen, ohne eine Nachstellmöglichkeit zu bekommen oder
die Fehlersituation einzugrenzen.

Bei uns im Hausnetz kenne ich diese Bugs mit der 8.50 zu Beispiel nicht. Es wäre zu fragen, ob
diese Abstürze bei Dir immer die gleichen Geräte betreffen, oder ob sie erst auftreten, wo eine
bestimmte Art von Clients zum Einsatz kommt. Bei einem anderen Forumsteilnehmer war es
z.B. ein RADIUS-Server, der ungewöhnlich große 802.1x/EAP-Pakete verschickt hat.

Und zum Abschluß noch eine ganz wilde Spekulation: LANCOM-Firmwaren bis einschließlich zur
8.50er-Release enthalten einen Fehler, daß sie mit A-MSDU-Aggregierung nicht umgehen
können. Das ist eine andere Form, kleinere Pakete zwecks Effizienzsteigerung in größere
zusammenzufassen (im Gegensatz zu der gängigeren A-MPDU-Aggregierung), die nur recht
selten verwendet wird (im LCOS gar nicht...). Wir haben sie zum ersten Mal bei bestimmten
Ralink-basierten Clients im Rahmen der WiFi-Zulassung gesehen, die aktuelle 8.50, von der
Du hoffentlich vom Support inzwischen die Ausgabe fürs richtige Gerät bekommen hast

,
behandelt empfangene A-MSDUs korrekt. Ich möchte nicht ausschließen, daß es im Umgang
mit solchen großen Paketen vorher zu Pufferüberläufen gekommen ist, die zu solchen Abstürzen
führen.

Gruß Alfred

marsbewohner · Beitrag von **marsbewohner** » 25 Jun 2011, 13:08

Hallo Alfred,

danke dir für deine Ausführungen und Infos.
Bisher warte ich auf die richtige FW vom Support noch vergebens

Das mit den Paketen wäre natürlich eine Richtung, allerdings haben wir meines Wissens nichts ungewöhnliches bei uns im Einsatz, Centrino, Broadcom und Atheros für WLAN, Intel und Broadcom für LAN.

Wenn es übers Netz ist muss es aber etwas sein das über LAN kommt, das Gerät steht jetzt ca. 2 Wochen im Leerlauf ohne WLAN aktiv, nur noch LAN um es abfragen zu können, dh Last oder Traffic sollte ausser Broadcasts und die Lanmonitor Abfrage nichts ankommen. Bei Bedarf kann ich da auch noch mehr Logs liefern, der Support hat auch schon einen ganzen Batzen, aber da ist seit dem 4.6. bisher im Ticket noch nichts bei rum gekommen.
Der Ersatz L-321agn welcher den problematischen ersetzt hat läuft mit der gleichen Konfig und FW problemlos durch. Bei Bedarf könnte ich den mit den Problemen gerne auch einschicken...

Interessanterweise wurde mein WLAN Ticket zum Mac Thema geschlossen und entfernt, myLancom listet es nicht mehr, kannst du da bitte mal schauen was mit der ID 1106.1617.0750.ACAL passiert ist?

Danke & Gruß,

alf29 · Beitrag von **alf29** » 25 Jun 2011, 18:34

Moin,

Bisher warte ich auf die richtige FW vom Support noch vergebens

Melde Dich nochmal, wenn's Montag auch noch nicht geklappt hat.

Das mit den Paketen wäre natürlich eine Richtung, allerdings haben wir meines Wissens nichts ungewöhnliches bei uns im Einsatz, Centrino, Broadcom und Atheros für WLAN, Intel und Broadcom für LAN.

Es muß auch nicht zwingend etwas aus dem WLAN sein.

das Gerät steht jetzt ca. 2 Wochen im Leerlauf ohne WLAN aktiv, nur noch LAN um es abfragen zu können, dh Last oder Traffic sollte ausser Broadcasts und die Lanmonitor Abfrage nichts ankommen.

Zumindest der Absturz deutet darauf hin (ich kann's von zu Hause nicht im Detail analysieren),
daß das in einer Routine im WLAN passiert, bei der es sich um Aggregierung dreht. Und die wird
erst aktiv, wenn ein Client verbunden ist und ernsthaft Durchsatz macht.

Der Ersatz L-321agn welcher den problematischen ersetzt hat läuft mit der gleichen Konfig und FW problemlos durch. Bei Bedarf könnte ich den mit den Problemen gerne auch einschicken...

Hardware-Probleme sind für einen Software-Entwickler natürlich etwas bequemes, denn dann
kann er jemand anders die Schuld zuschieben. Über ein Jahrzehnt Erfahrung lehren jedoch, daß
bei Abstürzen meistens die Software schuld ist

Interessanterweise wurde mein WLAN Ticket zum Mac Thema geschlossen und entfernt, myLancom listet es nicht mehr, kannst du da bitte mal schauen was mit der ID 1106.1617.0750.ACAL passiert ist?

Kann ich am Montag schauen. Wie gesagt ist man der Meinung, daß die Mac-Probleme
gelöst wären, kann sein, daß es damit in Zusammenhang steht.

Gruß Alfred

marsbewohner · Beitrag von **marsbewohner** » 27 Jun 2011, 19:10

Hallo Alfred,

am Wochenende mal wieder ein Watchdog, dieses mal gleiche Serie, anderes Gerät:

[TraceStarted] 2011/06/27 19:00:06,728
Used config:
# Show commands
show bootlog

[ShowCmd] 2011/06/27 19:00:07,321
Result of command: "show bootlog "
Boot log (3219 Bytes):

****

01/01/1900 00:00:01 System boot after power on

DEVICE: LANCOM L-321agn Wireless
HW-RELEASE: B
VERSION: 8.50.0091Rel / 08.04.2011

****

06/26/2011 17:36:27 LCOS-Watchdog
Task name = WI Type=e300: Program Interrupt (IEEE floating-point enabled exception)
Code=0x00000700 Task=01a3e460/00000000 Nest=0x00000000

R00=0x006b6f64 SP =0x01a41ad0 R02=0x00b60000 R03=0x01cf2200
R04=0x0086fdb0 R05=0x0086fdb0 R06=0x000090b2 R07=0x0086c8d4
R08=0x013707e0 R09=0x00000000 R10=0x010e0000 R11=0x00000000
R12=0x42024044 R13=0x010e0a78 R14=0x00000000 R15=0x00000000
R16=0x00000000 R17=0x00000000 R18=0x00000000 R19=0x00000000
R20=0x00000000 R21=0x00000000 R22=0x00000000 R23=0x01c4d100
R24=0x00000000 R25=0x00000000 R26=0x00000000 R27=0x00645a05
R28=0x019235e0 R29=0x012616c0 R30=0x01cf2200 R31=0x00000024

CR =0x42024042 XER =0x20000000 LR =0x0086718c CTR =0x00000000
DAR =0x00000000 DSR =0x00000000 TBL =0xb715ec84 TBU =0x0000146a
IBCR=0x00e20000 DBCR=0x00e20000 DBR =0x01e4b60f DBR2=0x03ffffc7
HID0=0xc090c000 HID1=0x0c000000 HID2=0x04e40000 MBAR=0x00000000
SPR0=0x00000000 SPR1=0x01cf2200 SPR2=0x0086fdb0 SPR3=0x000010b2
SPR4=0x00000000 SPR5=0x00000000 SPR6=0x00000000 SPR7=0x00000005
TGR0=0x00aa48c0 TGR1=0x00aa4011 TGR2=0x0022a940 TGR3=0x000a90b2

SRR0(PC) =0x00000000
SRR1(MSR)=0x000890b2

Stack dump (1024 bytes):
Adr:= 01a41ad0
Len:= 00000400
01A41AD0: 01 A4 1A D8 00 00 00 25 01 A4 1B 08 00 6B 6F 64 | .......% .....kod
01A41AE0: 01 B0 E7 50 01 C4 D1 24 00 6B 6E AC 00 00 00 3C | ...P...$ .kn....<
01A41AF0: 01 0E 00 00 00 00 00 0F 01 26 16 C0 00 00 00 02 | ........ .&......
01A41B00: 00 00 00 00 00 07 4B C0 01 A4 1B 40 00 6F 94 20 | ......K. ...@.o.
01A41B10: 03 7F 00 00 42 00 00 48 00 00 00 00 00 00 00 00 | ....B..H ........
01A41B20: 00 00 00 00 00 00 00 00 00 00 00 00 00 A5 A1 D4 | ........ ........
01A41B30: 01 A4 1C E8 DE AD BE AF 00 A5 9F 4C 01 26 16 C0 | ........ ...L.&..
01A41B40: 01 A4 1B 48 00 6B 64 E8 01 A4 1C 70 00 6D D8 B0 | ...H.kd. ...p.m..
01A41B50: 00 00 00 00 01 26 2F 44 00 6D D3 A4 00 00 00 3C | .....&/D .m.....<
01A41B60: 01 0E 00 00 00 00 00 0F 00 00 00 00 00 00 00 27 | ........ .......'
01A41B70: 01 A4 1B D0 01 D5 4A 40 00 00 00 0B 00 00 05 90 | ......J@ ........
01A41B80: 01 A4 1B 88 01 D5 4A 40 01 A4 1B C8 00 6B AA 64 | ......J@ .....k.d
01A41B90: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41BA0: 00 00 00 00 01 26 2F 44 00 6D D3 A4 00 00 00 3C | .....&/D .m.....<
01A41BB0: 24 00 00 22 00 87 3B 24 00 00 00 00 00 00 00 00 | $.."..;$ ........
01A41BC0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41BD0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41BE0: 00 00 00 00 00 00 00 00 00 00 00 00 02 9D CB C8 | ........ ........
01A41BF0: 01 26 16 C0 06 E4 31 EF 00 A5 9F 4C 01 B0 C1 80 | .&....1. ...L....
01A41C00: FB C7 22 04 00 00 05 90 88 00 80 EC 00 A5 ED 4C | .."..... .......L
01A41C10: 00 00 02 A3 00 00 00 01 00 00 00 00 01 9E 09 C0 | ........ ........
01A41C20: 01 A4 1C 30 00 00 00 0B 00 00 90 B2 00 6F A9 00 | ...0.... .....o..
01A41C30: 01 A4 1C 50 00 97 6E 60 00 97 6D FC 02 9D CB C8 | ...P..n` ..m.....
01A41C40: 01 26 16 C0 06 E4 31 EF BA 2F 33 E1 01 B0 C1 80 | .&....1. ./3.....
01A41C50: 01 A4 1C 70 00 97 6D 4C 00 00 00 00 00 A5 A1 D4 | ...p..mL ........
01A41C60: 01 A4 1C E8 DE AD BE AF 00 A5 9F 4C 01 26 16 C0 | ........ ...L.&..
01A41C70: 01 A4 1C 88 00 69 FC B0 00 00 00 00 DE AD BE AF | .....i.. ........
01A41C80: 01 A4 1C 88 01 26 16 C0 01 A4 1C 90 00 7B 7B 10 | .....&.. .....{{.
01A41C90: 01 A4 1C A0 00 69 F1 E4 00 00 00 00 01 26 16 C0 | .....i.. .....&..
01A41CA0: 01 A4 1C A8 00 96 C9 84 01 A4 1C B0 00 7B 7B 10 | ........ .....{{.
01A41CB0: 01 A4 1C B8 00 96 C9 64 01 A4 1C C0 00 98 B1 48 | .......d .......H
01A41CC0: 01 A4 1C C8 00 7B 7B 10 01 A4 1C D0 00 98 C4 24 | .....{{. .......$
01A41CD0: 01 A4 1C D8 00 7B 7B 10 01 A4 1C E0 00 97 24 D0 | .....{{. ......$.
01A41CE0: 01 A4 25 10 00 6A 22 F0 49 54 48 57 55 55 55 55 | ..%..j". ITHWUUUU
01A41CF0: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41D00: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41D10: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41D20: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41D30: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41D40: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41D50: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41D60: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41D70: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41D80: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41D90: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41DA0: 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 55 | UUUUUUUU UUUUUUUU
01A41DB0: 55 55 55 55 55 55 55 55 00 00 00 00 00 00 01 01 | UUUUUUUU ........
01A41DC0: 00 06 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41DD0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41DE0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41DF0: 00 00 00 02 05 03 01 00 00 00 03 E6 00 01 00 00 | ........ ........
01A41E00: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41E10: 00 00 00 04 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41E20: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41E30: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41E40: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41E50: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41E60: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41E70: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41E80: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41E90: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41EA0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41EB0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
01A41EC0: 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 00 | ........ ........
largest available memory block: 35342816 bytes

DEVICE: LANCOM L-321agn Wireless
HW-RELEASE: B
VERSION: 8.50.0091Rel / 08.04.2011

****

06/26/2011 17:36:32 System boot after LCOS-Watchdog

DEVICE: LANCOM L-321agn Wireless
HW-RELEASE: B
VERSION: 8.50.0091Rel / 08.04.2011

Gruß,